Home
last modified time | relevance | path

Searched refs:eth_hdr (Results 1 – 25 of 54) sorted by relevance

123

/dpdk/app/test-pmd/
H A Dmacswap_neon.h19 struct rte_ether_hdr *eth_hdr[4]; in do_macswap() local
60 v0 = vld1q_u8((uint8_t const *)eth_hdr[0]); in do_macswap()
61 v1 = vld1q_u8((uint8_t const *)eth_hdr[1]); in do_macswap()
62 v2 = vld1q_u8((uint8_t const *)eth_hdr[2]); in do_macswap()
63 v3 = vld1q_u8((uint8_t const *)eth_hdr[3]); in do_macswap()
70 vst1q_u8((uint8_t *)eth_hdr[0], v0); in do_macswap()
71 vst1q_u8((uint8_t *)eth_hdr[1], v1); in do_macswap()
72 vst1q_u8((uint8_t *)eth_hdr[2], v2); in do_macswap()
73 vst1q_u8((uint8_t *)eth_hdr[3], v3); in do_macswap()
89 v0 = vld1q_u8((uint8_t const *)eth_hdr[0]); in do_macswap()
[all …]
H A Dmacswap_sse.h14 struct rte_ether_hdr *eth_hdr[4]; in do_macswap() local
47 addr0 = _mm_loadu_si128((__m128i *)eth_hdr[0]); in do_macswap()
51 addr1 = _mm_loadu_si128((__m128i *)eth_hdr[1]); in do_macswap()
56 addr2 = _mm_loadu_si128((__m128i *)eth_hdr[2]); in do_macswap()
60 addr3 = _mm_loadu_si128((__m128i *)eth_hdr[3]); in do_macswap()
67 _mm_storeu_si128((__m128i *)eth_hdr[0], addr0); in do_macswap()
68 _mm_storeu_si128((__m128i *)eth_hdr[1], addr1); in do_macswap()
69 _mm_storeu_si128((__m128i *)eth_hdr[2], addr2); in do_macswap()
70 _mm_storeu_si128((__m128i *)eth_hdr[3], addr3); in do_macswap()
86 addr0 = _mm_loadu_si128((__m128i *)eth_hdr[0]); in do_macswap()
[all …]
H A Dmacswap.h14 struct rte_ether_hdr *eth_hdr; in do_macswap() local
29 eth_hdr = rte_pktmbuf_mtod(mb, struct rte_ether_hdr *); in do_macswap()
32 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()
34 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in do_macswap()
H A Dieee1588fwd.c96 struct rte_ether_hdr *eth_hdr; in ieee1588_packet_fwd() local
114 eth_hdr = rte_pktmbuf_mtod(mb, struct rte_ether_hdr *); in ieee1588_packet_fwd()
115 eth_type = rte_be_to_cpu_16(eth_hdr->ether_type); in ieee1588_packet_fwd()
181 rte_ether_addr_copy(&eth_hdr->dst_addr, &addr); in ieee1588_packet_fwd()
182 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in ieee1588_packet_fwd()
183 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in ieee1588_packet_fwd()
H A Dflowgen.c69 struct rte_ether_hdr *eth_hdr; in pkt_burst_flow_gen() local
123 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in pkt_burst_flow_gen()
124 rte_ether_addr_copy(&cfg_ether_dst, &eth_hdr->dst_addr); in pkt_burst_flow_gen()
125 rte_ether_addr_copy(&cfg_ether_src, &eth_hdr->src_addr); in pkt_burst_flow_gen()
126 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in pkt_burst_flow_gen()
129 ip_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in pkt_burst_flow_gen()
141 sizeof(*eth_hdr)); in pkt_burst_flow_gen()
150 sizeof(*eth_hdr) - in pkt_burst_flow_gen()
H A Dcsumonly.c262 struct rte_ether_hdr *eth_hdr; in parse_vxlan() local
277 parse_ethernet(eth_hdr, info); in parse_vxlan()
286 struct rte_ether_hdr *eth_hdr; in parse_vxlan_gpe() local
326 parse_ethernet(eth_hdr, info); in parse_vxlan_gpe()
338 struct rte_ether_hdr *eth_hdr; in parse_geneve() local
371 parse_ethernet(eth_hdr, info); in parse_geneve()
384 struct rte_ether_hdr *eth_hdr; in parse_gre() local
421 parse_ethernet(eth_hdr, info); in parse_gre()
821 struct rte_ether_hdr *eth_hdr; in pkt_burst_checksum_forward() local
898 &eth_hdr->dst_addr); in pkt_burst_checksum_forward()
[all …]
H A Dmacfwd.c51 struct rte_ether_hdr *eth_hdr; in pkt_burst_mac_forward() local
85 eth_hdr = rte_pktmbuf_mtod(mb, struct rte_ether_hdr *); in pkt_burst_mac_forward()
87 &eth_hdr->dst_addr); in pkt_burst_mac_forward()
89 &eth_hdr->src_addr); in pkt_burst_mac_forward()
H A D5tswap.c25 swap_mac(struct rte_ether_hdr *eth_hdr) in swap_mac() argument
30 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()
32 rte_ether_addr_copy(&addr, &eth_hdr->src_addr); in swap_mac()
H A Dtxonly.c191 struct rte_ether_hdr *eth_hdr, const uint16_t vlan_tci, in pkt_burst_prepare() argument
231 copy_buf_to_pkt(eth_hdr, sizeof(*eth_hdr), pkt, 0); in pkt_burst_prepare()
334 struct rte_ether_hdr eth_hdr; in pkt_burst_transmit() local
360 rte_ether_addr_copy(&peer_eth_addrs[fs->peer_addr], &eth_hdr.dst_addr); in pkt_burst_transmit()
361 rte_ether_addr_copy(&ports[fs->tx_port].eth_addr, &eth_hdr.src_addr); in pkt_burst_transmit()
362 eth_hdr.ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in pkt_burst_transmit()
368 &eth_hdr, vlan_tci, in pkt_burst_transmit()
383 if (unlikely(!pkt_burst_prepare(pkt, mbp, &eth_hdr, in pkt_burst_transmit()
/dpdk/examples/l3fwd/
H A Dl3fwd_em.h10 struct rte_ether_hdr *eth_hdr, struct lcore_conf *qconf) in l3fwd_em_handle_ipv4() argument
39 *(uint64_t *)&eth_hdr->dst_addr = dest_eth_addr[dst_port]; in l3fwd_em_handle_ipv4()
43 &eth_hdr->src_addr); in l3fwd_em_handle_ipv4()
50 struct rte_ether_hdr *eth_hdr, struct lcore_conf *qconf) in l3fwd_em_handle_ipv6() argument
67 *(uint64_t *)&eth_hdr->dst_addr = dest_eth_addr[dst_port]; in l3fwd_em_handle_ipv6()
71 &eth_hdr->src_addr); in l3fwd_em_handle_ipv6()
80 struct rte_ether_hdr *eth_hdr; in l3fwd_em_simple_forward() local
85 eth_hdr = rte_pktmbuf_mtod(m, struct rte_ether_hdr *); in l3fwd_em_simple_forward()
90 dst_port = l3fwd_em_handle_ipv4(m, portid, eth_hdr, qconf); in l3fwd_em_simple_forward()
104 struct rte_ether_hdr *eth_hdr; in l3fwd_em_simple_process() local
[all …]
H A Dl3fwd_lpm_sse.h19 struct rte_ether_hdr *eth_hdr; in processx4_step1() local
22 eth_hdr = rte_pktmbuf_mtod(pkt[0], struct rte_ether_hdr *); in processx4_step1()
23 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
27 eth_hdr = rte_pktmbuf_mtod(pkt[1], struct rte_ether_hdr *); in processx4_step1()
28 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
32 eth_hdr = rte_pktmbuf_mtod(pkt[2], struct rte_ether_hdr *); in processx4_step1()
33 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
37 eth_hdr = rte_pktmbuf_mtod(pkt[3], struct rte_ether_hdr *); in processx4_step1()
38 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
H A Dl3fwd_lpm_altivec.h21 struct rte_ether_hdr *eth_hdr; in processx4_step1() local
24 eth_hdr = rte_pktmbuf_mtod(pkt[0], struct rte_ether_hdr *); in processx4_step1()
25 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
30 eth_hdr = rte_pktmbuf_mtod(pkt[1], struct rte_ether_hdr *); in processx4_step1()
31 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
36 eth_hdr = rte_pktmbuf_mtod(pkt[2], struct rte_ether_hdr *); in processx4_step1()
37 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
42 eth_hdr = rte_pktmbuf_mtod(pkt[3], struct rte_ether_hdr *); in processx4_step1()
43 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
H A Dl3fwd_lpm_neon.h22 struct rte_ether_hdr *eth_hdr; in processx4_step1() local
25 eth_hdr = rte_pktmbuf_mtod(pkt[0], struct rte_ether_hdr *); in processx4_step1()
26 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
30 eth_hdr = rte_pktmbuf_mtod(pkt[1], struct rte_ether_hdr *); in processx4_step1()
31 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
35 eth_hdr = rte_pktmbuf_mtod(pkt[2], struct rte_ether_hdr *); in processx4_step1()
36 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
40 eth_hdr = rte_pktmbuf_mtod(pkt[3], struct rte_ether_hdr *); in processx4_step1()
41 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in processx4_step1()
H A Dl3fwd_lpm.h12 struct rte_ether_hdr *eth_hdr; in l3fwd_lpm_simple_forward() local
16 eth_hdr = rte_pktmbuf_mtod(m, struct rte_ether_hdr *); in l3fwd_lpm_simple_forward()
43 *(uint64_t *)&eth_hdr->dst_addr = dest_eth_addr[dst_port]; in l3fwd_lpm_simple_forward()
47 &eth_hdr->src_addr); in l3fwd_lpm_simple_forward()
65 *(uint64_t *)&eth_hdr->dst_addr = dest_eth_addr[dst_port]; in l3fwd_lpm_simple_forward()
69 &eth_hdr->src_addr); in l3fwd_lpm_simple_forward()
H A Dl3fwd_lpm.c80 struct rte_ether_hdr *eth_hdr; in lpm_get_dst_port() local
84 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in lpm_get_dst_port()
85 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in lpm_get_dst_port()
91 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in lpm_get_dst_port()
92 ipv6_hdr = (struct rte_ipv6_hdr *)(eth_hdr + 1); in lpm_get_dst_port()
112 struct rte_ether_hdr *eth_hdr; in lpm_get_dst_port_with_ipv4() local
122 ipv6_hdr = (struct rte_ipv6_hdr *)(eth_hdr + 1); in lpm_get_dst_port_with_ipv4()
239 struct rte_ether_hdr *eth_hdr = rte_pktmbuf_mtod(mbuf, in lpm_process_event_pkt() local
247 &eth_hdr->src_addr); in lpm_process_event_pkt()
686 struct rte_ether_hdr *eth_hdr; in lpm_parse_ptype() local
[all …]
H A Dl3fwd_altivec.h129 struct rte_ether_hdr *eth_hdr; in process_packet() local
132 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in process_packet()
134 te = *(__vector unsigned int *)eth_hdr; in process_packet()
137 rfc1812_process((struct rte_ipv4_hdr *)(eth_hdr + 1), dst_port, in process_packet()
147 *(__vector unsigned int *)eth_hdr = te; in process_packet()
H A Dl3fwd_sse.h108 struct rte_ether_hdr *eth_hdr; in process_packet() local
111 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in process_packet()
113 te = _mm_loadu_si128((__m128i *)eth_hdr); in process_packet()
116 rfc1812_process((struct rte_ipv4_hdr *)(eth_hdr + 1), dst_port, in process_packet()
120 _mm_storeu_si128((__m128i *)eth_hdr, te); in process_packet()
H A Dl3fwd_neon.h111 struct rte_ether_hdr *eth_hdr; in process_packet() local
114 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in process_packet()
116 te = vld1q_u32((uint32_t *)eth_hdr); in process_packet()
120 rfc1812_process((struct rte_ipv4_hdr *)(eth_hdr + 1), dst_port, in process_packet()
124 vst1q_u32((uint32_t *)eth_hdr, ve); in process_packet()
/dpdk/lib/net/
H A Drte_arp.c12 struct rte_ether_hdr *eth_hdr; in rte_net_make_rarp_packet() local
23 eth_hdr = (struct rte_ether_hdr *) in rte_net_make_rarp_packet()
25 if (eth_hdr == NULL) { in rte_net_make_rarp_packet()
31 memset(eth_hdr->dst_addr.addr_bytes, 0xff, RTE_ETHER_ADDR_LEN); in rte_net_make_rarp_packet()
32 rte_ether_addr_copy(mac, &eth_hdr->src_addr); in rte_net_make_rarp_packet()
33 eth_hdr->ether_type = RTE_BE16(RTE_ETHER_TYPE_RARP); in rte_net_make_rarp_packet()
36 rarp = (struct rte_arp_hdr *)(eth_hdr + 1); in rte_net_make_rarp_packet()
/dpdk/lib/node/
H A Dethdev_rx.c71 struct rte_ether_hdr *eth_hdr; in eth_pkt_parse_cb() local
108 eth_hdr = rte_pktmbuf_mtod(mbuf0, struct rte_ether_hdr *); in eth_pkt_parse_cb()
109 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
113 eth_hdr = rte_pktmbuf_mtod(mbuf1, struct rte_ether_hdr *); in eth_pkt_parse_cb()
114 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
118 eth_hdr = rte_pktmbuf_mtod(mbuf2, struct rte_ether_hdr *); in eth_pkt_parse_cb()
119 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
123 eth_hdr = rte_pktmbuf_mtod(mbuf3, struct rte_ether_hdr *); in eth_pkt_parse_cb()
124 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
135 eth_hdr = rte_pktmbuf_mtod(mbuf0, struct rte_ether_hdr *); in eth_pkt_parse_cb()
[all …]
/dpdk/app/test/
H A Dtest_sched.c105 struct rte_ether_hdr *eth_hdr; in prepare_pkt() local
110 eth_hdr = rte_pktmbuf_mtod(mbuf, struct rte_ether_hdr *); in prepare_pkt()
111 vlan1 = (struct rte_vlan_hdr *)(&eth_hdr->ether_type); in prepare_pkt()
113 (uintptr_t)&eth_hdr->ether_type + sizeof(struct rte_vlan_hdr)); in prepare_pkt()
114 eth_hdr = (struct rte_ether_hdr *)( in prepare_pkt()
115 (uintptr_t)&eth_hdr->ether_type + in prepare_pkt()
118 (uintptr_t)eth_hdr + sizeof(eth_hdr->ether_type)); in prepare_pkt()
122 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in prepare_pkt()
H A Dpacket_burst_generator.c55 initialize_eth_header(struct rte_ether_hdr *eth_hdr, in initialize_eth_header() argument
60 rte_ether_addr_copy(dst_mac, &eth_hdr->dst_addr); in initialize_eth_header()
61 rte_ether_addr_copy(src_mac, &eth_hdr->src_addr); in initialize_eth_header()
65 (uint8_t *)eth_hdr + sizeof(struct rte_ether_hdr)); in initialize_eth_header()
67 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_VLAN); in initialize_eth_header()
72 eth_hdr->ether_type = rte_cpu_to_be_16(ether_type); in initialize_eth_header()
262 struct rte_ether_hdr *eth_hdr, uint8_t vlan_enabled, in generate_packet_burst() argument
304 copy_buf_to_pkt(eth_hdr, eth_hdr_size, pkt, 0); in generate_packet_burst()
342 struct rte_mbuf **pkts_burst, struct rte_ether_hdr *eth_hdr, in generate_packet_burst_proto() argument
385 copy_buf_to_pkt(eth_hdr, eth_hdr_size, pkt, 0); in generate_packet_burst_proto()
H A Dpacket_burst_generator.h27 initialize_eth_header(struct rte_ether_hdr *eth_hdr,
63 struct rte_ether_hdr *eth_hdr, uint8_t vlan_enabled,
69 struct rte_mbuf **pkts_burst, struct rte_ether_hdr *eth_hdr,
/dpdk/examples/bond/
H A Dmain.c328 (struct rte_vlan_hdr *)(eth_hdr + 1); in get_vlan_offset()
362 struct rte_ether_hdr *eth_hdr; in lcore_main() local
404 eth_hdr = rte_pktmbuf_mtod(pkts[i], in lcore_main()
406 ether_type = eth_hdr->ether_type; in lcore_main()
409 offset = get_vlan_offset(eth_hdr, &ether_type); in lcore_main()
418 (char *)(eth_hdr + 1) + offset); in lcore_main()
423 rte_ether_addr_copy(&eth_hdr->src_addr, &eth_hdr->dst_addr); in lcore_main()
444 rte_ether_addr_copy(&eth_hdr->src_addr, in lcore_main()
445 &eth_hdr->dst_addr); in lcore_main()
447 &eth_hdr->src_addr); in lcore_main()
[all …]
/dpdk/examples/ptpclient/
H A Dptpclient.c384 struct rte_ether_hdr *eth_hdr; in parse_fup() local
398 eth_hdr = rte_pktmbuf_mtod(m, struct rte_ether_hdr *); in parse_fup()
436 rte_ether_addr_copy(&eth_addr, &eth_hdr->src_addr); in parse_fup()
441 eth_hdr->ether_type = htons(PTP_PROTOCOL); in parse_fup()
459 client_clkid->id[0] = eth_hdr->src_addr.addr_bytes[0]; in parse_fup()
460 client_clkid->id[1] = eth_hdr->src_addr.addr_bytes[1]; in parse_fup()
461 client_clkid->id[2] = eth_hdr->src_addr.addr_bytes[2]; in parse_fup()
464 client_clkid->id[5] = eth_hdr->src_addr.addr_bytes[3]; in parse_fup()
578 struct rte_ether_hdr *eth_hdr; in parse_ptp_frames() local
581 eth_hdr = rte_pktmbuf_mtod(m, struct rte_ether_hdr *); in parse_ptp_frames()
[all …]

123