Home
last modified time | relevance | path

Searched refs:src_addr (Results 1 – 25 of 148) sorted by relevance

123456

/dpdk/lib/hash/
H A Drte_thash.h73 uint32_t src_addr; member
91 uint8_t src_addr[16]; member
143 __m128i ipv6 = _mm_loadu_si128((const __m128i *)orig->src_addr); in rte_thash_load_v6_addrs()
144 *(__m128i *)targ->v6.src_addr = 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()
157 *((uint32_t *)targ->v6.src_addr + i) = in rte_thash_load_v6_addrs()
158 rte_be_to_cpu_32(*((const uint32_t *)orig->src_addr + i)); in rte_thash_load_v6_addrs()
/dpdk/app/test-pmd/
H A Dicmpecho.c321 ether_addr_dump(" ETH: src=", &eth_h->src_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()
390 &eth_h->src_addr); in reply_to_icmp_echo_rqsts()
397 rte_ether_addr_copy(&eth_h->src_addr, in reply_to_icmp_echo_rqsts()
414 ipv4_addr_dump(" IPV4: src=", ip_h->src_addr); in reply_to_icmp_echo_rqsts()
455 rte_ether_addr_copy(&eth_h->src_addr, &eth_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()
458 ip_addr = ip_h->src_addr; in reply_to_icmp_echo_rqsts()
467 ip_h->src_addr = rte_cpu_to_be_32(ip_src); in reply_to_icmp_echo_rqsts()
471 ip_h->src_addr = ip_h->dst_addr; in reply_to_icmp_echo_rqsts()
H A D5tswap.c31 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in swap_mac()
32 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in swap_mac()
41 addr = ipv4_hdr->src_addr; in swap_ipv4()
42 ipv4_hdr->src_addr = ipv4_hdr->dst_addr; in swap_ipv4()
52 memcpy(&addr, &ipv6_hdr->src_addr, 16); in swap_ipv6()
53 memcpy(&ipv6_hdr->src_addr, &ipv6_hdr->dst_addr, 16); in swap_ipv6()
H A Dmacswap.h33 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in do_macswap()
34 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in do_macswap()
/dpdk/app/test/
H A Dtest_acl.h85 .src_addr = RTE_IPV4(10,0,0,0),
180 .src_addr = RTE_IPV4(10,0,0,0),
191 .src_addr = RTE_IPV4(10,1,1,0),
202 .src_addr = RTE_IPV4(10,1,1,1),
398 .src_addr = RTE_IPV4(5,6,7,8),
416 .src_addr = RTE_IPV4(1,2,3,4),
434 .src_addr = RTE_IPV4(5,6,7,8),
450 .src_addr = RTE_IPV4(1,2,3,4),
680 .src_addr = RTE_IPV4(0, 0, 0, 1),
689 .src_addr = RTE_IPV4(0, 4, 3, 2),
[all …]
H A Dpacket_burst_generator.c61 rte_ether_addr_copy(src_mac, &eth_hdr->src_addr); in initialize_eth_header()
143 initialize_ipv6_header(struct rte_ipv6_hdr *ip_hdr, uint8_t *src_addr, in initialize_ipv6_header() argument
151 rte_memcpy(ip_hdr->src_addr, src_addr, sizeof(ip_hdr->src_addr)); in initialize_ipv6_header()
158 initialize_ipv4_header(struct rte_ipv4_hdr *ip_hdr, uint32_t src_addr, in initialize_ipv4_header() argument
177 ip_hdr->src_addr = rte_cpu_to_be_32(src_addr); in initialize_ipv4_header()
206 initialize_ipv4_header_proto(struct rte_ipv4_hdr *ip_hdr, uint32_t src_addr, in initialize_ipv4_header_proto() argument
225 ip_hdr->src_addr = rte_cpu_to_be_32(src_addr); in initialize_ipv4_header_proto()
H A Dpacket_burst_generator.h50 initialize_ipv6_header(struct rte_ipv6_hdr *ip_hdr, uint8_t *src_addr,
54 initialize_ipv4_header(struct rte_ipv4_hdr *ip_hdr, uint32_t src_addr,
58 initialize_ipv4_header_proto(struct rte_ipv4_hdr *ip_hdr, uint32_t src_addr,
H A Dtest_thash.c125 tuple.v4.src_addr = v4_tbl[i].src_ip; in test_toeplitz_hash_calc()
148 for (j = 0; j < RTE_DIM(ipv6_hdr.src_addr); j++) in test_toeplitz_hash_calc()
149 ipv6_hdr.src_addr[j] = v6_tbl[i].src_ip[j]; in test_toeplitz_hash_calc()
192 tuple.v4.src_addr = rte_cpu_to_be_32(v4_tbl[i].src_ip); in test_toeplitz_hash_gfni()
207 for (j = 0; j < RTE_DIM(tuple.v6.src_addr); j++) in test_toeplitz_hash_gfni()
208 tuple.v6.src_addr[j] = v6_tbl[i].src_ip[j]; in test_toeplitz_hash_gfni()
324 tuple[0].v4.src_addr = rte_cpu_to_be_32(v4_tbl[i].src_ip); in test_toeplitz_hash_gfni_bulk()
331 for (j = 0; j < RTE_DIM(tuple[1].v6.src_addr); j++) in test_toeplitz_hash_gfni_bulk()
332 tuple[1].v6.src_addr[j] = v6_tbl[i].src_ip[j]; in test_toeplitz_hash_gfni_bulk()
603 tuple.v4.src_addr = RTE_IPV4(0, 0, 0, 0); in test_predictable_rss_min_seq()
H A Dtest_flow_classify.c64 offsetof(struct rte_ipv4_hdr, src_addr),
115 .src_addr = 0xffffff00,
480 uint32_t src_addr = IPV4_ADDR(2, 2, 2, 3); in init_ipv4_udp_traffic() local
496 pktlen = initialize_ipv4_header(&pkt_ipv4_hdr, src_addr, dst_addr, in init_ipv4_udp_traffic()
517 uint32_t src_addr = IPV4_ADDR(1, 2, 3, 4); in init_ipv4_tcp_traffic() local
533 pktlen = initialize_ipv4_header_proto(&pkt_ipv4_hdr, src_addr, in init_ipv4_tcp_traffic()
554 uint32_t src_addr = IPV4_ADDR(11, 12, 13, 14); in init_ipv4_sctp_traffic() local
570 pktlen = initialize_ipv4_header_proto(&pkt_ipv4_hdr, src_addr, in init_ipv4_sctp_traffic()
H A Dtest_ipfrag.c143 hdr->src_addr = rte_cpu_to_be_32(0x8080808); in v4_allocate_packet_of()
167 memset(hdr->src_addr, 0x08, sizeof(hdr->src_addr)); in v6_allocate_packet_of()
168 memset(hdr->dst_addr, 0x04, sizeof(hdr->src_addr)); in v6_allocate_packet_of()
/dpdk/examples/ipsec-secgw/
H A Dflow.c42 uint32_t_to_char(rte_bswap32(hdr->src_addr), &a, &b, &c, &d); in ipv4_hdr_print()
64 memcpy(mask, &rte_flow_item_ipv4_mask.hdr.src_addr, sizeof(ip)); in ipv4_addr_cpy()
78 addr = hdr->src_addr; in ipv6_hdr_print()
113 memcpy(mask, &rte_flow_item_ipv6_mask.hdr.src_addr, sizeof(ip)); in ipv6_addr_cpy()
153 if (ipv4_addr_cpy(&rule->ipv4.spec.hdr.src_addr, in parse_flow_tokens()
154 &rule->ipv4.mask.hdr.src_addr, in parse_flow_tokens()
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()
H A Dsad.h36 (sa->src.ip.ip4 == ipv4->src_addr) && in cmp_sa_key()
40 (!memcmp(sa->src.ip.ip6.ip6, ipv6->src_addr, 16)) && in cmp_sa_key()
117 v4[nb_v4].sip = ipv4->src_addr; in sad_lookup()
133 memcpy(v6[nb_v6].sip, ipv6->src_addr, in sad_lookup()
134 sizeof(ipv6->src_addr)); in sad_lookup()
/dpdk/examples/pipeline/examples/
H A Dregisters.spec17 bit<48> src_addr
30 bit<32> src_addr
60 regadd pkt_counters h.ipv4.src_addr 1
61 regadd byte_counters h.ipv4.src_addr h.ipv4.total_len
H A Dl2fwd_macswp.spec9 bit<48> src_addr
30 mov h.ethernet.dst_addr h.ethernet.src_addr
31 mov h.ethernet.src_addr m.addr
H A Dmeter.spec17 bit<48> src_addr
30 bit<32> src_addr
59 meter meters h.ipv4.src_addr h.ipv4.total_len 0 m.port_out
H A Dfib.spec31 bit<48> src_addr
44 bit<32> src_addr
87 mov h.ethernet.src_addr t.ethernet_src_addr
130 h.ipv4.src_addr
163 mov m.vrf_id h.ipv4.src_addr
/dpdk/drivers/crypto/ccp/
H A Dccp_crypto.c1654 pst.src_addr = in ccp_perform_hmac()
1762 phys_addr_t src_addr, dest_addr; in ccp_perform_sha() local
1777 pst.src_addr = (phys_addr_t)sha_ctx; in ccp_perform_sha()
1919 pst.src_addr = in ccp_perform_sha3_hmac()
2077 phys_addr_t src_addr, dest_addr, key_addr; in ccp_perform_aes_cmac() local
2240 phys_addr_t src_addr, dest_addr, key_addr; in ccp_perform_aes() local
2261 pst.src_addr = b_info->lsb_buf_phys + in ccp_perform_aes()
2282 dest_addr = src_addr; in ccp_perform_aes()
2329 phys_addr_t src_addr, dest_addr, key_addr; in ccp_perform_3des() local
2369 dest_addr = src_addr; in ccp_perform_3des()
[all …]
/dpdk/lib/net/
H A Drte_ip.h62 rte_be32_t src_addr; /**< source address */ member
325 uint32_t src_addr; /* IP address of source host. */ in rte_ipv4_phdr_cksum() member
334 psd_hdr.src_addr = ipv4_hdr->src_addr; in rte_ipv4_phdr_cksum()
528 uint8_t src_addr[16]; /**< IP address of source host. */ member
575 sum = __rte_raw_cksum(ipv6_hdr->src_addr, in rte_ipv6_phdr_cksum()
576 sizeof(ipv6_hdr->src_addr) + sizeof(ipv6_hdr->dst_addr), in rte_ipv6_phdr_cksum()
/dpdk/drivers/net/tap/
H A Dtap_bpf_program.c74 __u32 src_addr; member
81 __u8 src_addr[16]; member
160 .src_addr = IPv4(*(src_dst_addr + 0), in rss_l3_l4()
187 *((uint32_t *)&v6_tuple.src_addr + j) = in rss_l3_l4()
/dpdk/drivers/dma/ioat/
H A Dioat_hw_defs.h131 uint64_t src_addr; member
187 uint64_t src_addr; member
226 uint64_t src_addr; member
267 uint64_t src_addr; member
/dpdk/drivers/net/qede/base/
H A Decore_hw.c745 u64 src_addr, in ecore_dmae_execute_sub_operation() argument
764 (void *)(osal_uintptr_t)src_addr, in ecore_dmae_execute_sub_operation()
810 (unsigned long)src_addr, (unsigned long)dst_addr, in ecore_dmae_execute_sub_operation()
827 u64 src_addr, in ecore_dmae_execute_command() argument
845 (unsigned long)src_addr, src_type, in ecore_dmae_execute_command()
854 (unsigned long)src_addr, src_type, in ecore_dmae_execute_command()
866 (unsigned long)src_addr, in ecore_dmae_execute_command()
884 src_addr_split = src_addr; in ecore_dmae_execute_command()
892 src_addr_split = src_addr + offset; in ecore_dmae_execute_command()
894 src_addr_split = src_addr + (offset * 4); in ecore_dmae_execute_command()
[all …]
/dpdk/drivers/common/cnxk/
H A Dcnxk_security.c279 memcpy(&sa->outer_hdr.ipv4.src_addr, &tunnel->ipv4.src_ip, in ot_ipsec_inb_tunnel_hdr_fill()
285 sa->outer_hdr.ipv4.src_addr = in ot_ipsec_inb_tunnel_hdr_fill()
286 rte_be_to_cpu_32(sa->outer_hdr.ipv4.src_addr); in ot_ipsec_inb_tunnel_hdr_fill()
293 memcpy(&sa->outer_hdr.ipv6.src_addr, &tunnel->ipv6.src_addr, in ot_ipsec_inb_tunnel_hdr_fill()
451 memcpy(&sa->outer_hdr.ipv4.src_addr, &tunnel->ipv4.src_ip, in cnxk_ot_ipsec_outb_sa_fill()
457 sa->outer_hdr.ipv4.src_addr = in cnxk_ot_ipsec_outb_sa_fill()
458 rte_be_to_cpu_32(sa->outer_hdr.ipv4.src_addr); in cnxk_ot_ipsec_outb_sa_fill()
482 memcpy(&sa->outer_hdr.ipv6.src_addr, &tunnel->ipv6.src_addr, in cnxk_ot_ipsec_outb_sa_fill()
/dpdk/drivers/raw/ioat/
H A Dioat_spec.h110 uint64_t src_addr; member
166 uint64_t src_addr; member
205 uint64_t src_addr; member
246 uint64_t src_addr; member
/dpdk/drivers/net/ice/base/
H A Dice_protocol_type.h237 u8 src_addr[ETH_ALEN]; member
246 u8 src_addr[ETH_ALEN]; member
264 __be32 src_addr; member
284 u8 src_addr[ICE_IPV6_ADDR_LENGTH]; member
/dpdk/examples/flow_filtering/
H A Dflow_blocks.c93 ip_spec.hdr.src_addr = htonl(src_ip); in generate_ipv4_flow()
94 ip_mask.hdr.src_addr = src_mask; in generate_ipv4_flow()

123456