Searched refs:rx_buf_ring (Results 1 – 9 of 9) sorted by relevance
202 tmp0 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons]); in bnxt_recv_pkts_vec()204 tmp1 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons + 2]); in bnxt_recv_pkts_vec()256 rxr->rx_buf_ring[mbcons + 3] = NULL; in bnxt_recv_pkts_vec()259 rxr->rx_buf_ring[mbcons + 2] = NULL; in bnxt_recv_pkts_vec()262 rxr->rx_buf_ring[mbcons + 1] = NULL; in bnxt_recv_pkts_vec()265 rxr->rx_buf_ring[mbcons + 0] = NULL; in bnxt_recv_pkts_vec()
211 t0 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons]); in bnxt_recv_pkts_vec()213 t1 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons + 2]); in bnxt_recv_pkts_vec()274 rxr->rx_buf_ring[mbcons + 3] = NULL; in bnxt_recv_pkts_vec()277 rxr->rx_buf_ring[mbcons + 2] = NULL; in bnxt_recv_pkts_vec()280 rxr->rx_buf_ring[mbcons + 1] = NULL; in bnxt_recv_pkts_vec()283 rxr->rx_buf_ring[mbcons + 0] = NULL; in bnxt_recv_pkts_vec()
45 struct rte_mbuf **rx_buf = &rxr->rx_buf_ring[prod]; in bnxt_alloc_rx_data()101 prod_rx_buf = &rxr->rx_buf_ring[prod]; in bnxt_reuse_rx_mbuf()122 cons_rx_buf = &rxr->rx_buf_ring[cons]; in bnxt_consume_rx_buf()926 struct rte_mbuf **rx_buf = &rxr->rx_buf_ring[i]; in bnxt_recv_pkts()1026 ring->vmem = (void **)&rxr->rx_buf_ring; in bnxt_init_rx_ring_struct()1124 if (unlikely(!rxr->rx_buf_ring[i])) { in bnxt_init_one_rx_ring()1139 rxr->rx_buf_ring[i] = &rxq->fake_mbuf; in bnxt_init_one_rx_ring()
61 struct rte_mbuf **rx_buf_ring; /* sw ring */ member
60 struct rte_mbuf **rx_bufs = &rxr->rx_buf_ring[rxq->rxrearm_start]; in bnxt_rxq_rearm()
58 prod_rx_buf = &rep_rxr->rx_buf_ring[rep_rxr->rx_prod & mask]; in bnxt_vfr_recv()91 cons_rx_buf = &rxr->rx_buf_ring[rxr->rx_cons & mask]; in bnxt_rep_rx_burst()660 rxq->rx_ring->rx_buf_ring = buf_ring; in bnxt_rep_rx_queue_setup_op()
213 sw_ring = rxq->rx_ring->rx_buf_ring; in bnxt_rx_queue_release_mbufs()
253 rx_ring_info->rx_buf_ring = in bnxt_alloc_rings()
2956 rx_buf = rxr->rx_buf_ring[cons]; in bnxt_rx_descriptor_status_op()