Home
last modified time | relevance | path

Searched refs:dst_addr (Results 1 – 25 of 151) sorted by relevance

1234567

/dpdk/lib/hash/
H A Drte_thash.h74 uint32_t dst_addr; member
92 uint8_t dst_addr[16]; member
146 ipv6 = _mm_loadu_si128((const __m128i *)orig->dst_addr); in rte_thash_load_v6_addrs()
147 *(__m128i *)targ->v6.dst_addr = 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()
159 *((uint32_t *)targ->v6.dst_addr + i) = in rte_thash_load_v6_addrs()
160 rte_be_to_cpu_32(*((const uint32_t *)orig->dst_addr + i)); in rte_thash_load_v6_addrs()
/dpdk/app/test-pmd/
H A Dicmpecho.c322 ether_addr_dump(" dst=", &eth_h->dst_addr); in reply_to_icmp_echo_rqsts()
387 rte_ether_addr_copy(&eth_h->src_addr, &eth_h->dst_addr); in reply_to_icmp_echo_rqsts()
415 ipv4_addr_dump(" dst=", ip_h->dst_addr); in reply_to_icmp_echo_rqsts()
456 rte_ether_addr_copy(&eth_h->dst_addr, &eth_h->src_addr); in reply_to_icmp_echo_rqsts()
457 rte_ether_addr_copy(&eth_addr, &eth_h->dst_addr); in reply_to_icmp_echo_rqsts()
459 if (is_multicast_ipv4_addr(ip_h->dst_addr)) { in reply_to_icmp_echo_rqsts()
468 ip_h->dst_addr = ip_addr; in reply_to_icmp_echo_rqsts()
471 ip_h->src_addr = ip_h->dst_addr; in reply_to_icmp_echo_rqsts()
472 ip_h->dst_addr = ip_addr; in reply_to_icmp_echo_rqsts()
H A D5tswap.c30 rte_ether_addr_copy(&eth_hdr->dst_addr, &addr); in swap_mac()
31 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in swap_mac()
42 ipv4_hdr->src_addr = ipv4_hdr->dst_addr; in swap_ipv4()
43 ipv4_hdr->dst_addr = addr; in swap_ipv4()
53 memcpy(&ipv6_hdr->src_addr, &ipv6_hdr->dst_addr, 16); in swap_ipv6()
54 memcpy(&ipv6_hdr->dst_addr, &addr, 16); in swap_ipv6()
H A Dmacswap.h32 rte_ether_addr_copy(&eth_hdr->dst_addr, &addr); in do_macswap()
33 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in do_macswap()
/dpdk/app/test/
H A Dpacket_burst_generator.c60 rte_ether_addr_copy(dst_mac, &eth_hdr->dst_addr); in initialize_eth_header()
144 uint8_t *dst_addr, uint16_t pkt_data_len) in initialize_ipv6_header() argument
152 rte_memcpy(ip_hdr->dst_addr, dst_addr, sizeof(ip_hdr->dst_addr)); in initialize_ipv6_header()
159 uint32_t dst_addr, uint16_t pkt_data_len) in initialize_ipv4_header() argument
178 ip_hdr->dst_addr = rte_cpu_to_be_32(dst_addr); in initialize_ipv4_header()
207 uint32_t dst_addr, uint16_t pkt_data_len, uint8_t proto) in initialize_ipv4_header_proto() argument
226 ip_hdr->dst_addr = rte_cpu_to_be_32(dst_addr); in initialize_ipv4_header_proto()
H A Dtest_acl.h34 uint32_t dst_addr; /**< IPv4 destination address. */ member
91 .dst_addr = RTE_IPV4(10,0,0,0),
145 .dst_addr = RTE_IPV4(192,168,0,0),
156 .dst_addr = RTE_IPV4(192,168,1,0),
167 .dst_addr = RTE_IPV4(192,168,1,50),
396 .dst_addr = RTE_IPV4(1,2,3,4),
414 .dst_addr = RTE_IPV4(5,6,7,8),
432 .dst_addr = RTE_IPV4(1,2,3,4),
448 .dst_addr = RTE_IPV4(5,6,7,8),
H A Dpacket_burst_generator.h51 uint8_t *dst_addr, uint16_t pkt_data_len);
55 uint32_t dst_addr, uint16_t pkt_data_len);
59 uint32_t dst_addr, uint16_t pkt_data_len, uint8_t proto);
H A Dtest_thash.c126 tuple.v4.dst_addr = v4_tbl[i].dst_ip; in test_toeplitz_hash_calc()
150 for (j = 0; j < RTE_DIM(ipv6_hdr.dst_addr); j++) in test_toeplitz_hash_calc()
151 ipv6_hdr.dst_addr[j] = v6_tbl[i].dst_ip[j]; in test_toeplitz_hash_calc()
193 tuple.v4.dst_addr = rte_cpu_to_be_32(v4_tbl[i].dst_ip); in test_toeplitz_hash_gfni()
209 for (j = 0; j < RTE_DIM(tuple.v6.dst_addr); j++) in test_toeplitz_hash_gfni()
210 tuple.v6.dst_addr[j] = v6_tbl[i].dst_ip[j]; in test_toeplitz_hash_gfni()
325 tuple[0].v4.dst_addr = rte_cpu_to_be_32(v4_tbl[i].dst_ip); in test_toeplitz_hash_gfni_bulk()
333 for (j = 0; j < RTE_DIM(tuple[1].v6.dst_addr); j++) in test_toeplitz_hash_gfni_bulk()
334 tuple[1].v6.dst_addr[j] = v6_tbl[i].dst_ip[j]; in test_toeplitz_hash_gfni_bulk()
604 tuple.v4.dst_addr = RTE_IPV4(0, 0, 0, 0); in test_predictable_rss_min_seq()
H A Dtest_flow_classify.c74 offsetof(struct rte_ipv4_hdr, dst_addr),
116 .dst_addr = 0xffffff00,
481 uint32_t dst_addr = IPV4_ADDR(2, 2, 2, 7); in init_ipv4_udp_traffic() local
496 pktlen = initialize_ipv4_header(&pkt_ipv4_hdr, src_addr, dst_addr, in init_ipv4_udp_traffic()
518 uint32_t dst_addr = IPV4_ADDR(5, 6, 7, 8); in init_ipv4_tcp_traffic() local
534 dst_addr, pktlen, IPPROTO_TCP); in init_ipv4_tcp_traffic()
555 uint32_t dst_addr = IPV4_ADDR(15, 16, 17, 18); in init_ipv4_sctp_traffic() local
571 dst_addr, pktlen, IPPROTO_SCTP); in init_ipv4_sctp_traffic()
/dpdk/examples/pipeline/examples/
H A Dfib.spec30 bit<48> dst_addr
45 bit<32> dst_addr
58 bit<32> dst_addr
86 mov h.ethernet.dst_addr t.ethernet_dst_addr
112 m.dst_addr lpm
131 h.ipv4.dst_addr
164 mov m.dst_addr h.ipv4.dst_addr
H A Dl2fwd_macswp.spec8 bit<48> dst_addr
29 mov m.addr h.ethernet.dst_addr
30 mov h.ethernet.dst_addr h.ethernet.src_addr
H A Dvxlan.spec8 bit<48> dst_addr
23 bit<32> dst_addr
118 mov h.outer_ethernet.dst_addr t.ethernet_dst_addr
133 mov h.outer_ipv4.dst_addr t.ipv4_dst_addr
174 h.ethernet.dst_addr exact
/dpdk/app/test-pipeline/
H A Dpipeline_acl.c59 offsetof(struct rte_ipv4_hdr, dst_addr),
205 uint32_t dst_addr = rule_params.field_value[DST_FIELD_IPV4]. in app_main_loop_worker_pipeline_acl() local
212 (dst_addr & 0xFF000000) >> 24, in app_main_loop_worker_pipeline_acl()
213 (dst_addr & 0x00FF0000) >> 16, in app_main_loop_worker_pipeline_acl()
214 (dst_addr & 0x0000FF00) >> 8, in app_main_loop_worker_pipeline_acl()
215 dst_addr & 0x000000FF, in app_main_loop_worker_pipeline_acl()
/dpdk/examples/ipsec-secgw/
H A Dsad.h37 (sa->dst.ip.ip4 == ipv4->dst_addr)) || in cmp_sa_key()
41 (!memcmp(sa->dst.ip.ip6.ip6, ipv6->dst_addr, 16)))) in cmp_sa_key()
116 v4[nb_v4].dip = ipv4->dst_addr; in sad_lookup()
131 memcpy(v6[nb_v6].dip, ipv6->dst_addr, in sad_lookup()
132 sizeof(ipv6->dst_addr)); in sad_lookup()
H A Dflow.c45 uint32_t_to_char(rte_bswap32(hdr->dst_addr), &a, &b, &c, &d); in ipv4_hdr_print()
89 addr = hdr->dst_addr; in ipv6_hdr_print()
170 if (ipv4_addr_cpy(&rule->ipv4.spec.hdr.dst_addr, in parse_flow_tokens()
171 &rule->ipv4.mask.hdr.dst_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()
/dpdk/examples/l3fwd/
H A Dl3fwd_lpm_sse.h24 x0 = ipv4_hdr->dst_addr; in processx4_step1()
29 x1 = ipv4_hdr->dst_addr; in processx4_step1()
34 x2 = ipv4_hdr->dst_addr; in processx4_step1()
39 x3 = ipv4_hdr->dst_addr; in processx4_step1()
H A Dl3fwd_lpm_altivec.h26 x0 = ipv4_hdr->dst_addr; in processx4_step1()
32 x1 = ipv4_hdr->dst_addr; in processx4_step1()
38 x2 = ipv4_hdr->dst_addr; in processx4_step1()
44 x3 = ipv4_hdr->dst_addr; in processx4_step1()
H A Dl3fwd_lpm_neon.h27 dst[0] = ipv4_hdr->dst_addr; in processx4_step1()
32 dst[1] = ipv4_hdr->dst_addr; in processx4_step1()
37 dst[2] = ipv4_hdr->dst_addr; in processx4_step1()
42 dst[3] = ipv4_hdr->dst_addr; in processx4_step1()
/dpdk/lib/node/
H A Dip4_lookup_neon.h81 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 0); in ip4_lookup_node_process_vec()
89 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 1); in ip4_lookup_node_process_vec()
97 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 2); in ip4_lookup_node_process_vec()
105 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 3); in ip4_lookup_node_process_vec()
201 rc = rte_lpm_lookup(lpm, rte_be_to_cpu_32(ipv4_hdr->dst_addr), in ip4_lookup_node_process_vec()
H A Dip4_lookup_sse.h77 ip0 = ipv4_hdr->dst_addr; in ip4_lookup_node_process_vec()
85 ip1 = ipv4_hdr->dst_addr; in ip4_lookup_node_process_vec()
93 ip2 = ipv4_hdr->dst_addr; in ip4_lookup_node_process_vec()
101 ip3 = ipv4_hdr->dst_addr; in ip4_lookup_node_process_vec()
206 rc = rte_lpm_lookup(lpm, rte_be_to_cpu_32(ipv4_hdr->dst_addr), in ip4_lookup_node_process_vec()
/dpdk/drivers/net/tap/
H A Dtap_bpf_program.c75 __u32 dst_addr; member
82 __u8 dst_addr[16]; member
164 .dst_addr = IPv4(*(src_dst_addr + 4), in rss_l3_l4()
191 *((uint32_t *)&v6_tuple.dst_addr + j) = in rss_l3_l4()
/dpdk/lib/net/
H A Drte_ip.h63 rte_be32_t dst_addr; /**< destination address */ member
326 uint32_t dst_addr; /* IP address of destination host. */ in rte_ipv4_phdr_cksum() member
335 psd_hdr.dst_addr = ipv4_hdr->dst_addr; in rte_ipv4_phdr_cksum()
529 uint8_t dst_addr[16]; /**< IP address of destination host(s). */ member
576 sizeof(ipv6_hdr->src_addr) + sizeof(ipv6_hdr->dst_addr), in rte_ipv6_phdr_cksum()
/dpdk/drivers/net/qede/base/
H A Decore_hw.c746 u64 dst_addr, in ecore_dmae_execute_sub_operation() argument
810 (unsigned long)src_addr, (unsigned long)dst_addr, in ecore_dmae_execute_sub_operation()
817 OSAL_MEMCPY((void *)(osal_uintptr_t)(dst_addr), in ecore_dmae_execute_sub_operation()
828 u64 dst_addr, in ecore_dmae_execute_command() argument
846 (unsigned long)dst_addr, dst_type, in ecore_dmae_execute_command()
855 (unsigned long)dst_addr, dst_type, in ecore_dmae_execute_command()
867 (unsigned long)dst_addr, in ecore_dmae_execute_command()
885 dst_addr_split = dst_addr; in ecore_dmae_execute_command()
898 dst_addr_split = dst_addr + offset; in ecore_dmae_execute_command()
900 dst_addr_split = dst_addr + (offset * 4); in ecore_dmae_execute_command()
[all …]
/dpdk/drivers/common/cnxk/
H A Dcnxk_security.c281 memcpy(&sa->outer_hdr.ipv4.dst_addr, &tunnel->ipv4.dst_ip, in ot_ipsec_inb_tunnel_hdr_fill()
287 sa->outer_hdr.ipv4.dst_addr = in ot_ipsec_inb_tunnel_hdr_fill()
288 rte_be_to_cpu_32(sa->outer_hdr.ipv4.dst_addr); in ot_ipsec_inb_tunnel_hdr_fill()
295 memcpy(&sa->outer_hdr.ipv6.dst_addr, &tunnel->ipv6.dst_addr, in ot_ipsec_inb_tunnel_hdr_fill()
453 memcpy(&sa->outer_hdr.ipv4.dst_addr, &tunnel->ipv4.dst_ip, in cnxk_ot_ipsec_outb_sa_fill()
459 sa->outer_hdr.ipv4.dst_addr = in cnxk_ot_ipsec_outb_sa_fill()
460 rte_be_to_cpu_32(sa->outer_hdr.ipv4.dst_addr); in cnxk_ot_ipsec_outb_sa_fill()
484 memcpy(&sa->outer_hdr.ipv6.dst_addr, &tunnel->ipv6.dst_addr, in cnxk_ot_ipsec_outb_sa_fill()
/dpdk/drivers/net/ice/base/
H A Dice_protocol_type.h236 u8 dst_addr[ETH_ALEN]; member
245 u8 dst_addr[ETH_ALEN]; member
265 __be32 dst_addr; member
285 u8 dst_addr[ICE_IPV6_ADDR_LENGTH]; member

1234567