Home
last modified time | relevance | path

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

1234

/f-stack/dpdk/lib/librte_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 …]
/f-stack/dpdk/lib/librte_gro/
H A Drte_gro.c34 #define IS_IPV4_TCP_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
36 (RTE_ETH_IS_TUNNEL_PKT(ptype) == 0))
38 #define IS_IPV4_UDP_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
40 (RTE_ETH_IS_TUNNEL_PKT(ptype) == 0))
42 #define IS_IPV4_VXLAN_TCP4_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
44 ((ptype & RTE_PTYPE_TUNNEL_VXLAN) == \
46 ((ptype & RTE_PTYPE_INNER_L4_TCP) == \
48 (((ptype & RTE_PTYPE_INNER_L3_MASK) == \
55 #define IS_IPV4_VXLAN_UDP4_PKT(ptype) (RTE_ETH_IS_IPV4_HDR(ptype) && \ argument
57 ((ptype & RTE_PTYPE_TUNNEL_VXLAN) == \
[all …]
/f-stack/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 …]
/f-stack/dpdk/drivers/net/sfc/
H A Dsfc_ef100_rx.c217 uint32_t ptype; in sfc_ef100_rx_class_decode() local
226 ptype = RTE_PTYPE_L2_ETHER; in sfc_ef100_rx_class_decode()
229 ptype = RTE_PTYPE_L2_ETHER_VLAN; in sfc_ef100_rx_class_decode()
232 ptype = RTE_PTYPE_L2_ETHER_QINQ; in sfc_ef100_rx_class_decode()
245 ptype |= RTE_PTYPE_TUNNEL_NVGRE; in sfc_ef100_rx_class_decode()
284 ptype |= RTE_PTYPE_L4_TCP; in sfc_ef100_rx_class_decode()
289 ptype |= RTE_PTYPE_L4_UDP; in sfc_ef100_rx_class_decode()
294 ptype |= RTE_PTYPE_L4_FRAG; in sfc_ef100_rx_class_decode()
337 ptype |= RTE_PTYPE_INNER_L4_TCP; in sfc_ef100_rx_class_decode()
342 ptype |= RTE_PTYPE_INNER_L4_UDP; in sfc_ef100_rx_class_decode()
[all …]
/f-stack/dpdk/drivers/net/ice/
H A Dice_fdir_filter.c182 ptype++) { in ice_fdir_prof_alloc()
194 fltr_ptype < ptype; in ice_fdir_prof_alloc()
569 ptype++) { in ice_fdir_prof_free()
599 vsi_num, ptype); in ice_fdir_prof_rm()
622 ptype++) { in ice_fdir_prof_rm_all()
698 ptype); in ice_fdir_cur_prof_conflict()
705 ptype); in ice_fdir_cur_prof_conflict()
747 switch (ptype) { in ice_fdir_cross_prof_conflict()
864 ptype); in ice_fdir_hw_tbl_conf()
872 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()
1010 enum ice_fltr_ptype ptype; in ice_acl_prof_free() local
1012 for (ptype = ICE_FLTR_PTYPE_NONF_NONE + 1; in ice_acl_prof_free()
1013 ptype < ICE_FLTR_PTYPE_MAX; ptype++) { in ice_acl_prof_free()
1014 rte_free(hw->acl_prof[ptype]); in ice_acl_prof_free()
[all …]
/f-stack/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 …]
/f-stack/dpdk/drivers/net/txgbe/
H A Dtxgbe_ptypes.c213 txgbe_encode_ptype_fcoe(u32 ptype) in txgbe_encode_ptype_fcoe() argument
217 UNREFERENCED_PARAMETER(ptype); in txgbe_encode_ptype_fcoe()
224 txgbe_encode_ptype_mac(u32 ptype) in txgbe_encode_ptype_mac() argument
230 switch (ptype & RTE_PTYPE_L2_MASK) { in txgbe_encode_ptype_mac()
254 txgbe_encode_ptype_ip(u32 ptype) in txgbe_encode_ptype_ip() argument
260 switch (ptype & RTE_PTYPE_L3_MASK) { in txgbe_encode_ptype_ip()
296 txgbe_encode_ptype_tunnel(u32 ptype) in txgbe_encode_ptype_tunnel() argument
390 u8 txgbe_encode_ptype(u32 ptype) in txgbe_encode_ptype() argument
394 if (ptype & RTE_PTYPE_TUNNEL_MASK) in txgbe_encode_ptype()
396 else if (ptype & RTE_PTYPE_L3_MASK) in txgbe_encode_ptype()
[all …]
/f-stack/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_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 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 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_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_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 \
/f-stack/dpdk/lib/librte_node/
H A Dethdev_rx.c56 l3_ptype(uint16_t etype, uint32_t ptype) in l3_ptype() argument
58 ptype = ptype & ~RTE_PTYPE_L3_MASK; in l3_ptype()
60 ptype |= RTE_PTYPE_L3_IPV4_EXT_UNKNOWN; in l3_ptype()
62 ptype |= RTE_PTYPE_L3_IPV6_EXT_UNKNOWN; in l3_ptype()
63 return ptype; in l3_ptype()
/f-stack/dpdk/drivers/net/octeontx2/
H A Dotx2_lookup.c97 nix_create_non_tunnel_ptype_array(uint16_t *ptype) in nix_create_non_tunnel_ptype_array() argument
200 ptype[idx] = val; in nix_create_non_tunnel_ptype_array()
206 nix_create_tunnel_ptype_array(uint16_t *ptype) in nix_create_tunnel_ptype_array() argument
213 ptype = ptype + PTYPE_NON_TUNNEL_ARRAY_SZ; in nix_create_tunnel_ptype_array()
250 ptype[idx] = val; in nix_create_tunnel_ptype_array()
/f-stack/freebsd/sys/
H A Dlinker_set.h87 #define SET_DECLARE(set, ptype) \ argument
88 extern ptype __weak_symbol *__CONCAT(__start_set_,set); \
89 extern ptype __weak_symbol *__CONCAT(__stop_set_,set)
/f-stack/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 …]
H A Dmlx5_rxtx_vec_altivec.h531 vector unsigned char pinfo, ptype; in rxq_cq_to_ptype_oflags_v() local
595 ptype = (vector unsigned char) in rxq_cq_to_ptype_oflags_v()
652 ptype = (vector unsigned char) in rxq_cq_to_ptype_oflags_v()
653 vec_and((vector unsigned long)ptype, in rxq_cq_to_ptype_oflags_v()
664 vec_or((vector unsigned long)ptype, in rxq_cq_to_ptype_oflags_v()
666 ptype = (vector unsigned char) in rxq_cq_to_ptype_oflags_v()
669 ptype = (vector unsigned char) in rxq_cq_to_ptype_oflags_v()
670 vec_packs((vector unsigned int)ptype, in rxq_cq_to_ptype_oflags_v()
677 ptype = (vector unsigned char) in rxq_cq_to_ptype_oflags_v()
678 vec_or((vector unsigned long)ptype, in rxq_cq_to_ptype_oflags_v()
[all …]
/f-stack/app/redis-5.0.5/src/
H A Dchildinfo.c62 void sendChildInfo(int ptype) { in sendChildInfo() argument
65 server.child_info_data.process_type = ptype; in sendChildInfo()
/f-stack/dpdk/lib/librte_eal/windows/
H A Deal.c41 enum rte_proc_type_t ptype = RTE_PROC_PRIMARY; in eal_proc_type_detect() local
61 ptype = RTE_PROC_SECONDARY; in eal_proc_type_detect()
65 ptype == RTE_PROC_PRIMARY ? "PRIMARY" : "SECONDARY"); in eal_proc_type_detect()
67 return ptype; in eal_proc_type_detect()
/f-stack/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

1234