Home
last modified time | relevance | path

Searched refs:ipv6 (Results 1 – 25 of 120) sorted by relevance

12345

/f-stack/dpdk/examples/ipsec-secgw/
H A Dsad.h30 struct rte_ipv6_hdr *ipv6) in cmp_sa_key() argument
41 (!memcmp(sa->dst.ip.ip6.ip6, ipv6->dst_addr, 16)))) in cmp_sa_key()
68 struct rte_ipv6_hdr *ipv6; in sad_lookup() local
100 if (cmp_sa_key(cached_sa, 1, ipv4, ipv6)) { in sad_lookup()
120 if (cmp_sa_key(cached_sa, 0, ipv4, ipv6)) { in sad_lookup()
126 memcpy(v6[nb_v6].dip, ipv6->dst_addr, in sad_lookup()
127 sizeof(ipv6->dst_addr)); in sad_lookup()
128 memcpy(v6[nb_v6].sip, ipv6->src_addr, in sad_lookup()
129 sizeof(ipv6->src_addr)); in sad_lookup()
153 ipv6 = rte_pktmbuf_mtod(pkts[v6_idxes[i]], in sad_lookup()
[all …]
H A Dep0.cfg93 c3:c3:c3:c3:c3:c3:c3:c3:c3 mode ipv6-tunnel \
99 4d:4d:4d:4d:4d:4d:4d:4d:4d mode ipv6-tunnel \
129 c3:c3:c3:c3:c3:c3:c3:c3:c3 mode ipv6-tunnel \
135 4d:4d:4d:4d:4d:4d:4d:4d:4d mode ipv6-tunnel \
139 sa in 127 cipher_algo null auth_algo null mode ipv6-tunnel \
162 rt ipv6 dst 2222:2222:2222:2222:2222:2222:2222:5555/116 port 0
163 rt ipv6 dst 2222:2222:2222:2222:2222:2222:2222:6666/116 port 1
164 rt ipv6 dst 0000:0000:1111:1111:0000:0000:0000:0000/116 port 0
165 rt ipv6 dst 0000:0000:1111:1111:1111:1111:0000:0000/116 port 1
166 rt ipv6 dst ffff:0000:0000:0000:aaaa:aaaa:0000:0000/116 port 2
[all …]
H A Dep1.cfg90 c3:c3:c3:c3:c3:c3:c3:c3:c3 mode ipv6-tunnel \
96 4d:4d:4d:4d:4d:4d:4d:4d:4d mode ipv6-tunnel \
123 c3:c3:c3:c3:c3:c3:c3:c3:c3 mode ipv6-tunnel \
129 4d:4d:4d:4d:4d:4d:4d:4d:4d mode ipv6-tunnel \
151 rt ipv6 dst 1111:1111:1111:1111:1111:1111:1111:5555/116 port 0
152 rt ipv6 dst 1111:1111:1111:1111:1111:1111:1111:6666/116 port 1
153 rt ipv6 dst ffff:0000:1111:1111:0000:0000:0000:0000/116 port 0
154 rt ipv6 dst ffff:0000:1111:1111:1111:1111:0000:0000/116 port 1
155 rt ipv6 dst 0000:0000:0000:0000:aaaa:aaaa:0000:0000/116 port 2
156 rt ipv6 dst 0000:0000:0000:0000:bbbb:bbbb:0000:0000/116 port 3
[all …]
H A Dflow.c28 } ipv6; member
158 if (ipv6_addr_cpy(rule->ipv6.spec.hdr.src_addr, in parse_flow_tokens()
159 rule->ipv6.mask.hdr.src_addr, in parse_flow_tokens()
175 if (ipv6_addr_cpy(rule->ipv6.spec.hdr.dst_addr, in parse_flow_tokens()
176 rule->ipv6.mask.hdr.dst_addr, in parse_flow_tokens()
235 pattern[1].spec = &rule->ipv6.spec; in flow_init_single()
236 pattern[1].mask = &rule->ipv6.mask; in flow_init_single()
273 ipv6_hdr_print(&rule->ipv6.spec.hdr); in flow_init()
276 ipv6_hdr_print(&rule->ipv6.mask.hdr); in flow_init()
/f-stack/dpdk/examples/ipsec-secgw/test/
H A Dtun_aesgcm_common_defs.sh21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
37 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
46 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6} ${SGW_CFG_XPRM_OUT}
52 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
53 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
79 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
84 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
108 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
H A Dtun_aescbc_sha1_common_defs.sh23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
41 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
60 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
61 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
87 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
92 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
105 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6}
118 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6}
124 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
H A Dtun_3descbc_sha1_common_defs.sh23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
43 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
64 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
65 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
91 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
96 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
111 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6}
126 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6}
132 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
H A Dtun_aesctr_sha1_common_defs.sh23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
41 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6} ${SGW_CFG_XPRM_IN}
60 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
61 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
87 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
92 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
105 mode ipv6-tunnel src ${REMOTE_IPV6} dst ${LOCAL_IPV6}
118 mode ipv6-tunnel src ${LOCAL_IPV6} dst ${REMOTE_IPV6}
124 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
[all …]
H A Dtrs_aesgcm_common_defs.sh21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
52 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
53 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
H A Dbypass_defs.sh12 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
15 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
21 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
22 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
H A Dtrs_aescbc_sha1_common_defs.sh21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
61 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
62 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
H A Dtrs_3descbc_sha1_common_defs.sh21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
65 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
66 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
H A Dtrs_aesctr_sha1_common_defs.sh21 sp ipv6 in esp protect 9 pri 2 src ${REMOTE_IPV6}/128 dst ${LOCAL_IPV6}/128 \
23 sp ipv6 in esp bypass pri 1 sport 0:65535 dport 0:65535
26 sp ipv6 out esp protect 9 pri 2 src ${LOCAL_IPV6}/128 dst ${REMOTE_IPV6}/128 \
28 sp ipv6 out esp bypass pri 1 sport 0:65535 dport 0:65535
61 rt ipv6 dst ${REMOTE_IPV6}/128 port 0
62 rt ipv6 dst ${LOCAL_IPV6}/128 port 1
H A Drun_test.sh211 ipv4-ipv6 ${i}
221 /bin/bash ${DIR}/load_env.sh ${options} ipv6-ipv6 ${i}
227 ipv6-ipv4 ${i}
H A Dcommon_defs.sh159 sysctl -w net.ipv6.conf.${LOCAL_IFACE}.mtu=${mtu}
177 sysctl -w net.ipv6.conf.${LOCAL_IFACE}.disable_ipv6=0
205 net.ipv6.conf.${REMOTE_IFACE}.disable_ipv6=0
/f-stack/dpdk/lib/librte_hash/
H A Drte_thash.h146 __m128i ipv6 = _mm_loadu_si128((const __m128i *)orig->src_addr); in rte_thash_load_v6_addrs() local
148 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask); in rte_thash_load_v6_addrs()
149 ipv6 = _mm_loadu_si128((const __m128i *)orig->dst_addr); in rte_thash_load_v6_addrs()
151 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask); in rte_thash_load_v6_addrs()
153 uint8x16_t ipv6 = vld1q_u8((uint8_t const *)orig->src_addr); in rte_thash_load_v6_addrs()
154 vst1q_u8((uint8_t *)targ->v6.src_addr, vrev32q_u8(ipv6)); in rte_thash_load_v6_addrs()
155 ipv6 = vld1q_u8((uint8_t const *)orig->dst_addr); in rte_thash_load_v6_addrs()
156 vst1q_u8((uint8_t *)targ->v6.dst_addr, vrev32q_u8(ipv6)); in rte_thash_load_v6_addrs()
/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_ipsec.c34 (a).ipv6[0] == (b).ipv6[0] && \
35 (a).ipv6[1] == (b).ipv6[1] && \
36 (a).ipv6[2] == (b).ipv6[2] && \
37 (a).ipv6[3] == (b).ipv6[3])
141 priv->rx_ip_tbl[ip_index].ip.ipv6[0] = in ixgbe_crypto_add_sa()
142 ic_session->dst_ip.ipv6[0]; in ixgbe_crypto_add_sa()
144 ic_session->dst_ip.ipv6[1]; in ixgbe_crypto_add_sa()
146 ic_session->dst_ip.ipv6[2]; in ixgbe_crypto_add_sa()
148 ic_session->dst_ip.ipv6[3]; in ixgbe_crypto_add_sa()
697 ipv6->hdr.src_addr, 16); in ixgbe_crypto_add_ingress_sa_from_flow()
[all …]
/f-stack/dpdk/drivers/net/iavf/
H A Drte_pmd_iavf.h59 } ipv6; member
215 data.ipv6.version, in rte_pmd_ifd_dump_proto_xtr_metadata()
216 data.ipv6.tc, in rte_pmd_ifd_dump_proto_xtr_metadata()
217 data.ipv6.flowhi4, in rte_pmd_ifd_dump_proto_xtr_metadata()
218 data.ipv6.nexthdr, in rte_pmd_ifd_dump_proto_xtr_metadata()
219 data.ipv6.hoplimit); in rte_pmd_ifd_dump_proto_xtr_metadata()
/f-stack/dpdk/drivers/net/ice/
H A Drte_pmd_ice.h59 } ipv6; member
211 data.ipv6.version, in rte_net_ice_dump_proto_xtr_metadata()
212 data.ipv6.tc, in rte_net_ice_dump_proto_xtr_metadata()
213 data.ipv6.flowhi4, in rte_net_ice_dump_proto_xtr_metadata()
214 data.ipv6.nexthdr, in rte_net_ice_dump_proto_xtr_metadata()
215 data.ipv6.hoplimit); in rte_net_ice_dump_proto_xtr_metadata()
/f-stack/dpdk/app/test-sad/
H A Dmain.c53 int ipv6; member
71 .ipv6 = 0,
190 if (config.ipv6) in parse_file()
198 if (config.ipv6) in parse_file()
248 if (config.ipv6) { in get_random_rules()
274 if (config.ipv6) { in get_random_rules()
289 if (config.ipv6) { in get_random_rules()
416 config.ipv6 = 1; in parse_opts()
470 af = (config.ipv6) ? AF_INET6 : AF_INET; in print_result()
473 spi = (config.ipv6 == 0) ? v4->spi : v6->spi; in print_result()
[all …]
/f-stack/dpdk/drivers/net/mlx5/
H A Dmlx5_flow_verbs.c656 struct ibv_flow_spec_ipv6 ipv6 = { in flow_verbs_translate_item_ipv6() local
669 RTE_DIM(ipv6.val.src_ip)); in flow_verbs_translate_item_ipv6()
671 RTE_DIM(ipv6.val.dst_ip)); in flow_verbs_translate_item_ipv6()
678 ipv6.val.flow_label = in flow_verbs_translate_item_ipv6()
684 ipv6.mask.flow_label = in flow_verbs_translate_item_ipv6()
692 ipv6.val.src_ip[i] &= ipv6.mask.src_ip[i]; in flow_verbs_translate_item_ipv6()
693 ipv6.val.dst_ip[i] &= ipv6.mask.dst_ip[i]; in flow_verbs_translate_item_ipv6()
695 ipv6.val.flow_label &= ipv6.mask.flow_label; in flow_verbs_translate_item_ipv6()
696 ipv6.val.traffic_class &= ipv6.mask.traffic_class; in flow_verbs_translate_item_ipv6()
697 ipv6.val.next_hdr &= ipv6.mask.next_hdr; in flow_verbs_translate_item_ipv6()
[all …]
/f-stack/dpdk/app/test/
H A Dtest_cmdline_ipaddr.c30 #define IP6(a,b,c,d,e,f,g,h) .ipv6 = \
278 NIP6(addr.addr.ipv6), addr.prefixlen); in dump_addr()
307 if (memcmp(&addr1.addr.ipv6, &addr2.addr.ipv6, in is_addr_different()
480 memcmp(&result.addr.ipv6, &tmp.addr.ipv6, sizeof(struct in6_addr))) { in test_parse_ipaddr_valid()
565 memcmp(&result.addr.ipv6, &tmp.addr.ipv6, sizeof(struct in6_addr))) { in test_parse_ipaddr_valid()
H A Dtest_ipsec_sad.c142 __test_add_invalid(int ipv6, union rte_ipsec_sad_key *tuple) in __test_add_invalid() argument
161 if (ipv6) in __test_add_invalid()
217 __test_delete_invalid(int ipv6, union rte_ipsec_sad_key *tuple) in __test_delete_invalid() argument
233 if (ipv6) in __test_delete_invalid()
293 if (ipv6) in __test_lookup_invalid()
335 __test_lookup_basic(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_basic() argument
351 if (ipv6) in __test_lookup_basic()
414 __test_lookup_adv(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_adv() argument
429 if (ipv6) in __test_lookup_adv()
678 __test_lookup_order(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_order() argument
[all …]
/f-stack/dpdk/app/test-pmd/
H A D5tswap.c102 struct rte_ipv6_hdr *ipv6; in pkt_burst_5tuple_swap() member
148 swap_ipv6(h.ipv6); in pkt_burst_5tuple_swap()
149 next_proto = h.ipv6->proto; in pkt_burst_5tuple_swap()
150 h.ipv6++; in pkt_burst_5tuple_swap()
/f-stack/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_flow.c133 struct rte_flow_item_ipv6 ipv6; member
733 ip_proto = spec.ipv6.hdr.proto; in flow_rule_match_acl_get()
734 ip_proto_mask = mask.ipv6.hdr.proto; in flow_rule_match_acl_get()
737 memcpy(rule_match->match.acl.ipv6.sa, in flow_rule_match_acl_get()
738 spec.ipv6.hdr.src_addr, in flow_rule_match_acl_get()
739 sizeof(spec.ipv6.hdr.src_addr)); in flow_rule_match_acl_get()
741 spec.ipv6.hdr.dst_addr, in flow_rule_match_acl_get()
742 sizeof(spec.ipv6.hdr.dst_addr)); in flow_rule_match_acl_get()
1749 &spec.ipv6.hdr.src_addr, in flow_rule_action_get()
1752 &spec.ipv6.hdr.dst_addr, in flow_rule_action_get()
[all …]

12345