Searched refs:rx_buf_ring (Results 1 – 10 of 10) sorted by relevance
49 rx_buf = &rxr->rx_buf_ring[prod]; in bnxt_alloc_rx_data()107 prod_rx_buf = &rxr->rx_buf_ring[prod]; in bnxt_reuse_rx_mbuf()128 cons_rx_buf = &rxr->rx_buf_ring[RING_IDX(rxr->rx_ring_struct, cons)]; in bnxt_consume_rx_buf()1129 rx_buf = &rxr->rx_buf_ring[ndx]; in bnxt_recv_pkts()1221 ring->vmem = (void **)&rxr->rx_buf_ring; in bnxt_init_rx_ring_struct()1321 if (unlikely(!rxr->rx_buf_ring[i])) { in bnxt_init_one_rx_ring()1336 rxr->rx_buf_ring[i] = &rxq->fake_mbuf; in bnxt_init_one_rx_ring()
62 prod_rx_buf = &rep_rxr->rx_buf_ring[rep_rxr->rx_raw_prod & mask]; in bnxt_vfr_recv()95 cons_rx_buf = &rxr->rx_buf_ring[rxr->rx_cons & mask]; in bnxt_rep_rx_burst()406 sw_ring = rxq->rx_ring->rx_buf_ring; in bnxt_vfr_rx_queue_release_mbufs()693 rxq->rx_ring->rx_buf_ring = buf_ring; in bnxt_rep_rx_queue_setup_op()
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()
60 struct rte_mbuf **rx_bufs = &rxr->rx_buf_ring[rxq->rxrearm_start]; in bnxt_rxq_rearm()
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()
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()
80 struct rte_mbuf **rx_buf_ring; /* sw ring */ member
209 sw_ring = rxq->rx_ring->rx_buf_ring; in bnxt_rx_queue_release_mbufs()
257 rx_ring_info->rx_buf_ring = in bnxt_alloc_rings()
3279 if (rxr->rx_buf_ring[cons]) in bnxt_rx_descriptor_status_op()