Home
last modified time | relevance | path

Searched refs:PKT_RX_IP_CKSUM_GOOD (Results 1 – 25 of 54) sorted by relevance

123

/f-stack/dpdk/drivers/net/enetc/
H A Denetc_rxtx.c177 m->ol_flags &= ~(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD); in enetc_slow_parsing()
194 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
201 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
208 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
215 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
222 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
229 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
236 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
243 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | in enetc_slow_parsing()
259 m->ol_flags |= PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD; in enetc_dev_rx_parse()
/f-stack/dpdk/drivers/net/octeontx2/
H A Dotx2_lookup.c280 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
290 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
297 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
303 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
309 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
315 val |= PKT_RX_IP_CKSUM_GOOD; in nix_create_rx_ol_flags_array()
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c269 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in _iavf_recv_raw_pkts_vec_avx2()
272 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx2()
274 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx2()
276 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx2()
281 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in _iavf_recv_raw_pkts_vec_avx2()
284 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx2()
286 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx2()
748 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
752 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
762 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
[all …]
H A Diavf_rxtx_vec_avx512.c291 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in _iavf_recv_raw_pkts_vec_avx512()
294 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx512()
296 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx512()
298 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx512()
303 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in _iavf_recv_raw_pkts_vec_avx512()
306 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx512()
308 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _iavf_recv_raw_pkts_vec_avx512()
764 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
768 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
778 PKT_RX_IP_CKSUM_GOOD) >> 1, in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
[all …]
H A Diavf_rxtx_vec_sse.c111 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
114 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
117 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
120 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
139 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in desc_to_olflags_v()
142 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in desc_to_olflags_v()
144 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in desc_to_olflags_v()
146 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1); in desc_to_olflags_v()
249 PKT_RX_IP_CKSUM_GOOD) >> 1, in flex_desc_to_olflags_v()
253 PKT_RX_IP_CKSUM_GOOD) >> 1, in flex_desc_to_olflags_v()
[all …]
/f-stack/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c214 ((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1), in enic_noscatter_vec_recv_pkts()
216 ((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1), in enic_noscatter_vec_recv_pkts()
217 (PKT_RX_IP_CKSUM_GOOD >> 1), /* 1101 ip4+ip4_ok */ in enic_noscatter_vec_recv_pkts()
218 (PKT_RX_IP_CKSUM_GOOD >> 1), /* 1100 ip4_ok+ip4 */ in enic_noscatter_vec_recv_pkts()
234 ((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1), in enic_noscatter_vec_recv_pkts()
235 ((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1), in enic_noscatter_vec_recv_pkts()
236 (PKT_RX_IP_CKSUM_GOOD >> 1), in enic_noscatter_vec_recv_pkts()
237 (PKT_RX_IP_CKSUM_GOOD >> 1), in enic_noscatter_vec_recv_pkts()
H A Denic_rxtx_common.h257 pkt_flags |= PKT_RX_IP_CKSUM_GOOD; in enic_cq_rx_to_pkt_flags()
/f-stack/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_neon.c96 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
99 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
102 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
105 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
123 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1, in desc_to_olflags_v()
125 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in desc_to_olflags_v()
127 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in desc_to_olflags_v()
129 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in desc_to_olflags_v()
H A Di40e_rxtx_vec_sse.c231 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
234 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
237 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
240 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in desc_to_olflags_v()
259 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | in desc_to_olflags_v()
262 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in desc_to_olflags_v()
264 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in desc_to_olflags_v()
266 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1); in desc_to_olflags_v()
H A Di40e_rxtx_vec_avx2.c346 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
348 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
350 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
352 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1, in _recv_raw_pkts_vec_avx2()
356 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD | PKT_RX_L4_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
358 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_EIP_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
360 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD) >> 1, in _recv_raw_pkts_vec_avx2()
362 (PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1); in _recv_raw_pkts_vec_avx2()
365 PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in _recv_raw_pkts_vec_avx2()
/f-stack/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c264 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
268 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
270 (PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
272 (PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
278 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
282 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
284 (PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx2()
286 (PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1); in _ice_recv_raw_pkts_vec_avx2()
288 _mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c243 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
247 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
249 (PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
251 (PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
257 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
261 PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
263 (PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1, in _ice_recv_raw_pkts_vec_avx512()
265 (PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1); in _ice_recv_raw_pkts_vec_avx512()
267 _mm256_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_IP_CKSUM_BAD | in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx_vec_sse.c141 PKT_RX_IP_CKSUM_GOOD) >> 1, in ice_rx_desc_to_olflags_v()
145 PKT_RX_IP_CKSUM_GOOD) >> 1, in ice_rx_desc_to_olflags_v()
147 (PKT_RX_L4_CKSUM_BAD | PKT_RX_IP_CKSUM_GOOD) >> 1, in ice_rx_desc_to_olflags_v()
149 (PKT_RX_L4_CKSUM_GOOD | PKT_RX_IP_CKSUM_GOOD) >> 1); in ice_rx_desc_to_olflags_v()
/f-stack/dpdk/drivers/event/octeontx/
H A Dssovf_worker.c430 val |= PKT_RX_IP_CKSUM_GOOD; in octeontx_create_rx_ol_flags_array()
439 val |= PKT_RX_IP_CKSUM_GOOD; in octeontx_create_rx_ol_flags_array()
446 val |= PKT_RX_IP_CKSUM_GOOD; in octeontx_create_rx_ol_flags_array()
456 val |= PKT_RX_IP_CKSUM_GOOD; in octeontx_create_rx_ol_flags_array()
462 val |= PKT_RX_IP_CKSUM_GOOD; in octeontx_create_rx_ol_flags_array()
/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_sse.c169 vlan_flags | PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
170 vlan_flags | PKT_RX_IP_CKSUM_GOOD, in desc_to_olflags_v()
174 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD, in desc_to_olflags_v()
175 PKT_RX_IP_CKSUM_GOOD); in desc_to_olflags_v()
/f-stack/dpdk/drivers/net/sfc/
H A Dsfc_ef10_rx_ev.h110 PKT_RX_IP_CKSUM_BAD : PKT_RX_IP_CKSUM_GOOD); in sfc_ef10_rx_ev_to_offloads()
H A Dsfc_ef100_rx.c267 *ol_flags |= PKT_RX_IP_CKSUM_GOOD; in sfc_ef100_rx_class_decode()
319 *ol_flags |= PKT_RX_IP_CKSUM_GOOD; in sfc_ef100_rx_class_decode()
/f-stack/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_altivec.h555 (uint8_t)(PKT_RX_IP_CKSUM_GOOD >> 1), 0, in rxq_cq_to_ptype_oflags_v()
557 (uint8_t)((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1), in rxq_cq_to_ptype_oflags_v()
561 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
563 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
565 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
567 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
H A Dmlx5_rxtx_vec_neon.h405 (uint8_t)(PKT_RX_IP_CKSUM_GOOD >> 1), in rxq_cq_to_ptype_oflags_v()
409 (uint8_t)((PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD) >> 1), in rxq_cq_to_ptype_oflags_v()
413 vdupq_n_u32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
H A Dmlx5_rxtx_vec_sse.h393 (uint8_t)((PKT_RX_IP_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
398 (uint8_t)(PKT_RX_IP_CKSUM_GOOD >> 1), in rxq_cq_to_ptype_oflags_v()
402 _mm_set1_epi32(PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD | in rxq_cq_to_ptype_oflags_v()
/f-stack/dpdk/drivers/net/axgbe/
H A Daxgbe_rxtx.c262 mbuf->ol_flags |= PKT_RX_IP_CKSUM_GOOD; in axgbe_recv_pkts()
265 mbuf->ol_flags &= ~PKT_RX_IP_CKSUM_GOOD; in axgbe_recv_pkts()
428 mbuf->ol_flags |= PKT_RX_IP_CKSUM_GOOD; in eth_axgbe_recv_scattered_pkts()
431 mbuf->ol_flags &= ~PKT_RX_IP_CKSUM_GOOD; in eth_axgbe_recv_scattered_pkts()
/f-stack/dpdk/lib/librte_mbuf/
H A Drte_mbuf_core.h98 #define PKT_RX_IP_CKSUM_GOOD (1ULL << 7) macro
H A Drte_mbuf.c756 case PKT_RX_IP_CKSUM_GOOD: return "PKT_RX_IP_CKSUM_GOOD"; in rte_get_rx_ol_flag_name()
798 { PKT_RX_IP_CKSUM_GOOD, PKT_RX_IP_CKSUM_MASK, NULL }, in rte_get_rx_ol_flag_list()
/f-stack/dpdk/drivers/net/hns3/
H A Dhns3_rxtx.h561 rxm->ol_flags |= PKT_RX_IP_CKSUM_GOOD; in hns3_rx_set_cksum_flag()
571 rxm->ol_flags |= PKT_RX_IP_CKSUM_GOOD; in hns3_rx_set_cksum_flag()
/f-stack/dpdk/drivers/net/thunderx/
H A Dnicvf_rxtx.c346 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_GOOD, in nicvf_set_olflags()
348 PKT_RX_IP_CKSUM_GOOD | PKT_RX_L4_CKSUM_BAD, in nicvf_set_olflags()

123