Home
last modified time | relevance | path

Searched refs:ptype (Results 1 – 25 of 75) sorted by relevance

123

/dpdk/lib/mbuf/
H A Drte_mbuf_ptype.c13 switch (ptype & RTE_PTYPE_L2_MASK) { in rte_get_ptype_l2_name()
31 switch (ptype & RTE_PTYPE_L3_MASK) { in rte_get_ptype_l3_name()
45 switch (ptype & RTE_PTYPE_L4_MASK) { in rte_get_ptype_l4_name()
60 switch (ptype & RTE_PTYPE_TUNNEL_MASK) { in rte_get_ptype_tunnel_name()
139 rte_get_ptype_l2_name(ptype)); in rte_get_ptype_name()
149 rte_get_ptype_l3_name(ptype)); in rte_get_ptype_name()
159 rte_get_ptype_l4_name(ptype)); in rte_get_ptype_name()
169 rte_get_ptype_tunnel_name(ptype)); in rte_get_ptype_name()
179 rte_get_ptype_inner_l2_name(ptype)); in rte_get_ptype_name()
189 rte_get_ptype_inner_l3_name(ptype)); in rte_get_ptype_name()
[all …]
H A Drte_mbuf_ptype.h675 #define RTE_ETH_IS_IPV4_HDR(ptype) ((ptype) & RTE_PTYPE_L3_IPV4) argument
682 #define RTE_ETH_IS_IPV6_HDR(ptype) ((ptype) & RTE_PTYPE_L3_IPV6) argument
685 #define RTE_ETH_IS_TUNNEL_PKT(ptype) ((ptype) & \ argument
699 const char *rte_get_ptype_l2_name(uint32_t ptype);
709 const char *rte_get_ptype_l3_name(uint32_t ptype);
719 const char *rte_get_ptype_l4_name(uint32_t ptype);
729 const char *rte_get_ptype_tunnel_name(uint32_t ptype);
739 const char *rte_get_ptype_inner_l2_name(uint32_t ptype);
749 const char *rte_get_ptype_inner_l3_name(uint32_t ptype);
759 const char *rte_get_ptype_inner_l4_name(uint32_t ptype);
[all …]
/dpdk/drivers/net/ngbe/
H A Dngbe_ptypes.c121 ngbe_encode_ptype_mac(u32 ptype) in ngbe_encode_ptype_mac() argument
127 switch (ptype & RTE_PTYPE_L2_MASK) { in ngbe_encode_ptype_mac()
148 ngbe_encode_ptype_ip(u32 ptype) in ngbe_encode_ptype_ip() argument
154 switch (ptype & RTE_PTYPE_L3_MASK) { in ngbe_encode_ptype_ip()
168 switch (ptype & RTE_PTYPE_L4_MASK) { in ngbe_encode_ptype_ip()
190 ngbe_encode_ptype_tunnel(u32 ptype) in ngbe_encode_ptype_tunnel() argument
196 switch (ptype & RTE_PTYPE_L3_MASK) { in ngbe_encode_ptype_tunnel()
285 u8 ngbe_encode_ptype(u32 ptype) in ngbe_encode_ptype() argument
289 if (ptype & RTE_PTYPE_TUNNEL_MASK) in ngbe_encode_ptype()
291 else if (ptype & RTE_PTYPE_L3_MASK) in ngbe_encode_ptype()
[all …]
/dpdk/lib/gro/
H A Drte_gro.c33 #define IS_IPV4_TCP_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
35 (RTE_ETH_IS_TUNNEL_PKT(ptype) == 0))
37 #define IS_IPV4_UDP_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
39 (RTE_ETH_IS_TUNNEL_PKT(ptype) == 0))
41 #define IS_IPV4_VXLAN_TCP4_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
43 ((ptype & RTE_PTYPE_TUNNEL_VXLAN) == \
45 ((ptype & RTE_PTYPE_INNER_L4_TCP) == \
47 (((ptype & RTE_PTYPE_INNER_L3_MASK) == \
54 #define IS_IPV4_VXLAN_UDP4_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
56 ((ptype & RTE_PTYPE_TUNNEL_VXLAN) == \
[all …]
/dpdk/drivers/net/octeontx/base/
H A Docteontx_pkivf.h301 pki_port_type_t ptype; in octeontx_pki_port_close() local
303 memset(&ptype, 0, len); in octeontx_pki_port_close()
304 ptype.port_type = OCTTX_PORT_TYPE_NET; in octeontx_pki_port_close()
310 res = octeontx_mbox_send(&hdr, &ptype, len, NULL, 0); in octeontx_pki_port_close()
323 pki_port_type_t ptype; in octeontx_pki_port_start() local
325 memset(&ptype, 0, len); in octeontx_pki_port_start()
326 ptype.port_type = OCTTX_PORT_TYPE_NET; in octeontx_pki_port_start()
332 res = octeontx_mbox_send(&hdr, &ptype, len, NULL, 0); in octeontx_pki_port_start()
345 pki_port_type_t ptype; in octeontx_pki_port_stop() local
347 memset(&ptype, 0, len); in octeontx_pki_port_stop()
[all …]
/dpdk/drivers/net/sfc/
H A Dsfc_ef100_rx.c238 uint32_t ptype; in sfc_ef100_rx_class_decode() local
247 ptype = RTE_PTYPE_L2_ETHER; in sfc_ef100_rx_class_decode()
250 ptype = RTE_PTYPE_L2_ETHER_VLAN; in sfc_ef100_rx_class_decode()
253 ptype = RTE_PTYPE_L2_ETHER_QINQ; in sfc_ef100_rx_class_decode()
266 ptype |= RTE_PTYPE_TUNNEL_NVGRE; in sfc_ef100_rx_class_decode()
305 ptype |= RTE_PTYPE_L4_TCP; in sfc_ef100_rx_class_decode()
310 ptype |= RTE_PTYPE_L4_UDP; in sfc_ef100_rx_class_decode()
315 ptype |= RTE_PTYPE_L4_FRAG; in sfc_ef100_rx_class_decode()
358 ptype |= RTE_PTYPE_INNER_L4_TCP; in sfc_ef100_rx_class_decode()
363 ptype |= RTE_PTYPE_INNER_L4_UDP; in sfc_ef100_rx_class_decode()
[all …]
/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c612 __m256i ptype = _mm256_or_si256(nonfrag_ptype, frag_ptype); in enic_noscatter_vec_recv_pkts() local
613 ptype = _mm256_slli_epi32(ptype, 4); in enic_noscatter_vec_recv_pkts()
626 _mm256_slli_epi32(_mm256_and_si256(ptype, in enic_noscatter_vec_recv_pkts()
641 ptype = _mm256_and_si256(ptype, in enic_noscatter_vec_recv_pkts()
649 ptype = _mm256_or_si256(ptype, tnl_ptype); in enic_noscatter_vec_recv_pkts()
650 ptype = _mm256_or_si256(ptype, vlan_ptype); in enic_noscatter_vec_recv_pkts()
651 ptype = _mm256_permute4x64_epi64(ptype, in enic_noscatter_vec_recv_pkts()
675 rearm01 = _mm256_blend_epi32(rearm01, ptype, 0x11); in enic_noscatter_vec_recv_pkts()
677 _mm256_shuffle_epi32(ptype, 1), 0x11); in enic_noscatter_vec_recv_pkts()
679 _mm256_shuffle_epi32(ptype, 2), 0x11); in enic_noscatter_vec_recv_pkts()
[all …]
/dpdk/drivers/net/ice/
H A Dice_fdir_filter.c175 ptype++) { in ice_fdir_prof_alloc()
187 fltr_ptype < ptype; in ice_fdir_prof_alloc()
560 ptype++) { in ice_fdir_prof_free()
590 vsi_num, ptype); in ice_fdir_prof_rm()
613 ptype++) { in ice_fdir_prof_rm_all()
689 ptype); in ice_fdir_cur_prof_conflict()
696 ptype); in ice_fdir_cur_prof_conflict()
738 switch (ptype) { in ice_fdir_cross_prof_conflict()
877 ptype); in ice_fdir_hw_tbl_conf()
885 ptype); in ice_fdir_hw_tbl_conf()
[all …]
H A Dice_acl_filter.c62 enum ice_fltr_ptype ptype, fltr_ptype; in ice_acl_prof_alloc() local
72 for (ptype = ICE_FLTR_PTYPE_NONF_NONE + 1; in ice_acl_prof_alloc()
73 ptype < ICE_FLTR_PTYPE_MAX; ptype++) { in ice_acl_prof_alloc()
74 if (!hw->acl_prof[ptype]) { in ice_acl_prof_alloc()
77 if (!hw->acl_prof[ptype]) in ice_acl_prof_alloc()
86 fltr_ptype < ptype; fltr_ptype++) { in ice_acl_prof_alloc()
1026 enum ice_fltr_ptype ptype; in ice_acl_prof_free() local
1028 for (ptype = ICE_FLTR_PTYPE_NONF_NONE + 1; in ice_acl_prof_free()
1029 ptype < ICE_FLTR_PTYPE_MAX; ptype++) { in ice_acl_prof_free()
1030 rte_free(hw->acl_prof[ptype]); in ice_acl_prof_free()
[all …]
/dpdk/drivers/net/txgbe/
H A Dtxgbe_ptypes.c215 txgbe_encode_ptype_fcoe(u32 ptype) in txgbe_encode_ptype_fcoe() argument
219 UNREFERENCED_PARAMETER(ptype); in txgbe_encode_ptype_fcoe()
226 txgbe_encode_ptype_mac(u32 ptype) in txgbe_encode_ptype_mac() argument
232 switch (ptype & RTE_PTYPE_L2_MASK) { in txgbe_encode_ptype_mac()
256 txgbe_encode_ptype_ip(u32 ptype) in txgbe_encode_ptype_ip() argument
262 switch (ptype & RTE_PTYPE_L3_MASK) { in txgbe_encode_ptype_ip()
298 txgbe_encode_ptype_tunnel(u32 ptype) in txgbe_encode_ptype_tunnel() argument
392 u8 txgbe_encode_ptype(u32 ptype) in txgbe_encode_ptype() argument
396 if (ptype & RTE_PTYPE_TUNNEL_MASK) in txgbe_encode_ptype()
398 else if (ptype & RTE_PTYPE_L3_MASK) in txgbe_encode_ptype()
[all …]
/dpdk/examples/ipsec-secgw/test/
H A Dtun_aesgcm_defs.sh15 dir out ptype main action allow \
21 dir in ptype main action allow \
48 dir out ptype main action allow \
54 dir in ptype main action allow \
83 dir out ptype main action allow \
89 dir in ptype main action allow \
118 dir out ptype main action allow \
124 dir in ptype main action allow \
H A Dtun_aesctr_sha1_defs.sh15 dir out ptype main action allow \
21 dir in ptype main action allow \
48 dir out ptype main action allow \
54 dir in ptype main action allow \
83 dir out ptype main action allow \
89 dir in ptype main action allow \
118 dir out ptype main action allow \
124 dir in ptype main action allow \
H A Dtun_3descbc_sha1_defs.sh15 dir out ptype main action allow \
21 dir in ptype main action allow \
48 dir out ptype main action allow \
54 dir in ptype main action allow \
83 dir out ptype main action allow \
89 dir in ptype main action allow \
118 dir out ptype main action allow \
124 dir in ptype main action allow \
H A Dtun_aescbc_sha1_defs.sh15 dir out ptype main action allow \
21 dir in ptype main action allow \
48 dir out ptype main action allow \
54 dir in ptype main action allow \
83 dir out ptype main action allow \
89 dir in ptype main action allow \
118 dir out ptype main action allow \
124 dir in ptype main action allow \
H A Dtrs_3descbc_sha1_defs.sh15 dir out ptype main action allow \
20 dir in ptype main action allow \
46 dir out ptype main action allow \
51 dir in ptype main action allow \
H A Dtrs_aesgcm_defs.sh15 dir out ptype main action allow \
20 dir in ptype main action allow \
46 dir out ptype main action allow \
51 dir in ptype main action allow \
H A Dtrs_aesctr_sha1_defs.sh15 dir out ptype main action allow \
20 dir in ptype main action allow \
46 dir out ptype main action allow \
51 dir in ptype main action allow \
H A Dtrs_aescbc_sha1_defs.sh15 dir out ptype main action allow \
20 dir in ptype main action allow \
46 dir out ptype main action allow \
51 dir in ptype main action allow \
/dpdk/lib/node/
H A Dethdev_rx.c55 l3_ptype(uint16_t etype, uint32_t ptype) in l3_ptype() argument
57 ptype = ptype & ~RTE_PTYPE_L3_MASK; in l3_ptype()
59 ptype |= RTE_PTYPE_L3_IPV4_EXT_UNKNOWN; in l3_ptype()
61 ptype |= RTE_PTYPE_L3_IPV6_EXT_UNKNOWN; in l3_ptype()
62 return ptype; in l3_ptype()
/dpdk/drivers/net/cnxk/
H A Dcnxk_lookup.c71 nix_create_non_tunnel_ptype_array(uint16_t *ptype) in nix_create_non_tunnel_ptype_array() argument
174 ptype[idx] = val; in nix_create_non_tunnel_ptype_array()
180 nix_create_tunnel_ptype_array(uint16_t *ptype) in nix_create_tunnel_ptype_array() argument
187 ptype = ptype + PTYPE_NON_TUNNEL_ARRAY_SZ; in nix_create_tunnel_ptype_array()
224 ptype[idx] = val; in nix_create_tunnel_ptype_array()
/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_packed.h160 uint32_t hdrlen, ptype; in virtio_vec_rx_offload() local
170 ptype = rte_net_get_ptype(m, &hdr_lens, RTE_PTYPE_ALL_MASK); in virtio_vec_rx_offload()
171 m->packet_type = ptype; in virtio_vec_rx_offload()
172 if ((ptype & RTE_PTYPE_L4_MASK) == RTE_PTYPE_L4_TCP || in virtio_vec_rx_offload()
173 (ptype & RTE_PTYPE_L4_MASK) == RTE_PTYPE_L4_UDP || in virtio_vec_rx_offload()
174 (ptype & RTE_PTYPE_L4_MASK) == RTE_PTYPE_L4_SCTP) in virtio_vec_rx_offload()
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_sse.h383 __m128i pinfo, ptype; in rxq_cq_to_ptype_oflags_v() local
416 ptype = _mm_unpacklo_epi64(pinfo0, pinfo1); in rxq_cq_to_ptype_oflags_v()
449 ptype = _mm_and_si128(ptype, ptype_mask); in rxq_cq_to_ptype_oflags_v()
453 pinfo = _mm_or_si128(ptype, pinfo); in rxq_cq_to_ptype_oflags_v()
454 ptype = _mm_srli_epi32(pinfo, 10); in rxq_cq_to_ptype_oflags_v()
455 ptype = _mm_packs_epi32(ptype, zero); in rxq_cq_to_ptype_oflags_v()
458 ptype = _mm_or_si128(ptype, op_err); in rxq_cq_to_ptype_oflags_v()
459 pt_idx0 = _mm_extract_epi8(ptype, 0); in rxq_cq_to_ptype_oflags_v()
460 pt_idx1 = _mm_extract_epi8(ptype, 2); in rxq_cq_to_ptype_oflags_v()
461 pt_idx2 = _mm_extract_epi8(ptype, 4); in rxq_cq_to_ptype_oflags_v()
[all …]
/dpdk/drivers/net/hns3/
H A Dhns3_rxtx.c2098 uint32_t *ptype = tbl->ptype; in hns3_init_adv_layout_ptype() local
2101 ptype[1] = RTE_PTYPE_L2_ETHER_ARP; in hns3_init_adv_layout_ptype()
2102 ptype[3] = RTE_PTYPE_L2_ETHER_LLDP; in hns3_init_adv_layout_ptype()
2103 ptype[8] = RTE_PTYPE_L2_ETHER_TIMESYNC; in hns3_init_adv_layout_ptype()
2106 ptype[17] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
2108 ptype[18] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
2110 ptype[19] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
2112 ptype[20] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
2114 ptype[21] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
2116 ptype[22] = RTE_PTYPE_L2_ETHER | RTE_PTYPE_L3_IPV4_EXT_UNKNOWN | in hns3_init_adv_layout_ptype()
[all …]
/dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_neon.c90 uint8x16_t ptype, udp_csum_skip; in desc_to_olflags_v() local
161 ptype = vzipq_u8(sterr_tmp1.val[0], sterr_tmp2.val[0]).val[0]; in desc_to_olflags_v()
164 udp_csum_skip = vandq_u8(ptype, udp_hdr_p_msk); in desc_to_olflags_v()
170 ptype = vandq_u8(ptype, rsstype_msk); in desc_to_olflags_v()
171 ptype = vqtbl1q_u8(rss_flags, ptype); in desc_to_olflags_v()
194 vtag_lo = vorrq_u8(ptype, vtag_lo); in desc_to_olflags_v()
/dpdk/examples/l3fwd/
H A Dl3fwd_common.h31 rfc1812_process(struct rte_ipv4_hdr *ipv4_hdr, uint16_t *dp, uint32_t ptype) in rfc1812_process() argument
35 if (RTE_ETH_IS_IPV4_HDR(ptype)) { in rfc1812_process()
50 #define rfc1812_process(mb, dp, ptype) do { } while (0) argument

123