| /f-stack/dpdk/drivers/net/iavf/ |
| H A D | iavf_rxtx_vec_sse.c | 96 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()
639 struct rte_mbuf **rx_pkts, in _recv_raw_pkts_vec_flex_rxd() argument
1001 rx_pkts + retval, in iavf_recv_scattered_pkts_vec()
1010 rx_pkts + retval, in iavf_recv_scattered_pkts_vec()
1071 rx_pkts + retval, in iavf_recv_scattered_pkts_vec_flex_rxd()
[all …]
|
| H A D | iavf_rxtx_vec_avx2.c | 139 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx2() argument
307 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx2()
804 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
969 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
972 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
975 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
978 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
981 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
984 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1312 rx_pkts + retval, nb_pkts); in iavf_recv_scattered_pkts_vec_avx2()
[all …]
|
| H A D | iavf_rxtx_vec_avx512.c | 146 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx512() argument
327 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx512()
638 struct rte_mbuf **rx_pkts, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd() argument
820 ((void *)&rx_pkts[i + 4], in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
979 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
982 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
985 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
988 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1327 rx_pkts + retval, nb_pkts); in iavf_recv_scattered_pkts_vec_avx512()
1389 (rx_queue, rx_pkts + retval, in iavf_recv_scattered_pkts_vec_avx512_flex_rxd()
[all …]
|
| H A D | iavf_rxtx.h | 417 struct rte_mbuf **rx_pkts,
420 struct rte_mbuf **rx_pkts,
423 struct rte_mbuf **rx_pkts,
444 struct rte_mbuf **rx_pkts,
447 struct rte_mbuf **rx_pkts,
454 struct rte_mbuf **rx_pkts,
457 struct rte_mbuf **rx_pkts,
460 struct rte_mbuf **rx_pkts,
473 struct rte_mbuf **rx_pkts,
476 struct rte_mbuf **rx_pkts,
[all …]
|
| /f-stack/dpdk/drivers/net/virtio/ |
| H A D | virtio_rxtx_simple_neon.c | 40 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 D | virtio_rxtx_simple_sse.c | 40 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 D | virtio_rxtx_simple_altivec.c | 40 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 D | virtio_ethdev.h | 80 uint16_t virtio_recv_pkts(void *rx_queue, struct rte_mbuf **rx_pkts,
82 uint16_t virtio_recv_pkts_packed(void *rx_queue, struct rte_mbuf **rx_pkts,
85 uint16_t virtio_recv_mergeable_pkts(void *rx_queue, struct rte_mbuf **rx_pkts,
89 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
92 struct rte_mbuf **rx_pkts, uint16_t nb_pkts);
105 uint16_t virtio_recv_pkts_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
108 uint16_t virtio_recv_pkts_packed_vec(void *rx_queue, struct rte_mbuf **rx_pkts,
|
| H A D | virtio_rxtx_packed_avx.c | 359 struct rte_mbuf **rx_pkts) in virtqueue_dequeue_batch_packed_vec() argument
406 addrs[i] = (uintptr_t)rx_pkts[i]->rx_descriptor_fields1; in virtqueue_dequeue_batch_packed_vec()
435 char *addr = (char *)rx_pkts[i]->buf_addr + in virtqueue_dequeue_batch_packed_vec()
437 virtio_vec_rx_offload(rx_pkts[i], in virtqueue_dequeue_batch_packed_vec()
443 rx_pkts[1]->pkt_len, rx_pkts[2]->pkt_len, in virtqueue_dequeue_batch_packed_vec()
444 rx_pkts[3]->pkt_len); in virtqueue_dequeue_batch_packed_vec()
459 struct rte_mbuf **rx_pkts) in virtqueue_dequeue_single_packed_vec() argument
496 *rx_pkts = cookie; in virtqueue_dequeue_single_packed_vec()
567 struct rte_mbuf **rx_pkts, in virtio_recv_pkts_packed_vec() argument
586 &rx_pkts[nb_rx])) { in virtio_recv_pkts_packed_vec()
[all …]
|
| /f-stack/dpdk/drivers/net/i40e/ |
| H A D | i40e_rxtx_vec_altivec.c | 181 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 D | i40e_rxtx_vec_neon.c | 82 struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
185 rx_pkts[i]->packet_type = ptype_tbl[ptype]; in desc_to_ptype_v()
290 vst1q_u64((uint64_t *)&rx_pkts[pos], mbp1); in _recv_raw_pkts_vec()
304 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
390 rx_pkts[pos]->next = NULL; in _recv_raw_pkts_vec()
391 rx_pkts[pos + 1]->next = NULL; in _recv_raw_pkts_vec()
392 rx_pkts[pos + 2]->next = NULL; in _recv_raw_pkts_vec()
393 rx_pkts[pos + 3]->next = NULL; in _recv_raw_pkts_vec()
477 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec()
496 rx_pkts + retval, in i40e_recv_scattered_pkts_vec()
[all …]
|
| H A D | i40e_rxtx_vec_sse.c | 216 __m128i descs[4], struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
296 descs, rx_pkts); in desc_to_olflags_v()
468 _mm_storeu_si128((__m128i *)&rx_pkts[pos], mbp1); in _recv_raw_pkts_vec()
488 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
489 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
490 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _recv_raw_pkts_vec()
491 rte_mbuf_prefetch_part2(rx_pkts[pos + 3]); in _recv_raw_pkts_vec()
577 desc_to_ptype_v(descs, &rx_pkts[pos], ptype_tbl); in _recv_raw_pkts_vec()
643 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec()
662 rx_pkts + retval, in i40e_recv_scattered_pkts_vec()
[all …]
|
| H A D | i40e_rxtx_vec_avx2.c | 149 struct rte_mbuf **rx_pkts, in desc_fdir_processing_32b() argument
376 _mm256_storeu_si256((void *)&rx_pkts[i], in _recv_raw_pkts_vec_avx2()
379 _mm256_storeu_si256((void *)&rx_pkts[i + 4], in _recv_raw_pkts_vec_avx2()
427 rte_mbuf_prefetch_part2(rx_pkts[i + j]); in _recv_raw_pkts_vec_avx2()
605 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 0); in _recv_raw_pkts_vec_avx2()
608 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 2); in _recv_raw_pkts_vec_avx2()
611 fdir_add_flags = desc_fdir_processing_32b(rxdp, rx_pkts, i, 4); in _recv_raw_pkts_vec_avx2()
778 rxq->pkt_first_seg = rx_pkts[i]; in i40e_recv_scattered_burst_vec_avx2()
780 return i + reassemble_packets(rxq, &rx_pkts[i], nb_bufs - i, in i40e_recv_scattered_burst_vec_avx2()
797 rx_pkts + retval, RTE_I40E_VPMD_RX_BURST); in i40e_recv_scattered_pkts_vec_avx2()
[all …]
|
| /f-stack/dpdk/drivers/net/ixgbe/ |
| H A D | ixgbe_rxtx_vec_sse.c | 135 struct rte_mbuf **rx_pkts) in desc_to_olflags_v() argument
262 struct rte_mbuf **rx_pkts) in desc_to_ptype_v() argument
292 rx_pkts[0]->packet_type = in desc_to_ptype_v()
295 rx_pkts[1]->packet_type = in desc_to_ptype_v()
298 rx_pkts[2]->packet_type = in desc_to_ptype_v()
301 rx_pkts[3]->packet_type = in desc_to_ptype_v()
457 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _recv_raw_pkts_vec()
458 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _recv_raw_pkts_vec()
603 rxq->pkt_first_seg = rx_pkts[i]; in ixgbe_recv_scattered_burst_vec()
622 rx_pkts + retval, in ixgbe_recv_scattered_pkts_vec()
[all …]
|
| H A D | ixgbe_rxtx_vec_neon.c | 127 rx_pkts[0]->ol_flags = vol.e[0]; in desc_to_olflags_v()
128 rx_pkts[1]->ol_flags = vol.e[1]; in desc_to_olflags_v()
129 rx_pkts[2]->ol_flags = vol.e[2]; in desc_to_olflags_v()
155 struct rte_mbuf **rx_pkts) in desc_to_ptype_v() argument
180 rx_pkts[0]->packet_type = in desc_to_ptype_v()
184 rx_pkts[1]->packet_type = in desc_to_ptype_v()
188 rx_pkts[2]->packet_type = in desc_to_ptype_v()
192 rx_pkts[3]->packet_type = in desc_to_ptype_v()
315 &rx_pkts[pos]); in _recv_raw_pkts_vec()
448 rx_pkts + retval, in ixgbe_recv_scattered_pkts_vec()
[all …]
|
| /f-stack/dpdk/drivers/net/ice/ |
| H A D | ice_rxtx_vec_sse.c | 105 struct rte_mbuf **rx_pkts) in ice_rx_desc_to_olflags_v() argument
198 rx_pkts[0]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
201 rx_pkts[1]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
204 rx_pkts[2]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
207 rx_pkts[3]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
408 rte_mbuf_prefetch_part2(rx_pkts[pos]); in _ice_recv_raw_pkts_vec()
409 rte_mbuf_prefetch_part2(rx_pkts[pos + 1]); in _ice_recv_raw_pkts_vec()
410 rte_mbuf_prefetch_part2(rx_pkts[pos + 2]); in _ice_recv_raw_pkts_vec()
597 rxq->pkt_first_seg = rx_pkts[i]; in ice_recv_scattered_burst_vec()
616 rx_pkts + retval, in ice_recv_scattered_pkts_vec()
[all …]
|
| H A D | ice_rxtx_vec_avx2.c | 322 ((void *)&rx_pkts[i + 4], in _ice_recv_raw_pkts_vec_avx2()
501 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
504 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
507 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
510 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
513 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
516 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
519 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
522 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
804 rxq->pkt_first_seg = rx_pkts[i]; in ice_recv_scattered_burst_vec_avx2()
[all …]
|
| H A D | ice_rxtx_vec_avx512.c | 152 struct rte_mbuf **rx_pkts, in _ice_recv_raw_pkts_vec_avx512() argument
299 ((void *)&rx_pkts[i + 4], in _ice_recv_raw_pkts_vec_avx512()
484 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
487 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
490 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
493 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
496 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
499 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
502 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
505 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
[all …]
|
| /f-stack/dpdk/drivers/net/fm10k/ |
| H A D | fm10k_rxtx_vec.c | 132 rx_pkts[0]->ol_flags = vol.e[0]; in fm10k_desc_to_olflags_v()
133 rx_pkts[1]->ol_flags = vol.e[1]; in fm10k_desc_to_olflags_v()
134 rx_pkts[2]->ol_flags = vol.e[2]; in fm10k_desc_to_olflags_v()
135 rx_pkts[3]->ol_flags = vol.e[3]; in fm10k_desc_to_olflags_v()
196 rx_pkts[0]->packet_type = vol.e[0]; in fm10k_desc_to_pktype_v()
557 rx_pkts[pos]->next = NULL; in fm10k_recv_raw_pkts_vec()
558 rx_pkts[pos + 1]->next = NULL; in fm10k_recv_raw_pkts_vec()
559 rx_pkts[pos + 2]->next = NULL; in fm10k_recv_raw_pkts_vec()
560 rx_pkts[pos + 3]->next = NULL; in fm10k_recv_raw_pkts_vec()
704 rx_pkts + retval, in fm10k_recv_scattered_pkts_vec()
[all …]
|
| /f-stack/dpdk/drivers/net/thunderx/ |
| H A D | nicvf_rxtx.h | 89 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);
|
| H A D | nicvf_rxtx.c | 468 rx_pkts[i] = pkt; in nicvf_recv_pkts()
491 return nicvf_recv_pkts(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_no_offload()
499 return nicvf_recv_pkts(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_cksum()
507 return nicvf_recv_pkts(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_vlan_strip()
515 return nicvf_recv_pkts(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_cksum_vlan_strip()
599 rx_pkts + i, rbptr_offset, mbuf_init, flag); in nicvf_recv_pkts_multiseg()
602 nicvf_prefetch_store_keep(rx_pkts[i]); in nicvf_recv_pkts_multiseg()
623 return nicvf_recv_pkts_multiseg(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_multiseg_no_offload()
631 return nicvf_recv_pkts_multiseg(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_multiseg_cksum()
639 return nicvf_recv_pkts_multiseg(rx_queue, rx_pkts, nb_pkts, in nicvf_recv_pkts_multiseg_vlan_strip()
[all …]
|
| /f-stack/dpdk/drivers/net/failsafe/ |
| H A D | failsafe_rxtx.c | 71 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()
|
| /f-stack/dpdk/drivers/net/sfc/ |
| H A D | sfc_ef10_rx.c | 218 *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 …]
|
| /f-stack/dpdk/drivers/net/hns3/ |
| H A D | hns3_rxtx_vec.h | 67 hns3_rx_reassemble_pkts(struct rte_mbuf **rx_pkts, in hns3_rx_reassemble_pkts() argument
78 rte_pktmbuf_free_seg(rx_pkts[i]); in hns3_rx_reassemble_pkts()
80 rx_pkts[count++] = rx_pkts[i]; in hns3_rx_reassemble_pkts()
|
| /f-stack/dpdk/drivers/net/octeontx2/ |
| H A D | otx2_rx.c | 45 nix_recv_pkts(void *rx_queue, struct rte_mbuf **rx_pkts, in nix_recv_pkts() argument
74 rx_pkts[packets++] = mbuf; in nix_recv_pkts()
114 nix_recv_pkts_vector(void *rx_queue, struct rte_mbuf **rx_pkts, in nix_recv_pkts_vector() argument
283 vst1q_u64((uint64_t *)&rx_pkts[packets], mbuf01); in nix_recv_pkts_vector()
284 vst1q_u64((uint64_t *)&rx_pkts[packets + 2], mbuf23); in nix_recv_pkts_vector()
311 packets += nix_recv_pkts(rx_queue, &rx_pkts[packets], in nix_recv_pkts_vector()
324 RTE_SET_USED(rx_pkts); in nix_recv_pkts_vector()
336 struct rte_mbuf **rx_pkts, uint16_t pkts) \
343 struct rte_mbuf **rx_pkts, uint16_t pkts) \
345 return nix_recv_pkts(rx_queue, rx_pkts, pkts, \
[all …]
|