Home
last modified time | relevance | path

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

123

/f-stack/dpdk/app/test-pmd/
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_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.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->d_addr, &addr); in do_macswap()
33 rte_ether_addr_copy(&eth_hdr->s_addr, &eth_hdr->d_addr); in do_macswap()
34 rte_ether_addr_copy(&addr, &eth_hdr->s_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->d_addr, &addr); in ieee1588_packet_fwd()
182 rte_ether_addr_copy(&eth_hdr->s_addr, &eth_hdr->d_addr); in ieee1588_packet_fwd()
183 rte_ether_addr_copy(&addr, &eth_hdr->s_addr); in ieee1588_packet_fwd()
H A Dflowgen.c89 struct rte_ether_hdr *eth_hdr; in pkt_burst_flow_gen() local
134 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in pkt_burst_flow_gen()
135 rte_ether_addr_copy(&cfg_ether_dst, &eth_hdr->d_addr); in pkt_burst_flow_gen()
136 rte_ether_addr_copy(&cfg_ether_src, &eth_hdr->s_addr); in pkt_burst_flow_gen()
137 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in pkt_burst_flow_gen()
140 ip_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in pkt_burst_flow_gen()
152 sizeof(*eth_hdr)); in pkt_burst_flow_gen()
162 sizeof(*eth_hdr) - in pkt_burst_flow_gen()
H A Dcsumonly.c258 struct rte_ether_hdr *eth_hdr; in parse_vxlan() local
274 parse_ethernet(eth_hdr, info); in parse_vxlan()
283 struct rte_ether_hdr *eth_hdr; in parse_vxlan_gpe() local
323 parse_ethernet(eth_hdr, info); in parse_vxlan_gpe()
335 struct rte_ether_hdr *eth_hdr; in parse_geneve() local
368 parse_ethernet(eth_hdr, info); in parse_geneve()
381 struct rte_ether_hdr *eth_hdr; in parse_gre() local
418 parse_ethernet(eth_hdr, info); in parse_gre()
802 struct rte_ether_hdr *eth_hdr; in pkt_burst_checksum_forward() local
871 &eth_hdr->d_addr); in pkt_burst_checksum_forward()
[all …]
H A Dmacfwd.c52 struct rte_ether_hdr *eth_hdr; in pkt_burst_mac_forward() local
86 eth_hdr = rte_pktmbuf_mtod(mb, struct rte_ether_hdr *); in pkt_burst_mac_forward()
88 &eth_hdr->d_addr); in pkt_burst_mac_forward()
90 &eth_hdr->s_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->d_addr, &addr); in swap_mac()
31 rte_ether_addr_copy(&eth_hdr->s_addr, &eth_hdr->d_addr); in swap_mac()
32 rte_ether_addr_copy(&addr, &eth_hdr->s_addr); in swap_mac()
H A Dtxonly.c189 struct rte_ether_hdr *eth_hdr, const uint16_t vlan_tci, in pkt_burst_prepare() argument
229 copy_buf_to_pkt(eth_hdr, sizeof(*eth_hdr), pkt, 0); in pkt_burst_prepare()
327 struct rte_ether_hdr eth_hdr; in pkt_burst_transmit() local
353 rte_ether_addr_copy(&peer_eth_addrs[fs->peer_addr], &eth_hdr.d_addr); in pkt_burst_transmit()
354 rte_ether_addr_copy(&ports[fs->tx_port].eth_addr, &eth_hdr.s_addr); in pkt_burst_transmit()
355 eth_hdr.ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in pkt_burst_transmit()
361 &eth_hdr, vlan_tci, in pkt_burst_transmit()
376 if (unlikely(!pkt_burst_prepare(pkt, mbp, &eth_hdr, in pkt_burst_transmit()
/f-stack/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->d_addr = dest_eth_addr[dst_port]; in l3fwd_em_handle_ipv4()
43 &eth_hdr->s_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->d_addr = dest_eth_addr[dst_port]; in l3fwd_em_handle_ipv6()
71 &eth_hdr->s_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->d_addr = dest_eth_addr[dst_port]; in l3fwd_lpm_simple_forward()
47 &eth_hdr->s_addr); in l3fwd_lpm_simple_forward()
65 *(uint64_t *)&eth_hdr->d_addr = dest_eth_addr[dst_port]; in l3fwd_lpm_simple_forward()
69 &eth_hdr->s_addr); in l3fwd_lpm_simple_forward()
H A Dl3fwd_lpm.c111 struct rte_ether_hdr *eth_hdr; in lpm_get_dst_port() local
115 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in lpm_get_dst_port()
116 ipv4_hdr = (struct rte_ipv4_hdr *)(eth_hdr + 1); in lpm_get_dst_port()
122 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in lpm_get_dst_port()
123 ipv6_hdr = (struct rte_ipv6_hdr *)(eth_hdr + 1); in lpm_get_dst_port()
143 struct rte_ether_hdr *eth_hdr; in lpm_get_dst_port_with_ipv4() local
153 ipv6_hdr = (struct rte_ipv6_hdr *)(eth_hdr + 1); in lpm_get_dst_port_with_ipv4()
267 struct rte_ether_hdr *eth_hdr = rte_pktmbuf_mtod(mbuf, in lpm_process_event_pkt() local
292 &eth_hdr->s_addr); in lpm_process_event_pkt()
585 struct rte_ether_hdr *eth_hdr; in lpm_parse_ptype() local
[all …]
H A Dl3fwd_altivec.h128 struct rte_ether_hdr *eth_hdr; in process_packet() local
131 eth_hdr = rte_pktmbuf_mtod(pkt, struct rte_ether_hdr *); in process_packet()
133 te = *(vector unsigned int *)eth_hdr; in process_packet()
136 rfc1812_process((struct rte_ipv4_hdr *)(eth_hdr + 1), dst_port, in process_packet()
146 *(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()
/f-stack/dpdk/lib/librte_net/
H A Drte_arp.c13 struct rte_ether_hdr *eth_hdr; in rte_net_make_rarp_packet() local
24 eth_hdr = (struct rte_ether_hdr *) in rte_net_make_rarp_packet()
26 if (eth_hdr == NULL) { in rte_net_make_rarp_packet()
32 memset(eth_hdr->d_addr.addr_bytes, 0xff, RTE_ETHER_ADDR_LEN); in rte_net_make_rarp_packet()
33 rte_ether_addr_copy(mac, &eth_hdr->s_addr); in rte_net_make_rarp_packet()
34 eth_hdr->ether_type = RTE_BE16(RTE_ETHER_TYPE_RARP); in rte_net_make_rarp_packet()
37 rarp = (struct rte_arp_hdr *)(eth_hdr + 1); in rte_net_make_rarp_packet()
/f-stack/dpdk/lib/librte_node/
H A Dethdev_rx.c72 struct rte_ether_hdr *eth_hdr; in eth_pkt_parse_cb() local
109 eth_hdr = rte_pktmbuf_mtod(mbuf0, struct rte_ether_hdr *); in eth_pkt_parse_cb()
110 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
114 eth_hdr = rte_pktmbuf_mtod(mbuf1, struct rte_ether_hdr *); in eth_pkt_parse_cb()
115 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
119 eth_hdr = rte_pktmbuf_mtod(mbuf2, struct rte_ether_hdr *); in eth_pkt_parse_cb()
120 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
124 eth_hdr = rte_pktmbuf_mtod(mbuf3, struct rte_ether_hdr *); in eth_pkt_parse_cb()
125 etype = eth_hdr->ether_type; in eth_pkt_parse_cb()
136 eth_hdr = rte_pktmbuf_mtod(mbuf0, struct rte_ether_hdr *); in eth_pkt_parse_cb()
[all …]
/f-stack/dpdk/app/test/
H A Dtest_sched.c96 struct rte_ether_hdr *eth_hdr; in prepare_pkt() local
101 eth_hdr = rte_pktmbuf_mtod(mbuf, struct rte_ether_hdr *); in prepare_pkt()
102 vlan1 = (struct rte_vlan_hdr *)(&eth_hdr->ether_type); in prepare_pkt()
104 (uintptr_t)&eth_hdr->ether_type + sizeof(struct rte_vlan_hdr)); in prepare_pkt()
105 eth_hdr = (struct rte_ether_hdr *)( in prepare_pkt()
106 (uintptr_t)&eth_hdr->ether_type + in prepare_pkt()
109 (uintptr_t)eth_hdr + sizeof(eth_hdr->ether_type)); in prepare_pkt()
113 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_IPV4); in prepare_pkt()
H A Dpacket_burst_generator.c54 initialize_eth_header(struct rte_ether_hdr *eth_hdr, in initialize_eth_header() argument
59 rte_ether_addr_copy(dst_mac, &eth_hdr->d_addr); in initialize_eth_header()
60 rte_ether_addr_copy(src_mac, &eth_hdr->s_addr); in initialize_eth_header()
64 (uint8_t *)eth_hdr + sizeof(struct rte_ether_hdr)); in initialize_eth_header()
66 eth_hdr->ether_type = rte_cpu_to_be_16(RTE_ETHER_TYPE_VLAN); in initialize_eth_header()
71 eth_hdr->ether_type = rte_cpu_to_be_16(ether_type); in initialize_eth_header()
260 struct rte_ether_hdr *eth_hdr, uint8_t vlan_enabled, in generate_packet_burst() argument
302 copy_buf_to_pkt(eth_hdr, eth_hdr_size, pkt, 0); in generate_packet_burst()
340 struct rte_mbuf **pkts_burst, struct rte_ether_hdr *eth_hdr, in generate_packet_burst_proto() argument
383 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,
/f-stack/dpdk/examples/bond/
H A Dmain.c331 (struct rte_vlan_hdr *)(eth_hdr + 1); in get_vlan_offset()
365 struct rte_ether_hdr *eth_hdr; in lcore_main() local
407 eth_hdr = rte_pktmbuf_mtod(pkts[i], in lcore_main()
409 ether_type = eth_hdr->ether_type; in lcore_main()
412 offset = get_vlan_offset(eth_hdr, &ether_type); in lcore_main()
421 (char *)(eth_hdr + 1) + offset); in lcore_main()
426 rte_ether_addr_copy(&eth_hdr->s_addr, &eth_hdr->d_addr); in lcore_main()
447 rte_ether_addr_copy(&eth_hdr->s_addr, &eth_hdr->d_addr); in lcore_main()
490 struct rte_ether_hdr *eth_hdr; in cmd_obj_send_parsed() local
524 memset(&eth_hdr->d_addr, 0xFF, RTE_ETHER_ADDR_LEN); in cmd_obj_send_parsed()
[all …]
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c101 struct rte_ether_hdr *eth_hdr; in parse_ptype() local
106 ether_type = eth_hdr->ether_type; in parse_ptype()
895 struct rte_ether_hdr *eth_hdr[8]; in simple_ipv4_fwd_8pkts() local
1125 struct rte_ether_hdr *eth_hdr[8]; in simple_ipv6_fwd_8pkts() local
1240 struct rte_ether_hdr *eth_hdr; in l3fwd_simple_forward() local
1275 &eth_hdr->s_addr); in l3fwd_simple_forward()
1297 &eth_hdr->s_addr); in l3fwd_simple_forward()
1360 struct rte_ether_hdr *eth_hdr; in get_dst_port() local
1385 struct rte_ether_hdr *eth_hdr; in process_packet() local
1398 te = _mm_load_si128((__m128i *)eth_hdr); in process_packet()
[all …]
/f-stack/dpdk/examples/ptpclient/
H A Dptpclient.c380 struct rte_ether_hdr *eth_hdr; in parse_fup() local
426 rte_ether_addr_copy(&eth_addr, &eth_hdr->s_addr); in parse_fup()
431 eth_hdr->ether_type = htons(PTP_PROTOCOL); in parse_fup()
449 client_clkid->id[0] = eth_hdr->s_addr.addr_bytes[0]; in parse_fup()
450 client_clkid->id[1] = eth_hdr->s_addr.addr_bytes[1]; in parse_fup()
451 client_clkid->id[2] = eth_hdr->s_addr.addr_bytes[2]; in parse_fup()
454 client_clkid->id[5] = eth_hdr->s_addr.addr_bytes[3]; in parse_fup()
455 client_clkid->id[6] = eth_hdr->s_addr.addr_bytes[4]; in parse_fup()
456 client_clkid->id[7] = eth_hdr->s_addr.addr_bytes[5]; in parse_fup()
566 struct rte_ether_hdr *eth_hdr; in parse_ptp_frames() local
[all …]

123