Home
last modified time | relevance | path

Searched refs:rx_pkts (Results 1 – 25 of 158) sorted by relevance

1234567

/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_sse.c96 struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
213 struct rte_mbuf **rx_pkts) in flex_desc_to_olflags_v() argument
306 rx_pkts[0]->hash.fdir.hi = in flex_desc_to_olflags_v()
309 rx_pkts[1]->hash.fdir.hi = in flex_desc_to_olflags_v()
312 rx_pkts[2]->hash.fdir.hi = in flex_desc_to_olflags_v()
315 rx_pkts[3]->hash.fdir.hi = in flex_desc_to_olflags_v()
641 struct rte_mbuf **rx_pkts, in _recv_raw_pkts_vec_flex_rxd() argument
1004 rx_pkts + retval, in iavf_recv_scattered_pkts_vec()
1013 rx_pkts + retval, in iavf_recv_scattered_pkts_vec()
1074 rx_pkts + retval, in iavf_recv_scattered_pkts_vec_flex_rxd()
[all …]
H A Diavf_rxtx_vec_avx2.c23 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx2() argument
191 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx2()
703 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
879 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
882 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
885 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
888 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
891 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
894 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1300 rx_pkts + retval, nb_pkts); in iavf_recv_scattered_pkts_vec_avx2()
[all …]
H A Diavf_rxtx_vec_avx512.c165 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx512() argument
284 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx512()
708 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() argument
833 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1106 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1109 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1112 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1639 (rx_queue, rx_pkts + retval, in iavf_recv_scattered_pkts_vec_avx512_flex_rxd_cmn()
1656 rx_pkts, in iavf_recv_scattered_pkts_vec_avx512_flex_rxd()
1684 rx_pkts, in iavf_recv_pkts_vec_avx512_flex_rxd_offload()
[all …]
H A Diavf_rxtx.h611 struct rte_mbuf **rx_pkts,
614 struct rte_mbuf **rx_pkts,
617 struct rte_mbuf **rx_pkts,
638 struct rte_mbuf **rx_pkts,
648 struct rte_mbuf **rx_pkts,
651 struct rte_mbuf **rx_pkts,
654 struct rte_mbuf **rx_pkts,
668 struct rte_mbuf **rx_pkts,
671 struct rte_mbuf **rx_pkts,
674 struct rte_mbuf **rx_pkts,
[all …]
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_altivec.c181 rx_pkts[0]->packet_type = in desc_to_ptype_v()
183 rx_pkts[1]->packet_type = in desc_to_ptype_v()
185 rx_pkts[2]->packet_type = in desc_to_ptype_v()
187 rx_pkts[3]->packet_type = in desc_to_ptype_v()
308 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
413 rx_pkts[pos]->next = NULL; in _recv_raw_pkts_vec()
414 rx_pkts[pos + 1]->next = NULL; in _recv_raw_pkts_vec()
415 rx_pkts[pos + 2]->next = NULL; in _recv_raw_pkts_vec()
416 rx_pkts[pos + 3]->next = NULL; in _recv_raw_pkts_vec()
515 rx_pkts + retval, in i40e_recv_scattered_pkts_vec()
[all …]
H A Di40e_rxtx_vec_neon.c322 rx_pkts[i]->packet_type = ptype_tbl[ptype]; in desc_to_ptype_v()
439 vst1q_u64((uint64_t *)&rx_pkts[pos], mbp1); in _recv_raw_pkts_vec()
443 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
444 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
544 rx_pkts[pos]->next = NULL; in _recv_raw_pkts_vec()
545 rx_pkts[pos + 1]->next = NULL; in _recv_raw_pkts_vec()
546 rx_pkts[pos + 2]->next = NULL; in _recv_raw_pkts_vec()
547 rx_pkts[pos + 3]->next = NULL; in _recv_raw_pkts_vec()
623 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec()
642 rx_pkts + retval, in i40e_recv_scattered_pkts_vec()
[all …]
H A Di40e_rxtx_vec_sse.c216 __m128i descs[4], struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
298 descs, rx_pkts); in desc_to_olflags_v()
470 _mm_storeu_si128((__m128i *)&rx_pkts[pos], mbp1); in _recv_raw_pkts_vec()
490 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
491 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
492 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _recv_raw_pkts_vec()
493 rte_mbuf_prefetch_part2(rx_pkts[pos + 3]); in _recv_raw_pkts_vec()
579 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
645 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec()
664 rx_pkts + retval, in i40e_recv_scattered_pkts_vec()
[all …]
H A Di40e_rxtx_vec_avx2.c37 struct rte_mbuf **rx_pkts, in desc_fdir_processing_32b() argument
272 _mm256_storeu_si256((void *)&rx_pkts[i], in _recv_raw_pkts_vec_avx2()
275 _mm256_storeu_si256((void *)&rx_pkts[i + 4], in _recv_raw_pkts_vec_avx2()
323 rte_mbuf_prefetch_part2(rx_pkts[i + j]); in _recv_raw_pkts_vec_avx2()
501 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 0); in _recv_raw_pkts_vec_avx2()
504 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 2); in _recv_raw_pkts_vec_avx2()
507 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 4); in _recv_raw_pkts_vec_avx2()
674 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec_avx2()
676 return i + reassemble_packets(rxq, &rx_pkts[i], nb_bufs - i, in i40e_recv_scattered_burst_vec_avx2()
693 rx_pkts + retval, RTE_I40E_VPMD_RX_BURST); in i40e_recv_scattered_pkts_vec_avx2()
[all …]
H A Di40e_rxtx_vec_avx512.c162 struct rte_mbuf **rx_pkts, in desc_fdir_processing_32b() argument
598 rx_pkts[i + 0]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
600 rx_pkts[i + 1]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
613 rx_pkts[i + 2]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
615 rx_pkts[i + 3]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
625 rx_pkts[i + 4]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
627 rx_pkts[i + 5]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
637 rx_pkts[i + 6]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
639 rx_pkts[i + 7]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
849 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec_avx512()
[all …]
/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple_sse.c40 virtio_recv_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts, in virtio_recv_pkts_vec() argument
110 ref_rx_pkts = rx_pkts; in virtio_recv_pkts_vec()
119 _mm_storeu_si128((__m128i *)&rx_pkts[0], mbp[0]); in virtio_recv_pkts_vec()
123 _mm_storeu_si128((__m128i *)&rx_pkts[2], mbp[1]); in virtio_recv_pkts_vec()
127 _mm_storeu_si128((__m128i *)&rx_pkts[4], mbp[2]); in virtio_recv_pkts_vec()
131 _mm_storeu_si128((__m128i *)&rx_pkts[6], mbp[3]); in virtio_recv_pkts_vec()
137 _mm_storeu_si128((void *)&rx_pkts[1]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
139 _mm_storeu_si128((void *)&rx_pkts[0]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
146 _mm_storeu_si128((void *)&rx_pkts[3]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
148 _mm_storeu_si128((void *)&rx_pkts[2]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_simple_altivec.c40 virtio_recv_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts, in virtio_recv_pkts_vec() argument
112 ref_rx_pkts = rx_pkts; in virtio_recv_pkts_vec()
121 *(__vector unsigned char *)&rx_pkts[0] = mbp[0]; in virtio_recv_pkts_vec()
125 *(__vector unsigned char *)&rx_pkts[2] = mbp[1]; in virtio_recv_pkts_vec()
129 *(__vector unsigned char *)&rx_pkts[4] = mbp[2]; in virtio_recv_pkts_vec()
133 *(__vector unsigned char *)&rx_pkts[6] = mbp[3]; in virtio_recv_pkts_vec()
141 *(__vector unsigned char *)&rx_pkts[0]->rx_descriptor_fields1 = in virtio_recv_pkts_vec()
143 *(__vector unsigned char *)&rx_pkts[1]->rx_descriptor_fields1 = in virtio_recv_pkts_vec()
152 *(__vector unsigned char *)&rx_pkts[2]->rx_descriptor_fields1 = in virtio_recv_pkts_vec()
154 *(__vector unsigned char *)&rx_pkts[3]->rx_descriptor_fields1 = in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_simple_neon.c40 struct rte_mbuf **__rte_restrict rx_pkts, in virtio_recv_pkts_vec() argument
110 ref_rx_pkts = rx_pkts; in virtio_recv_pkts_vec()
119 vst1q_u64((uint64_t *)&rx_pkts[0], mbp[0]); in virtio_recv_pkts_vec()
123 vst1q_u64((uint64_t *)&rx_pkts[2], mbp[1]); in virtio_recv_pkts_vec()
127 vst1q_u64((uint64_t *)&rx_pkts[4], mbp[2]); in virtio_recv_pkts_vec()
131 vst1q_u64((uint64_t *)&rx_pkts[6], mbp[3]); in virtio_recv_pkts_vec()
141 vst1q_u64((void *)&rx_pkts[1]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
143 vst1q_u64((void *)&rx_pkts[0]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
154 vst1q_u64((void *)&rx_pkts[3]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
156 vst1q_u64((void *)&rx_pkts[2]->rx_descriptor_fields1, in virtio_recv_pkts_vec()
[all …]
H A Dvirtio_rxtx_packed_neon.h164 struct rte_mbuf **rx_pkts) in virtqueue_dequeue_batch_packed_vec() argument
236 vst1q_u64((uint64_t *)&rx_pkts[0], mbp[0].val[0]); in virtqueue_dequeue_batch_packed_vec()
239 vst1q_u64((uint64_t *)&rx_pkts[2], mbp[1].val[0]); in virtqueue_dequeue_batch_packed_vec()
266 vst1q_u64((void *)&rx_pkts[0]->rx_descriptor_fields1, pkt_mb[0]); in virtqueue_dequeue_batch_packed_vec()
267 vst1q_u64((void *)&rx_pkts[1]->rx_descriptor_fields1, pkt_mb[1]); in virtqueue_dequeue_batch_packed_vec()
268 vst1q_u64((void *)&rx_pkts[2]->rx_descriptor_fields1, pkt_mb[2]); in virtqueue_dequeue_batch_packed_vec()
273 char *addr = (char *)rx_pkts[i]->buf_addr + in virtqueue_dequeue_batch_packed_vec()
275 virtio_vec_rx_offload(rx_pkts[i], in virtqueue_dequeue_batch_packed_vec()
280 virtio_update_batch_stats(&rxvq->stats, rx_pkts[0]->pkt_len, in virtqueue_dequeue_batch_packed_vec()
281 rx_pkts[1]->pkt_len, rx_pkts[2]->pkt_len, in virtqueue_dequeue_batch_packed_vec()
[all …]
H A Dvirtio_ethdev.h77 uint16_t virtio_recv_pkts(void *rx_queue, struct rte_mbuf **rx_pkts,
79 uint16_t virtio_recv_pkts_packed(void *rx_queue, struct rte_mbuf **rx_pkts,
82 uint16_t virtio_recv_mergeable_pkts(void *rx_queue, struct rte_mbuf **rx_pkts,
86 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
89 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
102 uint16_t virtio_recv_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
105 uint16_t virtio_recv_pkts_packed_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
H A Dvirtio_rxtx_packed_avx.h143 struct rte_mbuf **rx_pkts) in virtqueue_dequeue_batch_packed_vec() argument
187 rx_pkts[i] = (struct rte_mbuf *)vq->vq_descx[id + i].cookie; in virtqueue_dequeue_batch_packed_vec()
188 rte_packet_prefetch(rte_pktmbuf_mtod(rx_pkts[i], void *)); in virtqueue_dequeue_batch_packed_vec()
190 addrs[i] = (uintptr_t)rx_pkts[i]->rx_descriptor_fields1; in virtqueue_dequeue_batch_packed_vec()
219 char *addr = (char *)rx_pkts[i]->buf_addr + in virtqueue_dequeue_batch_packed_vec()
221 virtio_vec_rx_offload(rx_pkts[i], in virtqueue_dequeue_batch_packed_vec()
226 virtio_update_batch_stats(&rxvq->stats, rx_pkts[0]->pkt_len, in virtqueue_dequeue_batch_packed_vec()
227 rx_pkts[1]->pkt_len, rx_pkts[2]->pkt_len, in virtqueue_dequeue_batch_packed_vec()
228 rx_pkts[3]->pkt_len); in virtqueue_dequeue_batch_packed_vec()
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_sse.c105 struct rte_mbuf **rx_pkts) in ice_rx_desc_to_olflags_v() argument
234 rx_pkts[0]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
237 rx_pkts[1]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
240 rx_pkts[2]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
243 rx_pkts[3]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
444 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _ice_recv_raw_pkts_vec()
445 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _ice_recv_raw_pkts_vec()
446 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _ice_recv_raw_pkts_vec()
633 rxq->pkt_first_seg = rx_pkts[i]; in ice_recv_scattered_burst_vec()
652 rx_pkts + retval, in ice_recv_scattered_pkts_vec()
[all …]
H A Dice_rxtx_vec_avx2.c253 ((void *)&rx_pkts[i + 4], in _ice_recv_raw_pkts_vec_avx2()
445 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
448 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
451 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
454 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
457 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
773 struct rte_mbuf **rx_pkts, in ice_recv_scattered_pkts_vec_avx2_common() argument
793 struct rte_mbuf **rx_pkts, in ice_recv_scattered_pkts_vec_avx2() argument
797 rx_pkts, in ice_recv_scattered_pkts_vec_avx2()
804 struct rte_mbuf **rx_pkts, in ice_recv_scattered_pkts_vec_avx2_offload() argument
[all …]
H A Dice_rxtx_vec_avx512.c156 struct rte_mbuf **rx_pkts, in _ice_recv_raw_pkts_vec_avx512() argument
351 ((void *)&rx_pkts[i + 4], in _ice_recv_raw_pkts_vec_avx512()
556 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
559 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
562 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
565 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
568 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
571 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
574 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
946 rx_pkts + retval, nb_pkts); in ice_recv_scattered_pkts_vec_avx512()
[all …]
H A Dice_rxtx.h224 uint16_t ice_recv_pkts(void *rx_queue, struct rte_mbuf **rx_pkts,
254 uint16_t ice_recv_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
256 uint16_t ice_recv_scattered_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
260 uint16_t ice_recv_pkts_vec_avx2(void *rx_queue, struct rte_mbuf **rx_pkts,
262 uint16_t ice_recv_pkts_vec_avx2_offload(void *rx_queue, struct rte_mbuf **rx_pkts,
265 struct rte_mbuf **rx_pkts,
268 struct rte_mbuf **rx_pkts,
274 uint16_t ice_recv_pkts_vec_avx512(void *rx_queue, struct rte_mbuf **rx_pkts,
277 struct rte_mbuf **rx_pkts,
280 struct rte_mbuf **rx_pkts,
[all …]
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c87 struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
208 rx_pkts[0]->ol_flags = vol.e[0]; in desc_to_olflags_v()
209 rx_pkts[1]->ol_flags = vol.e[1]; in desc_to_olflags_v()
210 rx_pkts[2]->ol_flags = vol.e[2]; in desc_to_olflags_v()
236 struct rte_mbuf **rx_pkts) in desc_to_ptype_v() argument
261 rx_pkts[0]->packet_type = in desc_to_ptype_v()
265 rx_pkts[1]->packet_type = in desc_to_ptype_v()
269 rx_pkts[2]->packet_type = in desc_to_ptype_v()
273 rx_pkts[3]->packet_type = in desc_to_ptype_v()
536 rx_pkts + retval, in ixgbe_recv_scattered_pkts_vec()
[all …]
H A Dixgbe_rxtx_vec_sse.c283 struct rte_mbuf **rx_pkts) in desc_to_ptype_v() argument
313 rx_pkts[0]->packet_type = in desc_to_ptype_v()
316 rx_pkts[1]->packet_type = in desc_to_ptype_v()
319 rx_pkts[2]->packet_type = in desc_to_ptype_v()
322 rx_pkts[3]->packet_type = in desc_to_ptype_v()
493 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
494 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
517 &rx_pkts[pos]); in _recv_raw_pkts_vec()
640 rxq->pkt_first_seg = rx_pkts[i]; in ixgbe_recv_scattered_burst_vec()
659 rx_pkts + retval, in ixgbe_recv_scattered_pkts_vec()
[all …]
/dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx_vec.c133 rx_pkts[0]->ol_flags = vol.e[0]; in fm10k_desc_to_olflags_v()
134 rx_pkts[1]->ol_flags = vol.e[1]; in fm10k_desc_to_olflags_v()
135 rx_pkts[2]->ol_flags = vol.e[2]; in fm10k_desc_to_olflags_v()
136 rx_pkts[3]->ol_flags = vol.e[3]; in fm10k_desc_to_olflags_v()
197 rx_pkts[0]->packet_type = vol.e[0]; in fm10k_desc_to_pktype_v()
558 rx_pkts[pos]->next = NULL; in fm10k_recv_raw_pkts_vec()
559 rx_pkts[pos + 1]->next = NULL; in fm10k_recv_raw_pkts_vec()
560 rx_pkts[pos + 2]->next = NULL; in fm10k_recv_raw_pkts_vec()
561 rx_pkts[pos + 3]->next = NULL; in fm10k_recv_raw_pkts_vec()
705 rx_pkts + retval, in fm10k_recv_scattered_pkts_vec()
[all …]
/dpdk/drivers/net/thunderx/
H A Dnicvf_rxtx.h89 uint16_t nicvf_recv_pkts_no_offload(void *rxq, struct rte_mbuf **rx_pkts,
91 uint16_t nicvf_recv_pkts_cksum(void *rxq, struct rte_mbuf **rx_pkts,
93 uint16_t nicvf_recv_pkts_vlan_strip(void *rx_queue, struct rte_mbuf **rx_pkts,
96 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
99 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
101 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
103 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
105 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
/dpdk/drivers/net/sfc/
H A Dsfc_ef10_rx.c218 *rx_pkts++ = in sfc_ef10_rx_pending()
223 return rx_pkts; in sfc_ef10_rx_pending()
252 struct rte_mbuf **rx_pkts, in sfc_ef10_rx_process_event() argument
271 return rx_pkts; in sfc_ef10_rx_process_event()
285 return rx_pkts; in sfc_ef10_rx_process_event()
316 return rx_pkts; in sfc_ef10_rx_process_event()
356 *rx_pkts++ = m; in sfc_ef10_rx_process_event()
363 return rx_pkts; in sfc_ef10_rx_process_event()
376 *rx_pkts++ = m; in sfc_ef10_rx_process_event()
406 return rx_pkts; in sfc_ef10_rx_process_event()
[all …]
/dpdk/drivers/net/failsafe/
H A Dfailsafe_rxtx.c71 failsafe_rx_set_port(struct rte_mbuf **rx_pkts, uint16_t nb_pkts, uint16_t port) in failsafe_rx_set_port() argument
76 rx_pkts[i]->port = port; in failsafe_rx_set_port()
81 struct rte_mbuf **rx_pkts, in failsafe_rx_burst() argument
100 rx_pkt_burst(sub_rxq, rx_pkts, nb_pkts); in failsafe_rx_burst()
106 failsafe_rx_set_port(rx_pkts, nb_rx, in failsafe_rx_burst()
113 struct rte_mbuf **rx_pkts, in failsafe_rx_burst_fast() argument
128 rx_pkt_burst(sub_rxq, rx_pkts, nb_pkts); in failsafe_rx_burst_fast()
134 failsafe_rx_set_port(rx_pkts, nb_rx, in failsafe_rx_burst_fast()

1234567