Home
last modified time | relevance | path

Searched refs:mbcons (Results 1 – 3 of 3) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_sse.c165 uint32_t cons, mbcons; in recv_burst_vec_sse() local
179 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_sse()
186 nb_pkts = RTE_MIN(nb_pkts, RTE_MIN(rx_ring_size - mbcons, in recv_burst_vec_sse()
205 mbcons += BNXT_RX_DESCS_PER_LOOP_VEC128) { in recv_burst_vec_sse()
212 tmp0 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons]); in recv_burst_vec_sse()
214 tmp1 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons + 2]); in recv_burst_vec_sse()
H A Dbnxt_rxtx_vec_neon.c173 uint32_t cons, mbcons; in recv_burst_vec_neon() local
188 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_neon()
195 nb_pkts = RTE_MIN(nb_pkts, RTE_MIN(rx_ring_size - mbcons, in recv_burst_vec_neon()
214 mbcons += BNXT_RX_DESCS_PER_LOOP_VEC128) { in recv_burst_vec_neon()
222 t0 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons]); in recv_burst_vec_neon()
223 t1 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons + 2]); in recv_burst_vec_neon()
H A Dbnxt_rxtx_vec_avx2.c36 uint32_t cons, mbcons; in recv_burst_vec_avx2() local
93 mbcons = (raw_cons / 2) & (rx_ring_size - 1); in recv_burst_vec_avx2()
100 nb_pkts = RTE_MIN(nb_pkts, RTE_MIN(rx_ring_size - mbcons, in recv_burst_vec_avx2()
119 mbcons += BNXT_RX_DESCS_PER_LOOP_VEC256) { in recv_burst_vec_avx2()
126 t0 = _mm256_loadu_si256((void *)&rxr->rx_buf_ring[mbcons]); in recv_burst_vec_avx2()
129 t0 = _mm256_loadu_si256((void *)&rxr->rx_buf_ring[mbcons + 4]); in recv_burst_vec_avx2()