Searched refs:sw_ring (Results 1 - 25 of 29) sorted by relevance

12

/deb_dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple.h52 struct rte_mbuf **sw_ring; local
58 sw_ring = &vq->sw_ring[desc_idx];
61 ret = rte_mempool_get_bulk(rxvq->mpool, (void **)sw_ring,
72 p = (uintptr_t)&sw_ring[i]->rearm_data;
76 VIRTIO_MBUF_ADDR(sw_ring[i], vq) +
78 start_dp[i].len = sw_ring[i]->buf_len -
H A Dvirtio_rxtx_simple_neon.c78 struct rte_mbuf **sw_ring; local
124 sw_ring = &vq->sw_ring[desc_idx];
125 sw_ring_end = &vq->sw_ring[vq->vq_nentries];
141 mbp[0] = vld1q_u64((uint64_t *)(sw_ring + 0));
145 mbp[1] = vld1q_u64((uint64_t *)(sw_ring + 2));
149 mbp[2] = vld1q_u64((uint64_t *)(sw_ring + 4));
153 mbp[3] = vld1q_u64((uint64_t *)(sw_ring + 6));
210 if (sw_ring + nb_used <= sw_ring_end)
213 nb_pkts_received += sw_ring_end - sw_ring;
[all...]
H A Dvirtio_rxtx_simple_sse.c80 struct rte_mbuf **sw_ring; local
127 sw_ring = &vq->sw_ring[desc_idx];
128 sw_ring_end = &vq->sw_ring[vq->vq_nentries];
144 mbp[0] = _mm_loadu_si128((__m128i *)(sw_ring + 0));
148 mbp[1] = _mm_loadu_si128((__m128i *)(sw_ring + 2));
152 mbp[2] = _mm_loadu_si128((__m128i *)(sw_ring + 4));
156 mbp[3] = _mm_loadu_si128((__m128i *)(sw_ring + 6));
197 if (sw_ring + nb_used <= sw_ring_end)
200 nb_pkts_received += sw_ring_end - sw_ring;
[all...]
H A Dvirtqueue.c80 cookie = vq->sw_ring[idx];
82 vq->sw_ring[idx] = NULL;
115 rte_pktmbuf_free(vq->sw_ring[desc_idx]);
H A Dvirtio_ethdev.c344 void *sw_ring = NULL; local
444 sizeof(vq->sw_ring[0]);
446 sw_ring = rte_zmalloc_socket("sw_ring", sz_sw,
448 if (!sw_ring) {
454 vq->sw_ring = sw_ring;
521 rte_free(sw_ring);
547 rte_free(vq->sw_ring);
/deb_dpdk/drivers/net/bnxt/
H A Dbnxt_txq.c58 struct bnxt_sw_tx_bd *sw_ring; local
61 sw_ring = txq->tx_ring->tx_buf_ring;
62 if (sw_ring) {
64 if (sw_ring[i].mbuf) {
65 rte_pktmbuf_free(sw_ring[i].mbuf);
66 sw_ring[i].mbuf = NULL;
H A Dbnxt_rxq.c218 struct bnxt_sw_rx_bd *sw_ring; local
222 sw_ring = rxq->rx_ring->rx_buf_ring;
223 if (sw_ring) {
226 if (sw_ring[i].mbuf) {
227 rte_pktmbuf_free_seg(sw_ring[i].mbuf);
228 sw_ring[i].mbuf = NULL;
/deb_dpdk/drivers/net/bnx2x/
H A Dbnx2x_rxtx.c36 struct rte_mbuf **sw_ring; local
40 sw_ring = rx_queue->sw_ring;
41 if (NULL != sw_ring) {
43 if (NULL != sw_ring[i])
44 rte_pktmbuf_free(sw_ring[i]);
46 rte_free(sw_ring);
124 rxq->sw_ring = rte_zmalloc_socket("sw_ring", dma_size,
127 if (NULL == rxq->sw_ring) {
180 struct rte_mbuf **sw_ring; local
[all...]
H A Dbnx2x_rxtx.h33 struct rte_mbuf **sw_ring; /**< address of RX software ring. */ member in struct:bnx2x_rx_queue
55 struct rte_mbuf **sw_ring; /**< virtual address of SW ring. */ member in struct:bnx2x_tx_queue
/deb_dpdk/drivers/net/e1000/
H A Dem_rxtx.c105 struct em_rx_entry *sw_ring; /**< address of RX software ring. */ member in struct:em_rx_queue
164 struct em_tx_entry *sw_ring; /**< virtual address of SW ring. */ member in struct:em_tx_queue
308 struct em_tx_entry *sw_ring = txq->sw_ring; local
321 desc_to_clean_to = sw_ring[desc_to_clean_to].last_id;
379 struct em_tx_entry *sw_ring; local
400 sw_ring = txq->sw_ring;
403 txe = &sw_ring[tx_id];
534 txn = &sw_ring[tx
656 struct em_rx_entry *sw_ring; local
830 struct em_rx_entry *sw_ring; local
[all...]
H A Digb_rxtx.c110 struct igb_rx_entry *sw_ring; /**< address of RX software ring. */ member in struct:igb_rx_queue
179 struct igb_tx_entry *sw_ring; /**< virtual address of SW ring. */ member in struct:igb_tx_queue
388 struct igb_tx_entry *sw_ring; local
410 sw_ring = txq->sw_ring;
413 txe = &sw_ring[tx_id];
490 tx_end = sw_ring[tx_last].last_id;
496 tx_end = sw_ring[tx_end].next_id;
501 tx_end = sw_ring[tx_end].last_id;
552 txn = &sw_ring[tx
770 struct igb_rx_entry *sw_ring; local
947 struct igb_rx_entry *sw_ring; local
[all...]
/deb_dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_common.h126 txep = &txq->sw_ring[txq->tx_next_dd - (n - 1)];
179 if (rxq->sw_ring == NULL || rxq->rxrearm_nb >= rxq->nb_rx_desc)
185 if (rxq->sw_ring[i].mbuf != NULL)
186 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf);
192 if (rxq->sw_ring[i].mbuf != NULL)
193 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf);
200 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc);
H A Di40e_rxtx.c355 struct i40e_tx_entry *sw_ring = txq->sw_ring; local
366 desc_to_clean_to = sw_ring[desc_to_clean_to].last_id;
455 rxep = &rxq->sw_ring[rxq->rx_tail];
526 rxq->sw_ring[rxq->rx_tail + i].mbuf = NULL;
563 rxep = &(rxq->sw_ring[alloc_idx]);
630 rxq->sw_ring[j].mbuf = rxq->rx_stage[i];
686 struct i40e_rx_entry *sw_ring; local
704 sw_ring = rxq->sw_ring;
808 struct i40e_rx_entry *sw_ring = rxq->sw_ring; local
1029 struct i40e_tx_entry *sw_ring; local
[all...]
H A Di40e_rxtx_vec_neon.c55 struct i40e_rx_entry *rxep = &rxq->sw_ring[rxq->rxrearm_start];
223 struct i40e_rx_entry *sw_ring; local
282 sw_ring = &rxq->sw_ring[rxq->rx_tail];
306 mbp1 = vld1q_u64((uint64_t *)&sw_ring[pos]);
316 mbp2 = vld1q_u64((uint64_t *)&sw_ring[pos + 2]);
554 txep = &txq->sw_ring[tx_id];
574 txep = &txq->sw_ring[tx_id];
H A Di40e_rxtx_vec_sse.c56 struct i40e_rx_entry *rxep = &rxq->sw_ring[rxq->rxrearm_start];
246 struct i40e_rx_entry *sw_ring; local
307 sw_ring = &rxq->sw_ring[rxq->rx_tail];
330 mbp1 = _mm_loadu_si128((__m128i *)&sw_ring[pos]);
341 mbp2 = _mm_loadu_si128((__m128i *)&sw_ring[pos+2]);
570 txep = &txq->sw_ring[tx_id];
590 txep = &txq->sw_ring[tx_id];
H A Di40e_rxtx_vec_altivec.c56 struct i40e_rx_entry *rxep = &rxq->sw_ring[rxq->rxrearm_start];
240 struct i40e_rx_entry *sw_ring; local
303 sw_ring = &rxq->sw_ring[rxq->rx_tail];
324 mbp1 = *(vector unsigned long *)&sw_ring[pos];
334 mbp2 = *(vector unsigned long *)&sw_ring[pos + 2];
589 txep = &txq->sw_ring[tx_id];
609 txep = &txq->sw_ring[tx_id];
/deb_dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_common.h178 if (txq->sw_ring == NULL || txq->nb_tx_free == max_desc)
181 /* release the used mbufs in sw_ring */
203 if (rxq->sw_ring == NULL || rxq->rxrearm_nb >= rxq->nb_rx_desc)
209 if (rxq->sw_ring[i].mbuf != NULL)
210 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf);
216 if (rxq->sw_ring[i].mbuf != NULL)
217 rte_pktmbuf_free_seg(rxq->sw_ring[i].mbuf);
224 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_rx_desc);
233 if (txq->sw_ring !
[all...]
H A Dixgbe_rxtx_vec_neon.c52 struct ixgbe_rx_entry *rxep = &rxq->sw_ring[rxq->rxrearm_start];
196 struct ixgbe_rx_entry *sw_ring; local
240 sw_ring = &rxq->sw_ring[rxq->rx_tail];
261 mbp1 = vld1q_u64((uint64_t *)&sw_ring[pos]);
267 mbp2 = vld1q_u64((uint64_t *)&sw_ring[pos + 2]);
H A Dixgbe_rxtx.h124 struct ixgbe_rx_entry *sw_ring; /**< address of RX software ring. */ member in struct:ixgbe_rx_queue
213 struct ixgbe_tx_entry *sw_ring; /**< address of SW ring for scalar PMD. */ member in union:ixgbe_tx_queue::__anon367
H A Dixgbe_rxtx_vec_sse.c54 struct ixgbe_rx_entry *rxep = &rxq->sw_ring[rxq->rxrearm_start];
258 struct ixgbe_rx_entry *sw_ring; local
319 sw_ring = &rxq->sw_ring[rxq->rx_tail];
345 mbp1 = _mm_loadu_si128((__m128i *)&sw_ring[pos]);
357 mbp2 = _mm_loadu_si128((__m128i *)&sw_ring[pos+2]);
H A Dixgbe_rxtx.c134 txep = &(txq->sw_ring[txq->tx_next_dd - (txq->tx_rs_thresh - 1)]);
219 struct ixgbe_tx_entry *txep = &(txq->sw_ring[txq->tx_tail]);
541 struct ixgbe_tx_entry *sw_ring = txq->sw_ring; local
555 desc_to_clean_to = sw_ring[desc_to_clean_to].last_id;
602 struct ixgbe_tx_entry *sw_ring; local
626 sw_ring = txq->sw_ring;
629 txe = &sw_ring[tx_id];
811 txn = &sw_ring[tx
1639 struct ixgbe_rx_entry *sw_ring; local
1913 struct ixgbe_rx_entry *sw_ring = rxq->sw_ring; local
[all...]
/deb_dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx.c133 mbuf = q->sw_ring[next_dd];
170 rte_prefetch0(q->sw_ring[next_dd]);
179 rte_prefetch0(&q->sw_ring[next_dd]);
187 (void **)&q->sw_ring[q->next_alloc],
204 mbuf = q->sw_ring[q->next_alloc];
247 mbuf = q->sw_ring[next_dd];
259 rte_prefetch0(q->sw_ring[next_dd]);
268 rte_prefetch0(&q->sw_ring[next_dd]);
345 (void **)&q->sw_ring[q->next_alloc],
362 mbuf = q->sw_ring[
[all...]
H A Dfm10k_rxtx_vec.c288 struct rte_mbuf **mb_alloc = &rxq->sw_ring[rxq->rxrearm_start];
386 if (rxq->sw_ring == NULL || rxq->rxrearm_nb >= rxq->nb_desc)
391 rte_pktmbuf_free_seg(rxq->sw_ring[i]);
395 memset(rxq->sw_ring, 0, sizeof(rxq->sw_ring[0]) * rxq->nb_desc);
458 mbufp = &rxq->sw_ring[next_dd];
764 txep = &txq->sw_ring[txq->next_dd - (n - 1)];
834 txep = &txq->sw_ring[tx_id];
854 txep = &txq->sw_ring[tx_id];
878 struct rte_mbuf **txe = txq->sw_ring;
[all...]
H A Dfm10k_ethdev.c223 diag = rte_mempool_get_bulk(q->mp, (void **)q->sw_ring, q->nb_desc);
228 fm10k_pktmbuf_reset(q->sw_ring[i], q->port_id);
229 if (!fm10k_addr_alignment_valid(q->sw_ring[i])) {
230 rte_mempool_put_bulk(q->mp, (void **)q->sw_ring,
234 dma_addr = MBUF_DMA_ADDR_DEFAULT(q->sw_ring[i]);
244 q->sw_ring[q->nb_desc + i] = &q->fake_mbuf;
285 if (q->sw_ring[i]) {
286 rte_pktmbuf_free_seg(q->sw_ring[i]);
287 q->sw_ring[i] = NULL;
302 if (q->sw_ring) {
[all...]
H A Dfm10k.h183 struct rte_mbuf **sw_ring; member in struct:fm10k_rx_queue
224 struct rte_mbuf **sw_ring; member in struct:fm10k_tx_queue

Completed in 29 milliseconds

12