Home
last modified time | relevance | path

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

1234

/dpdk/lib/hash/
H A Drte_thash.h74 uint32_t src_addr; member
91 struct rte_ipv6_addr src_addr; member
155 __m128i ipv6 = _mm_loadu_si128((const __m128i *)&orig->src_addr); in __rte_aligned()
156 *(__m128i *)&targ->v6.src_addr = in __rte_aligned()
162 uint8x16_t ipv6 = vld1q_u8(orig->src_addr.a); in __rte_aligned()
163 vst1q_u8(targ->v6.src_addr.a, vrev32q_u8(ipv6)); in __rte_aligned()
169 *((uint32_t *)&targ->v6.src_addr + i) = in __rte_aligned()
170 rte_be_to_cpu_32(*((const uint32_t *)&orig->src_addr + i)); in __rte_aligned()
/dpdk/examples/pipeline/examples/
H A Dipsec.spec9 bit<48> src_addr
22 bit<32> src_addr
49 bit<32> src_addr
82 m.src_addr exact
109 mov m.src_addr h.ipv4.src_addr
130 mov h.ethernet.src_addr 0xa1b1c1d1e1f1
H A Dl2fwd_macswp.spec12 bit<48> src_addr
36 // Ethernet header: dst_addr swapped with src_addr.
39 mov h.ethernet.dst_addr h.ethernet.src_addr
40 mov h.ethernet.src_addr m.addr
H A Dhash_func.spec13 bit<48> src_addr
26 bit<32> src_addr
46 bit<32> src_addr
75 mov m.src_addr h.ipv4.src_addr
88 // (m.src_addr, m.dst_addr, m.protocol, m.src_port, m.dst_port). Only the first and
92 hash jhash m.hash m.src_addr m.dst_port
H A Dipv6_addr_swap.spec27 bit<48> src_addr
36 bit<128> src_addr
72 movh h.tmp.upper_half h.ipv6.src_addr
73 mov h.tmp.lower_half h.ipv6.src_addr
74 mov h.ipv6.src_addr h.tmp.upper_half
75 movh h.ipv6.src_addr h.tmp.lower_half
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 Drss.spec13 bit<48> src_addr
26 bit<32> src_addr
66 // (h.ipv4.src_addr, h.ipv4.dst_addr). Only the first and the last n-tuple fields are
70 rss rss0 m.hash h.ipv4.src_addr h.ipv4.dst_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
88 mov h.ethernet.src_addr t.ethernet_src_addr
130 h.ipv4.src_addr
163 mov m.vrf_id h.ipv4.src_addr
/dpdk/app/test-pmd/
H A D5tswap.h17 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in swap_mac()
18 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in swap_mac()
27 addr = ipv4_hdr->src_addr; in swap_ipv4()
28 ipv4_hdr->src_addr = ipv4_hdr->dst_addr; in swap_ipv4()
38 memcpy(&addr, &ipv6_hdr->src_addr, 16); in swap_ipv6()
39 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.h32 uint32_t src_addr; /**< IPv4 source address. */ member
85 .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),
[all …]
/dpdk/lib/gro/
H A Dgro_tcp6.h17 struct rte_ipv6_addr src_addr;
147 if (memcmp(&k1->src_addr, &k2->src_addr, 16)) in is_same_tcp6_flow()
15 uint8_t src_addr[16]; global() member
H A Dgro_tcp6.c102 dst->src_addr = src->src_addr; in insert_new_flow()
169 rte_ether_addr_copy(&(eth_hdr->src_addr), &(key.cmn_key.eth_saddr)); in gro_tcp6_reassemble()
171 key.src_addr = ipv6_hdr->src_addr; in gro_tcp6_reassemble()
/dpdk/examples/ipsec-secgw/
H A Dsad.h39 (sa->src.ip.ip4 == ipv4->src_addr) && in cmp_sa_key()
43 (rte_ipv6_addr_eq(&sa->src.ip.ip6, &ipv6->src_addr)) && in cmp_sa_key()
120 v4[nb_v4].sip = ipv4->src_addr; in sad_lookup()
135 v6[nb_v6].sip = ipv6->src_addr; in sad_lookup()
H A Dflow.c51 uint32_t_to_char(rte_bswap32(hdr->src_addr), &a, &b, &c, &d); in ipv4_hdr_print()
73 memcpy(mask, &rte_flow_item_ipv4_mask.hdr.src_addr, sizeof(ip)); in ipv4_addr_cpy()
86 printf("src: " RTE_IPV6_ADDR_FMT " \t", RTE_IPV6_ADDR_SPLIT(&hdr->src_addr)); in ipv6_hdr_print()
102 *mask = rte_flow_item_ipv6_mask.hdr.src_addr; in ipv6_hdr_print()
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()
178 if (ipv6_addr_cpy(&rule->ipv6.spec.hdr.src_addr, in parse_flow_tokens()
179 &rule->ipv6.mask.hdr.src_addr, in parse_flow_tokens()
/dpdk/drivers/crypto/ccp/
H A Dccp_crypto.c1531 CCP_CMD_SRC_LO(desc) = (uint32_t)(pst->src_addr); in ccp_perform_passthru()
1532 CCP_CMD_SRC_HI(desc) = high32_value(pst->src_addr); in ccp_perform_passthru()
1543 CCP_CMD_SRC_LO(desc) = (uint32_t)(pst->src_addr); in ccp_perform_passthru()
1564 phys_addr_t src_addr, dest_addr, dest_addr_t; in ccp_perform_hmac() local
1573 src_addr = rte_pktmbuf_iova_offset(op->sym->m_src, in ccp_perform_hmac()
1578 pst.src_addr = (phys_addr_t)rte_mem_virt2iova((void *)addr); in ccp_perform_hmac()
1609 CCP_CMD_SRC_LO(desc) = ((uint32_t)src_addr); in ccp_perform_hmac()
1610 CCP_CMD_SRC_HI(desc) = high32_value(src_addr); in ccp_perform_hmac()
1630 pst.src_addr = in ccp_perform_hmac()
1639 pst.src_addr = (phys_addr_t)(cmd_q->sb_sha * CCP_SB_BYTES); in ccp_perform_hmac()
[all …]
/dpdk/drivers/net/tap/bpf/
H A Dtap_rss.c67 __u32 src_addr; in parse_ipv4() member
72 .src_addr = bpf_ntohl(iph.saddr), in parse_ipv4()
157 __u32 src_addr[4]; in parse_ipv6() member
171 v6_tuple.src_addr[j] = bpf_ntohl(ip6h.saddr.in6_u.u6_addr32[j]); in parse_ipv6()
/dpdk/lib/net/
H A Drte_ip.h62 rte_be32_t src_addr; /**< source address */ global() member
334 uint32_t src_addr; /* IP address of source host. */ rte_ipv4_phdr_cksum() member
531 uint8_t src_addr[16]; /**< IP address of source host. */ global() member
/dpdk/examples/flow_filtering/
H A Dflow_blocks.c
/dpdk/lib/pipeline/
H A Drte_swx_ipsec.h243 struct in_addr src_addr;
252 struct rte_ipv6_addr src_addr;
242 struct in_addr src_addr; global() member
251 struct in6_addr src_addr; global() member
/dpdk/drivers/net/qede/base/
H A Decore_hw.c745 u64 src_addr, in ecore_dmae_execute_sub_operation() argument
756 cmd->src_addr_hi = OSAL_CPU_TO_LE32(DMA_HI(src_addr)); in ecore_dmae_execute_sub_operation()
757 cmd->src_addr_lo = OSAL_CPU_TO_LE32(DMA_LO(src_addr)); in ecore_dmae_execute_sub_operation()
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()
[all …]
/dpdk/examples/l3fwd/
H A Dl3fwd_lpm.h47 &eth_hdr->src_addr); in l3fwd_lpm_simple_forward()
69 &eth_hdr->src_addr); in l3fwd_lpm_simple_forward()
/dpdk/examples/ptpclient/
H A Dptpclient.c441 rte_ether_addr_copy(&eth_addr, &eth_hdr->src_addr); in parse_fup()
464 client_clkid->id[0] = eth_hdr->src_addr.addr_bytes[0]; in parse_fup()
465 client_clkid->id[1] = eth_hdr->src_addr.addr_bytes[1]; in parse_fup()
466 client_clkid->id[2] = eth_hdr->src_addr.addr_bytes[2]; in parse_fup()
469 client_clkid->id[5] = eth_hdr->src_addr.addr_bytes[3]; in parse_fup()
470 client_clkid->id[6] = eth_hdr->src_addr.addr_bytes[4]; in parse_fup()
471 client_clkid->id[7] = eth_hdr->src_addr.addr_bytes[5]; in parse_fup()
/dpdk/examples/bond/
H A Dmain.c414 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in lcore_main()
415 rte_ether_addr_copy(&bond_mac_addr, &eth_hdr->src_addr); in lcore_main()
435 rte_ether_addr_copy(&eth_hdr->src_addr, in lcore_main()
438 &eth_hdr->src_addr); in lcore_main()
439 ipv4_hdr->dst_addr = ipv4_hdr->src_addr; in lcore_main()
440 ipv4_hdr->src_addr = bond_ip; in lcore_main()
508 rte_ether_addr_copy(&bond_mac_addr, &eth_hdr->src_addr); in cmd_send_parsed()

1234