Home
last modified time | relevance | path

Searched refs:rearm_data (Results 1 – 25 of 45) sorted by relevance

12

/dpdk/drivers/net/hns3/
H A Dhns3_rxtx_vec.c174 offsetof(struct rte_mbuf, rearm_data)); in hns3_rxq_vec_setup_rearm_data()
176 offsetof(struct rte_mbuf, rearm_data)); in hns3_rxq_vec_setup_rearm_data()
178 offsetof(struct rte_mbuf, rearm_data)); in hns3_rxq_vec_setup_rearm_data()
180 offsetof(struct rte_mbuf, rearm_data)); in hns3_rxq_vec_setup_rearm_data()
182 offsetof(struct rte_mbuf, rearm_data) > 6); in hns3_rxq_vec_setup_rearm_data()
184 offsetof(struct rte_mbuf, rearm_data) > 6); in hns3_rxq_vec_setup_rearm_data()
186 offsetof(struct rte_mbuf, rearm_data) > 6); in hns3_rxq_vec_setup_rearm_data()
188 offsetof(struct rte_mbuf, rearm_data) > 6); in hns3_rxq_vec_setup_rearm_data()
192 p = (uintptr_t)&mb_def.rearm_data; in hns3_rxq_vec_setup_rearm_data()
H A Dhns3_rxtx_vec_neon.h230 *(uint64_t *)&sw_ring[pos + 0].mbuf->rearm_data = in hns3_recv_burst_vec()
232 *(uint64_t *)&sw_ring[pos + 1].mbuf->rearm_data = in hns3_recv_burst_vec()
263 *(uint64_t *)&sw_ring[pos + 2].mbuf->rearm_data = in hns3_recv_burst_vec()
265 *(uint64_t *)&sw_ring[pos + 3].mbuf->rearm_data = in hns3_recv_burst_vec()
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c372 offsetof(struct rte_mbuf, rearm_data) + 8); in _iavf_recv_raw_pkts_vec_avx2()
373 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _iavf_recv_raw_pkts_vec_avx2()
375 rearm_data), in _iavf_recv_raw_pkts_vec_avx2()
396 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 6]->rearm_data, in _iavf_recv_raw_pkts_vec_avx2()
398 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 4]->rearm_data, in _iavf_recv_raw_pkts_vec_avx2()
400 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 2]->rearm_data, in _iavf_recv_raw_pkts_vec_avx2()
402 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 0]->rearm_data, in _iavf_recv_raw_pkts_vec_avx2()
425 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 7]->rearm_data, in _iavf_recv_raw_pkts_vec_avx2()
1085 offsetof(struct rte_mbuf, rearm_data) + 8); in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
1086 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
[all …]
H A Diavf_rxtx_vec_avx512.c539 offsetof(struct rte_mbuf, rearm_data) + 8); in _iavf_recv_raw_pkts_vec_avx512()
540 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _iavf_recv_raw_pkts_vec_avx512()
542 rearm_data), in _iavf_recv_raw_pkts_vec_avx512()
575 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 6]->rearm_data, in _iavf_recv_raw_pkts_vec_avx512()
577 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 4]->rearm_data, in _iavf_recv_raw_pkts_vec_avx512()
579 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 2]->rearm_data, in _iavf_recv_raw_pkts_vec_avx512()
581 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 0]->rearm_data, in _iavf_recv_raw_pkts_vec_avx512()
611 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 7]->rearm_data, in _iavf_recv_raw_pkts_vec_avx512()
1351 offsetof(struct rte_mbuf, rearm_data) + 8); in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1352 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
[all …]
H A Diavf_rxtx_vec_sse.c183 offsetof(struct rte_mbuf, rearm_data) + 8); in desc_to_olflags_v()
184 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in desc_to_olflags_v()
185 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in desc_to_olflags_v()
186 _mm_store_si128((__m128i *)&rx_pkts[0]->rearm_data, rearm0); in desc_to_olflags_v()
187 _mm_store_si128((__m128i *)&rx_pkts[1]->rearm_data, rearm1); in desc_to_olflags_v()
188 _mm_store_si128((__m128i *)&rx_pkts[2]->rearm_data, rearm2); in desc_to_olflags_v()
189 _mm_store_si128((__m128i *)&rx_pkts[3]->rearm_data, rearm3); in desc_to_olflags_v()
335 offsetof(struct rte_mbuf, rearm_data) + 8); in flex_desc_to_olflags_v()
336 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in flex_desc_to_olflags_v()
337 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in flex_desc_to_olflags_v()
[all …]
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec.h42 offsetof(struct rte_mbuf, rearm_data) + 8);
43 S_ASSERT_RTE_MBUF(offsetof(struct rte_mbuf, rearm_data) ==
44 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16));
H A Dmlx5_rxtx_vec_neon.h98 vld1q_u64((void *)&t_pkt->rearm_data); in rxq_cq_decompress_v()
136 uint8_t *e0 = (void *)&elts[pos]->rearm_data; in rxq_cq_decompress_v()
137 uint8_t *e1 = (void *)&elts[pos + 1]->rearm_data; in rxq_cq_decompress_v()
138 uint8_t *e2 = (void *)&elts[pos + 2]->rearm_data; in rxq_cq_decompress_v()
139 uint8_t *e3 = (void *)&elts[pos + 3]->rearm_data; in rxq_cq_decompress_v()
490 vst1q_u64((void *)&pkts[0]->rearm_data, rearm0); in rxq_cq_to_ptype_oflags_v()
491 vst1q_u64((void *)&pkts[1]->rearm_data, rearm1); in rxq_cq_to_ptype_oflags_v()
492 vst1q_u64((void *)&pkts[2]->rearm_data, rearm2); in rxq_cq_to_ptype_oflags_v()
493 vst1q_u64((void *)&pkts[3]->rearm_data, rearm3); in rxq_cq_to_ptype_oflags_v()
H A Dmlx5_rxtx_vec_sse.h98 _mm_loadu_si128((__m128i *)&t_pkt->rearm_data); in rxq_cq_decompress_v()
141 _mm_storeu_si128((__m128i *)&elts[pos]->rearm_data, rearm); in rxq_cq_decompress_v()
142 _mm_storeu_si128((__m128i *)&elts[pos + 1]->rearm_data, rearm); in rxq_cq_decompress_v()
158 _mm_storeu_si128((__m128i *)&elts[pos + 2]->rearm_data, rearm); in rxq_cq_decompress_v()
159 _mm_storeu_si128((__m128i *)&elts[pos + 3]->rearm_data, rearm); in rxq_cq_decompress_v()
489 _mm_store_si128((__m128i *)&pkts[0]->rearm_data, rearm0); in rxq_cq_to_ptype_oflags_v()
490 _mm_store_si128((__m128i *)&pkts[1]->rearm_data, rearm1); in rxq_cq_to_ptype_oflags_v()
491 _mm_store_si128((__m128i *)&pkts[2]->rearm_data, rearm2); in rxq_cq_to_ptype_oflags_v()
492 _mm_store_si128((__m128i *)&pkts[3]->rearm_data, rearm3); in rxq_cq_to_ptype_oflags_v()
/dpdk/drivers/net/sfc/
H A Dsfc_ef10_rx.c71 uint64_t rearm_data; member
325 RTE_BUILD_BUG_ON(sizeof(m->rearm_data[0]) != sizeof(rxq->rearm_data)); in sfc_ef10_rx_process_event()
326 m->rearm_data[0] = rxq->rearm_data; in sfc_ef10_rx_process_event()
380 RTE_BUILD_BUG_ON(sizeof(m->rearm_data[0]) != in sfc_ef10_rx_process_event()
381 sizeof(rxq->rearm_data)); in sfc_ef10_rx_process_event()
382 m->rearm_data[0] = rxq->rearm_data; in sfc_ef10_rx_process_event()
636 RTE_BUILD_BUG_ON(sizeof(m.rearm_data[0]) != sizeof(uint64_t)); in sfc_ef10_mk_mbuf_rearm_data()
637 return m.rearm_data[0]; in sfc_ef10_mk_mbuf_rearm_data()
681 rxq->rearm_data = in sfc_ef10_rx_qcreate()
H A Dsfc_ef100_rx.c79 uint64_t rearm_data; member
546 RTE_BUILD_BUG_ON(sizeof(pkt->rearm_data[0]) != in sfc_ef100_rx_process_ready_pkts()
547 sizeof(rxq->rearm_data)); in sfc_ef100_rx_process_ready_pkts()
548 pkt->rearm_data[0] = rxq->rearm_data; in sfc_ef100_rx_process_ready_pkts()
752 RTE_BUILD_BUG_ON(sizeof(m.rearm_data[0]) != sizeof(uint64_t)); in sfc_ef100_mk_mbuf_rearm_data()
753 return m.rearm_data[0]; in sfc_ef100_mk_mbuf_rearm_data()
886 rxq->rearm_data = sfc_ef100_mk_mbuf_rearm_data(rxq->dp.dpq.port_id, in sfc_ef100_rx_qstart()
/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_packed_avx.h39 __m256i mbufs = _mm256_set_epi64x(*tx_pkts[3]->rearm_data, in virtqueue_enqueue_batch_packed_vec()
40 *tx_pkts[2]->rearm_data, in virtqueue_enqueue_batch_packed_vec()
41 *tx_pkts[1]->rearm_data, in virtqueue_enqueue_batch_packed_vec()
42 *tx_pkts[0]->rearm_data); in virtqueue_enqueue_batch_packed_vec()
57 offsetof(struct rte_mbuf, rearm_data)); in virtqueue_enqueue_batch_packed_vec()
H A Dvirtio_rxtx_packed_neon.h62 pkts[0] = vld1_u16((uint16_t *)&tx_pkts[0]->rearm_data); in virtqueue_enqueue_batch_packed_vec()
63 pkts[1] = vld1_u16((uint16_t *)&tx_pkts[1]->rearm_data); in virtqueue_enqueue_batch_packed_vec()
64 pkts[2] = vld1_u16((uint16_t *)&tx_pkts[2]->rearm_data); in virtqueue_enqueue_batch_packed_vec()
65 pkts[3] = vld1_u16((uint16_t *)&tx_pkts[3]->rearm_data); in virtqueue_enqueue_batch_packed_vec()
81 offsetof(struct rte_mbuf, rearm_data)); in virtqueue_enqueue_batch_packed_vec()
/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c22 *(uint64_t *)&mb->rearm_data = enic->mbuf_initializer; in rx_one()
740 _mm256_storeu_si256((__m256i *)&rxmb[0]->rearm_data, rearm0); in enic_noscatter_vec_recv_pkts()
741 _mm256_storeu_si256((__m256i *)&rxmb[1]->rearm_data, rearm1); in enic_noscatter_vec_recv_pkts()
742 _mm256_storeu_si256((__m256i *)&rxmb[2]->rearm_data, rearm2); in enic_noscatter_vec_recv_pkts()
743 _mm256_storeu_si256((__m256i *)&rxmb[3]->rearm_data, rearm3); in enic_noscatter_vec_recv_pkts()
744 _mm256_storeu_si256((__m256i *)&rxmb[4]->rearm_data, rearm4); in enic_noscatter_vec_recv_pkts()
745 _mm256_storeu_si256((__m256i *)&rxmb[5]->rearm_data, rearm5); in enic_noscatter_vec_recv_pkts()
746 _mm256_storeu_si256((__m256i *)&rxmb[6]->rearm_data, rearm6); in enic_noscatter_vec_recv_pkts()
747 _mm256_storeu_si256((__m256i *)&rxmb[7]->rearm_data, rearm7); in enic_noscatter_vec_recv_pkts()
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_sse.c101 uint32_t *rearm0 = (uint32_t *)rx_pkts[0]->rearm_data + 2; in desc_to_olflags_v_ipsec()
102 uint32_t *rearm1 = (uint32_t *)rx_pkts[1]->rearm_data + 2; in desc_to_olflags_v_ipsec()
103 uint32_t *rearm2 = (uint32_t *)rx_pkts[2]->rearm_data + 2; in desc_to_olflags_v_ipsec()
104 uint32_t *rearm3 = (uint32_t *)rx_pkts[3]->rearm_data + 2; in desc_to_olflags_v_ipsec()
255 offsetof(struct rte_mbuf, rearm_data) + 8); in desc_to_olflags_v()
256 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in desc_to_olflags_v()
257 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in desc_to_olflags_v()
258 _mm_store_si128((__m128i *)&rx_pkts[0]->rearm_data, rearm0); in desc_to_olflags_v()
259 _mm_store_si128((__m128i *)&rx_pkts[1]->rearm_data, rearm1); in desc_to_olflags_v()
260 _mm_store_si128((__m128i *)&rx_pkts[2]->rearm_data, rearm2); in desc_to_olflags_v()
[all …]
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_avx2.c530 offsetof(struct rte_mbuf, rearm_data) + 8); in _recv_raw_pkts_vec_avx2()
531 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _recv_raw_pkts_vec_avx2()
532 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in _recv_raw_pkts_vec_avx2()
546 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 6]->rearm_data, rearm6); in _recv_raw_pkts_vec_avx2()
547 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 4]->rearm_data, rearm4); in _recv_raw_pkts_vec_avx2()
548 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 2]->rearm_data, rearm2); in _recv_raw_pkts_vec_avx2()
549 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 0]->rearm_data, rearm0); in _recv_raw_pkts_vec_avx2()
564 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 7]->rearm_data, rearm7); in _recv_raw_pkts_vec_avx2()
565 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 5]->rearm_data, rearm5); in _recv_raw_pkts_vec_avx2()
566 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 3]->rearm_data, rearm3); in _recv_raw_pkts_vec_avx2()
[all …]
H A Di40e_rxtx_vec_avx512.c685 offsetof(struct rte_mbuf, rearm_data) + 8); in _recv_raw_pkts_vec_avx512()
686 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _recv_raw_pkts_vec_avx512()
687 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in _recv_raw_pkts_vec_avx512()
706 ((__m256i *)&rx_pkts[i + 6]->rearm_data, rearm6); in _recv_raw_pkts_vec_avx512()
708 ((__m256i *)&rx_pkts[i + 4]->rearm_data, rearm4); in _recv_raw_pkts_vec_avx512()
710 ((__m256i *)&rx_pkts[i + 2]->rearm_data, rearm2); in _recv_raw_pkts_vec_avx512()
712 ((__m256i *)&rx_pkts[i + 0]->rearm_data, rearm0); in _recv_raw_pkts_vec_avx512()
732 ((__m256i *)&rx_pkts[i + 7]->rearm_data, rearm7); in _recv_raw_pkts_vec_avx512()
734 ((__m256i *)&rx_pkts[i + 5]->rearm_data, rearm5); in _recv_raw_pkts_vec_avx512()
736 ((__m256i *)&rx_pkts[i + 3]->rearm_data, rearm3); in _recv_raw_pkts_vec_avx512()
[all …]
H A Di40e_rxtx_vec_sse.c320 offsetof(struct rte_mbuf, rearm_data) + 8); in desc_to_olflags_v()
321 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in desc_to_olflags_v()
322 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in desc_to_olflags_v()
323 _mm_store_si128((__m128i *)&rx_pkts[0]->rearm_data, rearm0); in desc_to_olflags_v()
324 _mm_store_si128((__m128i *)&rx_pkts[1]->rearm_data, rearm1); in desc_to_olflags_v()
325 _mm_store_si128((__m128i *)&rx_pkts[2]->rearm_data, rearm2); in desc_to_olflags_v()
326 _mm_store_si128((__m128i *)&rx_pkts[3]->rearm_data, rearm3); in desc_to_olflags_v()
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c575 offsetof(struct rte_mbuf, rearm_data) + 8); in _ice_recv_raw_pkts_vec_avx2()
576 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _ice_recv_raw_pkts_vec_avx2()
578 rearm_data), in _ice_recv_raw_pkts_vec_avx2()
599 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 6]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
601 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 4]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
603 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 2]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
605 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 0]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
628 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 7]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
630 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 5]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
632 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 3]->rearm_data, in _ice_recv_raw_pkts_vec_avx2()
[all …]
H A Dice_rxtx_vec_avx512.c686 offsetof(struct rte_mbuf, rearm_data) + 8); in _ice_recv_raw_pkts_vec_avx512()
687 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in _ice_recv_raw_pkts_vec_avx512()
689 rearm_data), in _ice_recv_raw_pkts_vec_avx512()
713 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 6]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
715 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 4]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
717 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 2]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
719 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 0]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
743 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 7]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
745 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 5]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
747 _mm256_storeu_si256((__m256i *)&rx_pkts[i + 3]->rearm_data, in _ice_recv_raw_pkts_vec_avx512()
[all …]
H A Dice_rxtx_vec_sse.c263 offsetof(struct rte_mbuf, rearm_data) + 8); in ice_rx_desc_to_olflags_v()
264 RTE_BUILD_BUG_ON(offsetof(struct rte_mbuf, rearm_data) != in ice_rx_desc_to_olflags_v()
265 RTE_ALIGN(offsetof(struct rte_mbuf, rearm_data), 16)); in ice_rx_desc_to_olflags_v()
266 _mm_store_si128((__m128i *)&rx_pkts[0]->rearm_data, rearm0); in ice_rx_desc_to_olflags_v()
267 _mm_store_si128((__m128i *)&rx_pkts[1]->rearm_data, rearm1); in ice_rx_desc_to_olflags_v()
268 _mm_store_si128((__m128i *)&rx_pkts[2]->rearm_data, rearm2); in ice_rx_desc_to_olflags_v()
269 _mm_store_si128((__m128i *)&rx_pkts[3]->rearm_data, rearm3); in ice_rx_desc_to_olflags_v()
/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_avx2.c313 _mm256_storeu_si256((void *)&rx_pkts[i + 0]->rearm_data, in recv_burst_vec_avx2()
315 _mm256_storeu_si256((void *)&rx_pkts[i + 1]->rearm_data, in recv_burst_vec_avx2()
317 _mm256_storeu_si256((void *)&rx_pkts[i + 2]->rearm_data, in recv_burst_vec_avx2()
319 _mm256_storeu_si256((void *)&rx_pkts[i + 3]->rearm_data, in recv_burst_vec_avx2()
339 _mm256_storeu_si256((void *)&rx_pkts[i + 4]->rearm_data, in recv_burst_vec_avx2()
341 _mm256_storeu_si256((void *)&rx_pkts[i + 5]->rearm_data, in recv_burst_vec_avx2()
343 _mm256_storeu_si256((void *)&rx_pkts[i + 6]->rearm_data, in recv_burst_vec_avx2()
345 _mm256_storeu_si256((void *)&rx_pkts[i + 7]->rearm_data, in recv_burst_vec_avx2()
H A Dbnxt_rxtx_vec_sse.c123 _mm_store_si128((void *)&mbuf[0]->rearm_data, in descs_to_mbufs()
127 _mm_store_si128((void *)&mbuf[1]->rearm_data, in descs_to_mbufs()
131 _mm_store_si128((void *)&mbuf[2]->rearm_data, in descs_to_mbufs()
135 _mm_store_si128((void *)&mbuf[3]->rearm_data, in descs_to_mbufs()
H A Dbnxt_rxtx_vec_neon.c138 vst1q_u32((uint32_t *)&mbuf[0]->rearm_data, in descs_to_mbufs()
141 vst1q_u32((uint32_t *)&mbuf[1]->rearm_data, in descs_to_mbufs()
144 vst1q_u32((uint32_t *)&mbuf[2]->rearm_data, in descs_to_mbufs()
147 vst1q_u32((uint32_t *)&mbuf[3]->rearm_data, in descs_to_mbufs()
/dpdk/drivers/net/thunderx/
H A Dnicvf_rxtx.h69 *(uint64_t *)(&pkt->rearm_data) = init.value; in nicvf_mbuff_init_update()
83 *(uint64_t *)(&pkt->rearm_data) = init.value; in nicvf_mbuff_init_mseg_update()
/dpdk/drivers/net/cnxk/
H A Dcn10k_rx.h185 *(uint64_t *)(&mbuf->rearm_data) = mbuf_init; in nix_sec_attach_frags()
209 *(uint64_t *)(&mbuf->rearm_data) = mbuf_init; in nix_sec_attach_frags()
237 *(uint64_t *)(&mbuf->rearm_data) = mbuf_init; in nix_sec_attach_frags()
264 *(uint64_t *)(&mbuf->rearm_data) = mbuf_init; in nix_sec_attach_frags()
476 *(uint64_t *)(&inner->rearm_data) = mbuf_init; in nix_sec_meta_to_mbuf_sc()
542 *(uint64_t *)(&inner->rearm_data) = mbuf_init; in nix_sec_meta_to_mbuf_sc()
613 mbuf_init = *(uint64_t *)(&inner->rearm_data); in nix_sec_meta_to_mbuf()
721 *(uint64_t *)(&mbuf->rearm_data) = rearm; in nix_cqe_xtract_mseg()
782 *(uint64_t *)(&mbuf->rearm_data) = val; in cn10k_nix_cqe_to_mbuf()
1671 vst1q_u64((uint64_t *)mbuf0->rearm_data, rearm0); in cn10k_nix_recv_pkts_vector()
[all …]

12