d/numam-dpdk
1
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity

event/cnxk: fix mbuf offset calculation

Browse Source 
Fix incorrect mbuf offset calculation when HEADROOM exceeds 128B
while processing event vectors.

Fixes: 7fbbc981d5 ("event/cnxk: support vectorized Rx event fast path")
Cc: stable@dpdk.org

Signed-off-by: Pavan Nikhilesh <pbhagavatula@marvell.com>
This commit is contained in:
Pavan Nikhilesh 2022-10-25 21:41:29 +05:30 committed by Jerin Jacob
parent 4109d71e52
commit 9b70a944b4
1 changed files with 5 additions and 3 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

8
drivers/net/cnxk/cn10k_rx.h
View File

@ -1203,9 +1203,11 @@ cn10k_nix_recv_pkts_vector(void *args, struct rte_mbuf **mbufs, uint16_t pkts,
mbuf23 = vqsubq_u64(mbuf23, data_off);
} else {
mbuf01 =
vsubq_u64(vld1q_u64((uint64_t *)cq0), data_off);
mbuf23 = vsubq_u64(vld1q_u64((uint64_t *)(cq0 + 16)),
data_off);
vsubq_u64(vld1q_u64((uint64_t *)cq0),
vdupq_n_u64(sizeof(struct rte_mbuf)));
mbuf23 =
vsubq_u64(vld1q_u64((uint64_t *)(cq0 + 16)),
vdupq_n_u64(sizeof(struct rte_mbuf)));
}
/* Move mbufs to scalar registers for future use */