Home
last modified time | relevance | path

Searched refs:sw_ring (Results 1 – 25 of 74) sorted by relevance

123

/dpdk/drivers/net/hns3/
H A Dhns3_rxtx_vec_neon.h52 tx_entry = &txq->sw_ring[next_to_use]; in hns3_xmit_fixed_burst_vec()
72 tx_entry = &txq->sw_ring[next_to_use]; in hns3_xmit_fixed_burst_vec()
94 struct hns3_entry *sw_ring, in hns3_desc_parse_field() argument
105 pkt = sw_ring[i].mbuf; in hns3_desc_parse_field()
135 struct hns3_entry *sw_ring = &rxq->sw_ring[rx_id]; in hns3_recv_burst_vec() local
184 mbp1 = vld1q_u64((uint64_t *)&sw_ring[pos]); in hns3_recv_burst_vec()
194 mbp2 = vld1q_u64((uint64_t *)&sw_ring[pos + 2]); in hns3_recv_burst_vec()
281 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
283 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
285 rte_prefetch0(sw_ring[pos + in hns3_recv_burst_vec()
[all …]
H A Dhns3_rxtx_vec.c59 struct hns3_entry *rxep = &rxq->sw_ring[rxq->rx_rearm_start]; in hns3_rxq_rearm_mbuf()
127 rte_prefetch0(rxq->sw_ring[rxq->next_to_use + 0].mbuf); in hns3_recv_pkts_vec()
128 rte_prefetch0(rxq->sw_ring[rxq->next_to_use + 1].mbuf); in hns3_recv_pkts_vec()
129 rte_prefetch0(rxq->sw_ring[rxq->next_to_use + 2].mbuf); in hns3_recv_pkts_vec()
130 rte_prefetch0(rxq->sw_ring[rxq->next_to_use + 3].mbuf); in hns3_recv_pkts_vec()
199 struct hns3_entry *sw_ring = &rxq->sw_ring[rxq->nb_rx_desc]; in hns3_rxq_vec_setup() local
207 sw_ring[i].mbuf = &rxq->fake_mbuf; in hns3_rxq_vec_setup()
H A Dhns3_rxtx_vec_sve.c66 hns3_rx_prefetch_mbuf_sve(struct hns3_entry *sw_ring) in hns3_rx_prefetch_mbuf_sve() argument
68 svuint64_t prf1st = svld1_u64(PG64_256BIT, (uint64_t *)&sw_ring[0]); in hns3_rx_prefetch_mbuf_sve()
69 svuint64_t prf2st = svld1_u64(PG64_256BIT, (uint64_t *)&sw_ring[4]); in hns3_rx_prefetch_mbuf_sve()
84 struct hns3_entry *sw_ring = &rxq->sw_ring[rx_id]; in hns3_recv_burst_vec_sve() local
143 mbp1st = svld1_u64(PG64_256BIT, (uint64_t *)&sw_ring[pos]); in hns3_recv_burst_vec_sve()
154 mbp2st = svld1_u64(PG64_256BIT, (uint64_t *)&sw_ring[pos + 4]); in hns3_recv_burst_vec_sve()
224 hns3_rx_prefetch_mbuf_sve(&sw_ring[pos + in hns3_recv_burst_vec_sve()
244 struct hns3_entry *rxep = &rxq->sw_ring[rxq->rx_rearm_start]; in hns3_rxq_rearm_mbuf_sve()
309 hns3_rx_prefetch_mbuf_sve(&rxq->sw_ring[rxq->next_to_use]); in hns3_recv_pkts_vec_sve()
387 struct hns3_entry *tx_entry = &txq->sw_ring[txq->next_to_use]; in hns3_tx_fill_hw_ring_sve()
/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple_sse.c49 struct rte_mbuf **sw_ring; in virtio_recv_pkts_vec() local
104 sw_ring = &vq->sw_ring[desc_idx]; in virtio_recv_pkts_vec()
105 sw_ring_end = &vq->sw_ring[vq->vq_nentries]; in virtio_recv_pkts_vec()
117 mbp[0] = _mm_loadu_si128((__m128i *)(sw_ring + 0)); in virtio_recv_pkts_vec()
121 mbp[1] = _mm_loadu_si128((__m128i *)(sw_ring + 2)); in virtio_recv_pkts_vec()
125 mbp[2] = _mm_loadu_si128((__m128i *)(sw_ring + 4)); in virtio_recv_pkts_vec()
129 mbp[3] = _mm_loadu_si128((__m128i *)(sw_ring + 6)); in virtio_recv_pkts_vec()
170 if (sw_ring + nb_used <= sw_ring_end) in virtio_recv_pkts_vec()
173 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
178 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_simple_altivec.c49 struct rte_mbuf **sw_ring; in virtio_recv_pkts_vec() local
106 sw_ring = &vq->sw_ring[desc_idx]; in virtio_recv_pkts_vec()
107 sw_ring_end = &vq->sw_ring[vq->vq_nentries]; in virtio_recv_pkts_vec()
119 mbp[0] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 0)); in virtio_recv_pkts_vec()
123 mbp[1] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 2)); in virtio_recv_pkts_vec()
127 mbp[2] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 4)); in virtio_recv_pkts_vec()
180 if (sw_ring + nb_used <= sw_ring_end) in virtio_recv_pkts_vec()
183 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
186 if (unlikely(sw_ring + RTE_VIRTIO_DESC_PER_LOOP >= in virtio_recv_pkts_vec()
188 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_simple_neon.c49 struct rte_mbuf **sw_ring; in virtio_recv_pkts_vec() local
104 sw_ring = &vq->sw_ring[desc_idx]; in virtio_recv_pkts_vec()
105 sw_ring_end = &vq->sw_ring[vq->vq_nentries]; in virtio_recv_pkts_vec()
117 mbp[0] = vld1q_u64((uint64_t *)(sw_ring + 0)); in virtio_recv_pkts_vec()
121 mbp[1] = vld1q_u64((uint64_t *)(sw_ring + 2)); in virtio_recv_pkts_vec()
125 mbp[2] = vld1q_u64((uint64_t *)(sw_ring + 4)); in virtio_recv_pkts_vec()
129 mbp[3] = vld1q_u64((uint64_t *)(sw_ring + 6)); in virtio_recv_pkts_vec()
186 if (sw_ring + nb_used <= sw_ring_end) in virtio_recv_pkts_vec()
189 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
194 nb_pkts_received += sw_ring_end - sw_ring; in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_simple.h23 struct rte_mbuf **sw_ring; in virtio_rxq_rearm_vec() local
29 sw_ring = &vq->sw_ring[desc_idx]; in virtio_rxq_rearm_vec()
32 ret = rte_mempool_get_bulk(rxvq->mpool, (void **)sw_ring, in virtio_rxq_rearm_vec()
43 p = (uintptr_t)&sw_ring[i]->rearm_data; in virtio_rxq_rearm_vec()
46 start_dp[i].addr = VIRTIO_MBUF_ADDR(sw_ring[i], vq) + in virtio_rxq_rearm_vec()
48 start_dp[i].len = sw_ring[i]->buf_len - in virtio_rxq_rearm_vec()
/dpdk/drivers/net/bnx2x/
H A Dbnx2x_rxtx.c23 struct rte_mbuf **sw_ring; in bnx2x_rx_queue_release() local
27 sw_ring = rx_queue->sw_ring; in bnx2x_rx_queue_release()
28 if (NULL != sw_ring) { in bnx2x_rx_queue_release()
30 rte_pktmbuf_free(sw_ring[i]); in bnx2x_rx_queue_release()
32 rte_free(sw_ring); in bnx2x_rx_queue_release()
113 if (NULL == rxq->sw_ring) { in bnx2x_dev_rx_queue_setup()
128 rxq->sw_ring[idx] = mbuf; in bnx2x_dev_rx_queue_setup()
167 struct rte_mbuf **sw_ring; in bnx2x_tx_queue_release() local
171 sw_ring = tx_queue->sw_ring; in bnx2x_tx_queue_release()
172 if (NULL != sw_ring) { in bnx2x_tx_queue_release()
[all …]
/dpdk/drivers/net/sfc/
H A Dsfc_tso.c20 sfc_efx_tso_alloc_tsoh_objs(struct sfc_efx_tx_sw_desc *sw_ring, in sfc_efx_tso_alloc_tsoh_objs() argument
26 sw_ring[i].tsoh = rte_malloc_socket("sfc-efx-txq-tsoh-obj", in sfc_efx_tso_alloc_tsoh_objs()
30 if (sw_ring[i].tsoh == NULL) in sfc_efx_tso_alloc_tsoh_objs()
38 rte_free(sw_ring[--i].tsoh); in sfc_efx_tso_alloc_tsoh_objs()
44 sfc_efx_tso_free_tsoh_objs(struct sfc_efx_tx_sw_desc *sw_ring, in sfc_efx_tso_free_tsoh_objs() argument
50 rte_free(sw_ring[i].tsoh); in sfc_efx_tso_free_tsoh_objs()
51 sw_ring[i].tsoh = NULL; in sfc_efx_tso_free_tsoh_objs()
128 tsoh = txq->sw_ring[idx & txq->ptr_mask].tsoh; in sfc_efx_tso_do()
H A Dsfc_ef10_rx.c70 struct sfc_ef10_rx_sw_desc *sw_ring; member
154 rxd = &rxq->sw_ring[id]; in sfc_ef10_rx_qrefill()
184 rte_prefetch0(&rxq->sw_ring[next_id]); in sfc_ef10_rx_prefetch_next()
191 next_mbuf = rxq->sw_ring[next_id].mbuf; in sfc_ef10_rx_prefetch_next()
297 rxd = &rxq->sw_ring[pending++ & ptr_mask]; in sfc_ef10_rx_process_event()
319 rxd = &rxq->sw_ring[pending++ & ptr_mask]; in sfc_ef10_rx_process_event()
369 rxd = &rxq->sw_ring[pending++ & ptr_mask]; in sfc_ef10_rx_process_event()
669 sizeof(*rxq->sw_ring), in sfc_ef10_rx_qcreate()
671 if (rxq->sw_ring == NULL) in sfc_ef10_rx_qcreate()
714 rte_free(rxq->sw_ring); in sfc_ef10_rx_qdestroy()
[all …]
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_common.h152 if (unlikely(!rxq->sw_ring)) { in _ice_rx_queue_release_mbufs_vec()
163 if (rxq->sw_ring[i].mbuf) in _ice_rx_queue_release_mbufs_vec()
164 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _ice_rx_queue_release_mbufs_vec()
170 if (rxq->sw_ring[i].mbuf) in _ice_rx_queue_release_mbufs_vec()
171 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _ice_rx_queue_release_mbufs_vec()
178 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc); in _ice_rx_queue_release_mbufs_vec()
186 if (unlikely(!txq || !txq->sw_ring)) { in _ice_tx_queue_release_mbufs_vec()
220 rte_pktmbuf_free_seg(txq->sw_ring[i].mbuf); in _ice_tx_queue_release_mbufs_vec()
221 txq->sw_ring[i].mbuf = NULL; in _ice_tx_queue_release_mbufs_vec()
226 rte_pktmbuf_free_seg(txq->sw_ring[i].mbuf); in _ice_tx_queue_release_mbufs_vec()
[all …]
/dpdk/drivers/net/igc/
H A Digc_txrx.c353 struct igc_rx_entry * const sw_ring = rxq->sw_ring; in igc_recv_pkts() local
424 rxe = &sw_ring[rx_id]; in igc_recv_pkts()
497 struct igc_rx_entry * const sw_ring = rxq->sw_ring; in igc_recv_scattered_pkts() local
568 rxe = &sw_ring[rx_id]; in igc_recv_scattered_pkts()
702 if (rxq->sw_ring != NULL) { in igc_rx_queue_release_mbufs()
716 rte_free(rxq->sw_ring); in igc_rx_queue_release()
1385 if (rxq->sw_ring == NULL) { in eth_igc_rx_queue_setup()
1611 struct igc_tx_entry * const sw_ring = txq->sw_ring; in igc_xmit_pkts() local
1632 txe = &sw_ring[tx_id]; in igc_xmit_pkts()
1880 rte_free(txq->sw_ring); in igc_tx_queue_release()
[all …]
/dpdk/drivers/net/atlantic/
H A Datl_rxtx.c56 struct atl_rx_entry *sw_ring; member
74 struct atl_tx_entry *sw_ring; member
158 if (rxq->sw_ring == NULL) { in atl_rx_queue_setup()
179 rte_free(rxq->sw_ring); in atl_rx_queue_setup()
206 tx_entry = txq->sw_ring; in atl_reset_tx_queue()
273 if (txq->sw_ring == NULL) { in atl_tx_queue_setup()
293 rte_free(txq->sw_ring); in atl_tx_queue_setup()
509 rte_free(rxq->sw_ring); in atl_rx_queue_release()
580 rte_free(txq->sw_ring); in atl_tx_queue_release()
921 struct atl_rx_entry *sw_ring = rxq->sw_ring; in atl_recv_pkts() local
[all …]
/dpdk/drivers/net/e1000/
H A Dem_rxtx.c299 struct em_tx_entry *sw_ring = txq->sw_ring; in em_xmit_cleanup() local
370 struct em_tx_entry *sw_ring; in eth_em_xmit_pkts() local
391 sw_ring = txq->sw_ring; in eth_em_xmit_pkts()
394 txe = &sw_ring[tx_id]; in eth_em_xmit_pkts()
702 sw_ring = rxq->sw_ring; in eth_em_recv_pkts()
761 rxe = &sw_ring[rx_id]; in eth_em_recv_pkts()
878 sw_ring = rxq->sw_ring; in eth_em_recv_scattered_pkts()
940 rxe = &sw_ring[rx_id]; in eth_em_recv_scattered_pkts()
1104 if (txq->sw_ring != NULL) { in em_tx_queue_release_mbufs()
1119 rte_free(txq->sw_ring); in em_tx_queue_release()
[all …]
H A Digb_rxtx.c405 sw_ring = txq->sw_ring; in eth_igb_xmit_pkts()
408 txe = &sw_ring[tx_id]; in eth_igb_xmit_pkts()
830 sw_ring = rxq->sw_ring; in eth_igb_recv_pkts()
888 rxe = &sw_ring[rx_id]; in eth_igb_recv_pkts()
1017 sw_ring = rxq->sw_ring; in eth_igb_recv_scattered_pkts()
1079 rxe = &sw_ring[rx_id]; in eth_igb_recv_scattered_pkts()
1264 if (txq->sw_ring != NULL) { in igb_tx_queue_release_mbufs()
1279 rte_free(txq->sw_ring); in igb_tx_queue_release()
1305 sw_ring = txq->sw_ring; in igb_tx_done_cleanup()
1348 sw_ring[tx_id].mbuf); in igb_tx_done_cleanup()
[all …]
/dpdk/drivers/net/axgbe/
H A Daxgbe_rxtx.c19 struct rte_mbuf **sw_ring; in axgbe_rx_queue_release() local
22 sw_ring = rx_queue->sw_ring; in axgbe_rx_queue_release()
23 if (sw_ring) { in axgbe_rx_queue_release()
25 rte_pktmbuf_free(sw_ring[i]); in axgbe_rx_queue_release()
27 rte_free(sw_ring); in axgbe_rx_queue_release()
106 if (!rxq->sw_ring) { in axgbe_dev_rx_queue_setup()
246 mbuf = rxq->sw_ring[idx]; in axgbe_recv_pkts()
506 sw_ring = tx_queue->sw_ring; in axgbe_tx_queue_release()
507 if (sw_ring) { in axgbe_tx_queue_release()
511 rte_free(sw_ring); in axgbe_tx_queue_release()
[all …]
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_common.h149 if (txq->sw_ring == NULL || txq->nb_tx_free == max_desc) in _ixgbe_tx_queue_release_mbufs_vec()
173 if (rxq->sw_ring == NULL || rxq->rxrearm_nb >= rxq->nb_rx_desc) in _ixgbe_rx_queue_release_mbufs_vec()
179 if (rxq->sw_ring[i].mbuf != NULL) in _ixgbe_rx_queue_release_mbufs_vec()
180 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _ixgbe_rx_queue_release_mbufs_vec()
186 if (rxq->sw_ring[i].mbuf != NULL) in _ixgbe_rx_queue_release_mbufs_vec()
187 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _ixgbe_rx_queue_release_mbufs_vec()
194 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc); in _ixgbe_rx_queue_release_mbufs_vec()
203 if (txq->sw_ring != NULL) { in _ixgbe_tx_free_swring_vec()
/dpdk/drivers/net/bnxt/
H A Dbnxt_txq.c57 struct rte_mbuf **sw_ring; in bnxt_tx_queue_release_mbufs() local
63 sw_ring = txq->tx_ring->tx_buf_ring; in bnxt_tx_queue_release_mbufs()
64 if (sw_ring) { in bnxt_tx_queue_release_mbufs()
66 if (sw_ring[i]) { in bnxt_tx_queue_release_mbufs()
67 rte_pktmbuf_free_seg(sw_ring[i]); in bnxt_tx_queue_release_mbufs()
68 sw_ring[i] = NULL; in bnxt_tx_queue_release_mbufs()
H A Dbnxt_rxq.c202 struct rte_mbuf **sw_ring; in bnxt_rx_queue_release_mbufs() local
209 sw_ring = rxq->rx_ring->rx_buf_ring; in bnxt_rx_queue_release_mbufs()
210 if (sw_ring) { in bnxt_rx_queue_release_mbufs()
223 if (sw_ring[i]) { in bnxt_rx_queue_release_mbufs()
224 if (sw_ring[i] != &rxq->fake_mbuf) in bnxt_rx_queue_release_mbufs()
226 sw_ring[i] = NULL; in bnxt_rx_queue_release_mbufs()
236 sw_ring = rxq->rx_ring->ag_buf_ring; in bnxt_rx_queue_release_mbufs()
237 if (sw_ring) { in bnxt_rx_queue_release_mbufs()
240 if (sw_ring[i]) { in bnxt_rx_queue_release_mbufs()
241 rte_pktmbuf_free_seg(sw_ring[i]); in bnxt_rx_queue_release_mbufs()
[all …]
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_common.h101 txep = &txq->sw_ring[txq->tx_next_dd - (n - 1)]; in i40e_tx_free_bufs()
165 if (rxq->sw_ring == NULL || rxq->rxrearm_nb >= rxq->nb_rx_desc) in _i40e_rx_queue_release_mbufs_vec()
171 if (rxq->sw_ring[i].mbuf != NULL) in _i40e_rx_queue_release_mbufs_vec()
172 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _i40e_rx_queue_release_mbufs_vec()
178 if (rxq->sw_ring[i].mbuf != NULL) in _i40e_rx_queue_release_mbufs_vec()
179 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf); in _i40e_rx_queue_release_mbufs_vec()
186 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc); in _i40e_rx_queue_release_mbufs_vec()
H A Di40e_rxtx.c375 struct i40e_tx_entry *sw_ring = txq->sw_ring; in i40e_xmit_cleanup() local
727 sw_ring = rxq->sw_ring; in i40e_recv_pkts()
838 struct i40e_rx_entry *sw_ring = rxq->sw_ring; in i40e_recv_scattered_pkts() local
1099 sw_ring = txq->sw_ring; in i40e_xmit_pkts()
2048 rxq->sw_ring = in i40e_dev_rx_queue_setup()
2053 if (!rxq->sw_ring) { in i40e_dev_rx_queue_setup()
2129 rte_free(q->sw_ring); in i40e_rx_queue_release()
2435 txq->sw_ring = in i40e_dev_tx_queue_setup()
2440 if (!txq->sw_ring) { in i40e_dev_tx_queue_setup()
2520 if (!rxq->sw_ring) { in i40e_rx_queue_release_mbufs()
[all …]
/dpdk/drivers/raw/ntb/
H A Dntb.c277 if (!q || !q->sw_ring) { in ntb_rxq_release_mbufs()
300 rte_free(rxq->sw_ring); in ntb_rxq_release()
339 rxq->sw_ring = in ntb_rxq_setup()
345 if (!rxq->sw_ring) { in ntb_rxq_setup()
362 if (!q || !q->sw_ring) { in ntb_txq_release_mbufs()
385 rte_free(txq->sw_ring); in ntb_txq_release()
420 txq->sw_ring = in ntb_txq_setup()
426 if (!txq->sw_ring) { in ntb_txq_setup()
581 struct ntb_tx_entry *sw_ring = txq->sw_ring; in ntb_enqueue_cleanup() local
607 struct ntb_tx_entry *sw_ring = txq->sw_ring; in ntb_enqueue_bufs() local
[all …]
/dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx.c115 mbuf = q->sw_ring[next_dd]; in fm10k_recv_pkts()
152 rte_prefetch0(q->sw_ring[next_dd]); in fm10k_recv_pkts()
161 rte_prefetch0(&q->sw_ring[next_dd]); in fm10k_recv_pkts()
169 (void **)&q->sw_ring[q->next_alloc], in fm10k_recv_pkts()
186 mbuf = q->sw_ring[q->next_alloc]; in fm10k_recv_pkts()
229 mbuf = q->sw_ring[next_dd]; in fm10k_recv_scattered_pkts()
241 rte_prefetch0(q->sw_ring[next_dd]); in fm10k_recv_scattered_pkts()
250 rte_prefetch0(&q->sw_ring[next_dd]); in fm10k_recv_scattered_pkts()
344 mbuf = q->sw_ring[q->next_alloc]; in fm10k_recv_scattered_pkts()
591 q->sw_ring[q->next_free] = mb; in tx_xmit_pkt()
[all …]
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_common.h102 txep = &txq->sw_ring[txq->next_dd - (n - 1)]; in iavf_tx_free_bufs()
155 if (!rxq->sw_ring || rxq->rxrearm_nb >= rxq->nb_rx_desc) in _iavf_rx_queue_release_mbufs_vec()
161 if (rxq->sw_ring[i]) in _iavf_rx_queue_release_mbufs_vec()
162 rte_pktmbuf_free_seg(rxq->sw_ring[i]); in _iavf_rx_queue_release_mbufs_vec()
168 if (rxq->sw_ring[i]) in _iavf_rx_queue_release_mbufs_vec()
169 rte_pktmbuf_free_seg(rxq->sw_ring[i]); in _iavf_rx_queue_release_mbufs_vec()
176 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc); in _iavf_rx_queue_release_mbufs_vec()
185 if (!txq->sw_ring || txq->nb_free == max_desc) in _iavf_tx_queue_release_mbufs_vec()
191 rte_pktmbuf_free_seg(txq->sw_ring[i].mbuf); in _iavf_tx_queue_release_mbufs_vec()
192 txq->sw_ring[i].mbuf = NULL; in _iavf_tx_queue_release_mbufs_vec()
[all …]
/dpdk/drivers/net/ngbe/
H A Dngbe_rxtx.c512 struct ngbe_tx_entry *sw_ring = txq->sw_ring; in ngbe_xmit_cleanup() local
599 sw_ring = txq->sw_ring; in ngbe_xmit_pkts()
602 txe = &sw_ring[tx_id]; in ngbe_xmit_pkts()
1258 sw_ring = rxq->sw_ring; in ngbe_recv_pkts()
1318 rxe = &sw_ring[rx_id]; in ngbe_recv_pkts()
1470 struct ngbe_rx_entry *sw_ring = rxq->sw_ring; in ngbe_recv_pkts_sc() local
1535 rxe = &sw_ring[rx_id]; in ngbe_recv_pkts_sc()
1706 if (txq->sw_ring != NULL) { in ngbe_tx_queue_release_mbufs()
1809 rte_free(txq->sw_ring); in ngbe_tx_free_swring()
2050 if (txq->sw_ring == NULL) { in ngbe_dev_tx_queue_setup()
[all …]

123