Home
last modified time | relevance | path

Searched refs:rxr (Results 1 – 9 of 9) sorted by relevance

/f-stack/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c97 uint16_t prod = RING_NEXT(rxr->rx_ring_struct, rxr->rx_prod); in bnxt_reuse_rx_mbuf()
112 rxr->rx_prod = prod; in bnxt_reuse_rx_mbuf()
179 bnxt_reuse_rx_mbuf(rxr, bnxt_consume_rx_buf(rxr, data_cons)); in bnxt_tpa_start()
201 uint16_t next = RING_NEXT(rxr->ag_ring_struct, rxr->ag_prod); in bnxt_prod_ag_mbuf()
211 rxr->ag_prod = next; in bnxt_prod_ag_mbuf()
854 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_recv_pkts()
898 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_recv_pkts()
911 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_recv_pkts()
915 bnxt_db_write(&rxr->ag_db, rxr->ag_prod); in bnxt_recv_pkts()
935 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_recv_pkts()
[all …]
H A Dbnxt_ring.c518 rxr->rx_prod = 0; in bnxt_alloc_rx_ring()
522 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_alloc_rx_ring()
554 rxr->ag_prod = 0; in bnxt_alloc_rx_agg_ring()
558 bnxt_db_write(&rxr->ag_db, rxr->ag_prod); in bnxt_alloc_rx_agg_ring()
608 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_alloc_hwrm_rx_ring()
609 bnxt_db_write(&rxr->ag_db, rxr->ag_prod); in bnxt_alloc_hwrm_rx_ring()
643 rxr = rxq->rx_ring; in bnxt_init_all_rings()
644 ring = rxr->rx_ring_struct; in bnxt_init_all_rings()
647 ring = rxr->ag_ring_struct; in bnxt_init_all_rings()
714 bnxt_db_write(&rxr->rx_db, rxr->rx_prod); in bnxt_alloc_hwrm_rings()
[all …]
H A Dbnxt_rxtx_vec_sse.c148 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in bnxt_recv_pkts_vec() local
150 uint16_t rx_ring_size = rxr->rx_ring_struct->ring_size; in bnxt_recv_pkts_vec()
166 bnxt_rxq_rearm(rxq, rxr); in bnxt_recv_pkts_vec()
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()
280 rxr->rx_prod = in bnxt_recv_pkts_vec()
[all …]
H A Dbnxt_rxtx_vec_neon.c155 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in bnxt_recv_pkts_vec() local
157 uint16_t rx_ring_size = rxr->rx_ring_struct->ring_size; in bnxt_recv_pkts_vec()
174 bnxt_rxq_rearm(rxq, rxr); 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()
298 rxr->rx_prod = in bnxt_recv_pkts_vec()
[all …]
H A Dbnxt_rxtx_vec_common.h57 bnxt_rxq_rearm(struct bnxt_rx_queue *rxq, struct bnxt_rx_ring_info *rxr) in bnxt_rxq_rearm() argument
59 struct rx_prod_pkt_bd *rxbds = &rxr->rx_desc_ring[rxq->rxrearm_start]; in bnxt_rxq_rearm()
60 struct rte_mbuf **rx_bufs = &rxr->rx_buf_ring[rxq->rxrearm_start]; in bnxt_rxq_rearm()
91 bnxt_db_write(&rxr->rx_db, rxq->rxrearm_start - 1); in bnxt_rxq_rearm()
H A Dbnxt_reps.c81 struct bnxt_rx_ring_info *rxr; in bnxt_rep_rx_burst() local
88 rxr = rxq->rx_ring; in bnxt_rep_rx_burst()
89 mask = rxr->rx_ring_struct->ring_mask; in bnxt_rep_rx_burst()
91 cons_rx_buf = &rxr->rx_buf_ring[rxr->rx_cons & mask]; in bnxt_rep_rx_burst()
98 rxr->rx_cons++; in bnxt_rep_rx_burst()
566 struct bnxt_rx_ring_info *rxr; in bnxt_init_rep_rx_ring() local
569 rxr = rte_zmalloc_socket("bnxt_rep_rx_ring", in bnxt_init_rep_rx_ring()
572 if (rxr == NULL) in bnxt_init_rep_rx_ring()
574 rxq->rx_ring = rxr; in bnxt_init_rep_rx_ring()
581 rxr->rx_ring_struct = ring; in bnxt_init_rep_rx_ring()
H A Dbnxt_hwrm.c1931 struct bnxt_rx_ring_info *rxr; in bnxt_hwrm_vnic_cfg() local
1951 rxr = rxq->rx_ring; in bnxt_hwrm_vnic_cfg()
1955 rte_cpu_to_le_16(rxr->rx_ring_struct->fw_ring_id); in bnxt_hwrm_vnic_cfg()
2553 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in bnxt_free_hwrm_rx_ring() local
2554 struct bnxt_ring *ring = rxr->rx_ring_struct; in bnxt_free_hwrm_rx_ring()
2565 ring = rxr->ag_ring_struct; in bnxt_free_hwrm_rx_ring()
4832 struct bnxt_rx_ring_info *rxr; in bnxt_vnic_rss_configure_thor() local
4870 rxr = rxqs[k]->rx_ring; in bnxt_vnic_rss_configure_thor()
4873 ring_id = rxr->rx_ring_struct->fw_ring_id; in bnxt_vnic_rss_configure_thor()
H A Dbnxt_ethdev.c2925 struct bnxt_rx_ring_info *rxr; in bnxt_rx_descriptor_status_op() local
2940 rxr = rxq->rx_ring; in bnxt_rx_descriptor_status_op()
2956 rx_buf = rxr->rx_buf_ring[cons]; in bnxt_rx_descriptor_status_op()
/f-stack/dpdk/drivers/net/enetc/
H A Denetc_ethdev.c247 rte_free(rxr->q_swbd); in enetc_free_bdr()
248 rte_free(rxr->bd_base); in enetc_free_bdr()
249 rxr->q_swbd = NULL; in enetc_free_bdr()
250 rxr->bd_base = NULL; in enetc_free_bdr()
373 if (rxr->q_swbd == NULL) in enetc_alloc_rxbdr()
378 if (rxr->bd_base == NULL) { in enetc_alloc_rxbdr()
379 rte_free(rxr->q_swbd); in enetc_alloc_rxbdr()
380 rxr->q_swbd = NULL; in enetc_alloc_rxbdr()
385 rxr->next_to_clean = 0; in enetc_alloc_rxbdr()
386 rxr->next_to_use = 0; in enetc_alloc_rxbdr()
[all …]