Home
last modified time | relevance | path

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

123456

/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_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 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 Drun_test.sh211 ipv4-ipv6 ${i}
221 /bin/bash ${DIR}/load_env.sh ${options} ipv6-ipv6 ${i}
227 ipv6-ipv4 ${i}
/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
105 if (cmp_sa_key(cached_sa, 1, ipv4, ipv6)) { in sad_lookup()
125 if (cmp_sa_key(cached_sa, 0, ipv4, ipv6)) { in sad_lookup()
131 memcpy(v6[nb_v6].dip, ipv6->dst_addr, in sad_lookup()
132 sizeof(ipv6->dst_addr)); in sad_lookup()
133 memcpy(v6[nb_v6].sip, ipv6->src_addr, in sad_lookup()
134 sizeof(ipv6->src_addr)); in sad_lookup()
158 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()
237 pattern[1].spec = &rule->ipv6.spec; in flow_init_single()
238 pattern[1].mask = &rule->ipv6.mask; in flow_init_single()
275 ipv6_hdr_print(&rule->ipv6.spec.hdr); in flow_init()
278 ipv6_hdr_print(&rule->ipv6.mask.hdr); in flow_init()
/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 …]
/dpdk/drivers/net/txgbe/
H A Dtxgbe_ipsec.c15 (a).ipv6[0] == (b).ipv6[0] && \
16 (a).ipv6[1] == (b).ipv6[1] && \
17 (a).ipv6[2] == (b).ipv6[2] && \
18 (a).ipv6[3] == (b).ipv6[3])
121 priv->rx_ip_tbl[ip_index].ip.ipv6[0] = in txgbe_crypto_add_sa()
122 ic_session->dst_ip.ipv6[0]; in txgbe_crypto_add_sa()
124 ic_session->dst_ip.ipv6[1]; in txgbe_crypto_add_sa()
126 ic_session->dst_ip.ipv6[2]; in txgbe_crypto_add_sa()
128 ic_session->dst_ip.ipv6[3]; in txgbe_crypto_add_sa()
673 ipv6->hdr.src_addr, 16); in txgbe_crypto_add_ingress_sa_from_flow()
[all …]
/dpdk/lib/hash/
H A Drte_thash.h143 __m128i ipv6 = _mm_loadu_si128((const __m128i *)orig->src_addr); in rte_thash_load_v6_addrs() local
145 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask); in rte_thash_load_v6_addrs()
146 ipv6 = _mm_loadu_si128((const __m128i *)orig->dst_addr); in rte_thash_load_v6_addrs()
148 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask); in rte_thash_load_v6_addrs()
150 uint8x16_t ipv6 = vld1q_u8((uint8_t const *)orig->src_addr); in rte_thash_load_v6_addrs()
151 vst1q_u8((uint8_t *)targ->v6.src_addr, vrev32q_u8(ipv6)); in rte_thash_load_v6_addrs()
152 ipv6 = vld1q_u8((uint8_t const *)orig->dst_addr); in rte_thash_load_v6_addrs()
153 vst1q_u8((uint8_t *)targ->v6.dst_addr, vrev32q_u8(ipv6)); in rte_thash_load_v6_addrs()
/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()
/dpdk/drivers/net/iavf/
H A Drte_pmd_iavf.h59 } ipv6; member
216 data.ipv6.version, in rte_pmd_ifd_dump_proto_xtr_metadata()
217 data.ipv6.tc, in rte_pmd_ifd_dump_proto_xtr_metadata()
218 data.ipv6.flowhi4, in rte_pmd_ifd_dump_proto_xtr_metadata()
219 data.ipv6.nexthdr, in rte_pmd_ifd_dump_proto_xtr_metadata()
220 data.ipv6.hoplimit); in rte_pmd_ifd_dump_proto_xtr_metadata()
/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 …]
/dpdk/drivers/net/mlx5/
H A Dmlx5_flow_verbs.c603 struct ibv_flow_spec_ipv6 ipv6 = { in flow_verbs_translate_item_ipv6() local
616 RTE_DIM(ipv6.val.src_ip)); in flow_verbs_translate_item_ipv6()
618 RTE_DIM(ipv6.val.dst_ip)); in flow_verbs_translate_item_ipv6()
625 ipv6.val.flow_label = in flow_verbs_translate_item_ipv6()
631 ipv6.mask.flow_label = in flow_verbs_translate_item_ipv6()
639 ipv6.val.src_ip[i] &= ipv6.mask.src_ip[i]; in flow_verbs_translate_item_ipv6()
640 ipv6.val.dst_ip[i] &= ipv6.mask.dst_ip[i]; in flow_verbs_translate_item_ipv6()
642 ipv6.val.flow_label &= ipv6.mask.flow_label; in flow_verbs_translate_item_ipv6()
643 ipv6.val.traffic_class &= ipv6.mask.traffic_class; in flow_verbs_translate_item_ipv6()
644 ipv6.val.next_hdr &= ipv6.mask.next_hdr; in flow_verbs_translate_item_ipv6()
[all …]
/dpdk/drivers/net/cnxk/
H A Dcnxk_ethdev_sec_telemetry.c109 for (j = 0; j < RTE_DIM(out_sa->outer_hdr.ipv6.src_addr); j++) in copy_outb_sa_10k()
111 out_sa->outer_hdr.ipv6.src_addr[j]); in copy_outb_sa_10k()
113 for (j = 0; j < RTE_DIM(out_sa->outer_hdr.ipv6.dst_addr); j++) in copy_outb_sa_10k()
115 out_sa->outer_hdr.ipv6.dst_addr[j]); in copy_outb_sa_10k()
182 for (j = 0; j < RTE_DIM(in_sa->outer_hdr.ipv6.src_addr); j++) in copy_inb_sa_10k()
184 in_sa->outer_hdr.ipv6.src_addr[j]); in copy_inb_sa_10k()
186 for (j = 0; j < RTE_DIM(in_sa->outer_hdr.ipv6.dst_addr); j++) in copy_inb_sa_10k()
188 in_sa->outer_hdr.ipv6.dst_addr[j]); in copy_inb_sa_10k()
/dpdk/app/test/
H A Dtest_cmdline_ipaddr.c31 #define IP6(a,b,c,d,e,f,g,h) .ipv6 = \
277 NIP6(addr.addr.ipv6), addr.prefixlen); in dump_addr()
306 if (memcmp(&addr1.addr.ipv6, &addr2.addr.ipv6, in is_addr_different()
479 memcmp(&result.addr.ipv6, &tmp.addr.ipv6, sizeof(struct in6_addr))) { in test_parse_ipaddr_valid()
564 memcmp(&result.addr.ipv6, &tmp.addr.ipv6, sizeof(struct in6_addr))) { in test_parse_ipaddr_valid()
H A Dtest_ipsec_sad.c153 __test_add_invalid(int ipv6, union rte_ipsec_sad_key *tuple) in __test_add_invalid() argument
172 if (ipv6) in __test_add_invalid()
228 __test_delete_invalid(int ipv6, union rte_ipsec_sad_key *tuple) in __test_delete_invalid() argument
244 if (ipv6) in __test_delete_invalid()
304 if (ipv6) in __test_lookup_invalid()
346 __test_lookup_basic(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_basic() argument
362 if (ipv6) in __test_lookup_basic()
425 __test_lookup_adv(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_adv() argument
440 if (ipv6) in __test_lookup_adv()
689 __test_lookup_order(int ipv6, union rte_ipsec_sad_key *tuple, in __test_lookup_order() argument
[all …]
/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()

123456