Home
last modified time | relevance | path

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

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c128 cons_rx_buf = &rxr->rx_buf_ring[RING_IDX(rxr->rx_ring_struct, cons)]; in bnxt_consume_rx_buf()
152 if (rxr->tpa_info) in bnxt_rx_ring_reset()
165 bnxt_db_write(&rxr->rx_db, rxr->rx_raw_prod); in bnxt_rx_ring_reset()
166 bnxt_db_write(&rxr->ag_db, rxr->ag_raw_prod); in bnxt_rx_ring_reset()
167 if (rxr->tpa_info) in bnxt_rx_ring_reset()
285 bnxt_reuse_rx_mbuf(rxr, bnxt_consume_rx_buf(rxr, data_cons)); in bnxt_tpa_start()
287 rxr->rx_next_cons = RING_IDX(rxr->rx_ring_struct, in bnxt_tpa_start()
1052 bnxt_db_write(&rxr->rx_db, rxr->rx_raw_prod); in bnxt_recv_pkts()
1113 bnxt_db_write(&rxr->rx_db, rxr->rx_raw_prod); in bnxt_recv_pkts()
1117 bnxt_db_write(&rxr->ag_db, rxr->ag_raw_prod); in bnxt_recv_pkts()
[all …]
H A Dbnxt_ring.c537 rxr->rx_raw_prod = 0; in bnxt_alloc_rx_ring()
542 bnxt_db_write(&rxr->rx_db, rxr->rx_raw_prod); in bnxt_alloc_rx_ring()
577 rxr->ag_raw_prod = 0; in bnxt_alloc_rx_agg_ring()
582 bnxt_db_write(&rxr->ag_db, rxr->ag_raw_prod); in bnxt_alloc_rx_agg_ring()
657 bnxt_db_write(&rxr->rx_db, rxr->rx_raw_prod); in bnxt_alloc_hwrm_rx_ring()
659 bnxt_db_write(&rxr->ag_db, rxr->ag_raw_prod); in bnxt_alloc_hwrm_rx_ring()
684 struct bnxt_rx_ring_info *rxr; in bnxt_init_all_rings() local
693 rxr = rxq->rx_ring; in bnxt_init_all_rings()
694 ring = rxr->rx_ring_struct; in bnxt_init_all_rings()
698 ring = rxr->ag_ring_struct; in bnxt_init_all_rings()
[all …]
H A Dbnxt_rxtx_vec_sse.c30 rxr->ol_flags_table[_mm_extract_epi32((ol_index), (pi))]; \
34 of |= rxr->ol_flags_err_table[tmp]; \
58 struct bnxt_rx_ring_info *rxr) in descs_to_mbufs() argument
158 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in recv_burst_vec_sse() local
160 uint16_t rx_ring_size = rxr->rx_ring_struct->ring_size; in recv_burst_vec_sse()
176 bnxt_rxq_rearm(rxq, rxr); 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()
268 rxr); in recv_burst_vec_sse()
276 rxr->rx_raw_prod = RING_ADV(rxr->rx_raw_prod, nb_rx_pkts); in recv_burst_vec_sse()
H A Dbnxt_rxtx_vec_neon.c30 rxr->ol_flags_table[vgetq_lane_u32((ol_idx), (pi))]; \
34 of |= rxr->ol_flags_err_table[tmp]; \
62 struct bnxt_rx_ring_info *rxr) in descs_to_mbufs() argument
166 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in recv_burst_vec_neon() local
168 uint16_t rx_ring_size = rxr->rx_ring_struct->ring_size; in recv_burst_vec_neon()
185 bnxt_rxq_rearm(rxq, rxr); 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()
296 rxr); in recv_burst_vec_neon()
304 rxr->rx_raw_prod = RING_ADV(rxr->rx_raw_prod, nb_rx_pkts); in recv_burst_vec_neon()
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_rxtx_vec_avx2.c29 struct bnxt_rx_ring_info *rxr = rxq->rx_ring; in recv_burst_vec_avx2() local
31 uint16_t rx_ring_size = rxr->rx_ring_struct->ring_size; in recv_burst_vec_avx2()
88 bnxt_rxq_rearm(rxq, rxr); 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()
244 ol_flags = _mm256_i32gather_epi32((int *)rxr->ol_flags_table, in recv_burst_vec_avx2()
246 errors = _mm256_i32gather_epi32((int *)rxr->ol_flags_err_table, in recv_burst_vec_avx2()
354 rxr->rx_raw_prod = RING_ADV(rxr->rx_raw_prod, nb_rx_pkts); in recv_burst_vec_avx2()
H A Dbnxt_reps.c85 struct bnxt_rx_ring_info *rxr; in bnxt_rep_rx_burst() local
92 rxr = rxq->rx_ring; in bnxt_rep_rx_burst()
93 mask = rxr->rx_ring_struct->ring_mask; in bnxt_rep_rx_burst()
95 cons_rx_buf = &rxr->rx_buf_ring[rxr->rx_cons & mask]; in bnxt_rep_rx_burst()
102 rxr->rx_cons++; in bnxt_rep_rx_burst()
597 struct bnxt_rx_ring_info *rxr; in bnxt_init_rep_rx_ring() local
600 rxr = rte_zmalloc_socket("bnxt_rep_rx_ring", in bnxt_init_rep_rx_ring()
603 if (rxr == NULL) in bnxt_init_rep_rx_ring()
605 rxq->rx_ring = rxr; in bnxt_init_rep_rx_ring()
612 rxr->rx_ring_struct = ring; in bnxt_init_rep_rx_ring()
H A Dbnxt_hwrm.c2110 struct bnxt_rx_ring_info *rxr; in bnxt_hwrm_vnic_cfg() local
2130 rxr = rxq->rx_ring; in bnxt_hwrm_vnic_cfg()
2134 rte_cpu_to_le_16(rxr->rx_ring_struct->fw_ring_id); in bnxt_hwrm_vnic_cfg()
2704 struct bnxt_rx_ring_info *rxr = rxq ? rxq->rx_ring : NULL; in bnxt_free_hwrm_rx_ring() local
2705 struct bnxt_ring *ring = rxr ? rxr->rx_ring_struct : NULL; in bnxt_free_hwrm_rx_ring()
2724 (rxr && rxr->ag_ring_struct == NULL)) in bnxt_free_hwrm_rx_ring()
2727 ring = rxr ? rxr->ag_ring_struct : NULL; in bnxt_free_hwrm_rx_ring()
5114 struct bnxt_rx_ring_info *rxr; in bnxt_vnic_rss_configure_p5() local
5151 rxr = rxqs[k]->rx_ring; in bnxt_vnic_rss_configure_p5()
5154 ring_id = rxr->rx_ring_struct->fw_ring_id; in bnxt_vnic_rss_configure_p5()
H A Dbnxt_ethdev.c3211 struct bnxt_rx_ring_info *rxr; in bnxt_rx_descriptor_status_op() local
3224 rxr = rxq->rx_ring; in bnxt_rx_descriptor_status_op()
3247 cons = RING_CMP(rxr->rx_ring_struct, raw_cons / 2); in bnxt_rx_descriptor_status_op()
3279 if (rxr->rx_buf_ring[cons]) in bnxt_rx_descriptor_status_op()
/dpdk/drivers/net/enetc/
H A Denetc_ethdev.c261 rte_free(rxr->q_swbd); in enetc_free_bdr()
262 rte_free(rxr->bd_base); in enetc_free_bdr()
263 rxr->q_swbd = NULL; in enetc_free_bdr()
264 rxr->bd_base = NULL; in enetc_free_bdr()
389 if (rxr->q_swbd == NULL) in enetc_alloc_rxbdr()
394 if (rxr->bd_base == NULL) { in enetc_alloc_rxbdr()
395 rte_free(rxr->q_swbd); in enetc_alloc_rxbdr()
396 rxr->q_swbd = NULL; in enetc_alloc_rxbdr()
401 rxr->next_to_clean = 0; in enetc_alloc_rxbdr()
402 rxr->next_to_use = 0; in enetc_alloc_rxbdr()
[all …]