Home
last modified time | relevance | path

Searched refs:dst_port (Results 1 – 25 of 140) sorted by relevance

123456

/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_altivec.h73 &dst_port[0], pkt[0]->packet_type); in processx4_step3()
76 &dst_port[1], pkt[1]->packet_type); in processx4_step3()
79 &dst_port[2], pkt[2]->packet_type); in processx4_step3()
82 &dst_port[3], pkt[3]->packet_type); in processx4_step3()
154 uint16_t dst_port[MAX_PKT_BURST], int nb_rx) in send_packets_multi()
173 processx4_step3(pkts_burst, dst_port); in send_packets_multi()
176 dp1 = *(vector unsigned short *)dst_port; in send_packets_multi()
186 &dst_port[j - FWDSTEP + 1]); in send_packets_multi()
210 dlp = dst_port[j - 1]; in send_packets_multi()
220 process_packet(pkts_burst[j], dst_port + j); in send_packets_multi()
[all …]
H A Dl3fwd_sse.h28 ve[0] = val_eth[dst_port[0]]; in processx4_step3()
31 ve[1] = val_eth[dst_port[1]]; in processx4_step3()
34 ve[2] = val_eth[dst_port[2]]; in processx4_step3()
37 ve[3] = val_eth[dst_port[3]]; in processx4_step3()
53 &dst_port[0], pkt[0]->packet_type); in processx4_step3()
56 &dst_port[1], pkt[1]->packet_type); in processx4_step3()
114 ve = val_eth[dst_port[0]]; in process_packet()
160 &dst_port[j - FWDSTEP + 1]); in send_packets_multi()
168 sizeof(dst_port[0])); in send_packets_multi()
182 dlp = dst_port[j - 1]; in send_packets_multi()
[all …]
H A Dl3fwd_lpm.h14 uint16_t dst_port; in l3fwd_lpm_simple_forward() local
33 if (dst_port >= RTE_MAX_ETHPORTS || in l3fwd_lpm_simple_forward()
34 (enabled_port_mask & 1 << dst_port) == 0) in l3fwd_lpm_simple_forward()
35 dst_port = portid; in l3fwd_lpm_simple_forward()
46 rte_ether_addr_copy(&ports_eth_addr[dst_port], in l3fwd_lpm_simple_forward()
49 send_single_packet(qconf, m, dst_port); in l3fwd_lpm_simple_forward()
60 if (dst_port >= RTE_MAX_ETHPORTS || in l3fwd_lpm_simple_forward()
61 (enabled_port_mask & 1 << dst_port) == 0) in l3fwd_lpm_simple_forward()
62 dst_port = portid; in l3fwd_lpm_simple_forward()
68 rte_ether_addr_copy(&ports_eth_addr[dst_port], in l3fwd_lpm_simple_forward()
[all …]
H A Dl3fwd_em.h13 uint16_t dst_port; in l3fwd_em_handle_ipv4() local
29 if (dst_port >= RTE_MAX_ETHPORTS || in l3fwd_em_handle_ipv4()
30 (enabled_port_mask & 1 << dst_port) == 0) in l3fwd_em_handle_ipv4()
31 dst_port = portid; in l3fwd_em_handle_ipv4()
45 return dst_port; in l3fwd_em_handle_ipv4()
54 uint16_t dst_port; in l3fwd_em_handle_ipv6() local
62 if (dst_port >= RTE_MAX_ETHPORTS || in l3fwd_em_handle_ipv6()
64 dst_port = portid; in l3fwd_em_handle_ipv6()
73 return dst_port; in l3fwd_em_handle_ipv6()
81 uint16_t dst_port; in l3fwd_em_simple_forward() local
[all …]
H A Dl3fwd_neon.h53 &dst_port[0], pkt[0]->packet_type); in processx4_step3()
56 &dst_port[1], pkt[1]->packet_type); in processx4_step3()
59 &dst_port[2], pkt[2]->packet_type); in processx4_step3()
62 &dst_port[3], pkt[3]->packet_type); in processx4_step3()
132 uint16_t dst_port[MAX_PKT_BURST], int nb_rx) in send_packets_multi()
151 processx4_step3(pkts_burst, dst_port); in send_packets_multi()
154 dp1 = vld1q_u16(dst_port); in send_packets_multi()
185 dlp = dst_port[j - 1]; in send_packets_multi()
195 process_packet(pkts_burst[j], dst_port + j); in send_packets_multi()
196 GROUP_PORT_STEP(dlp, dst_port, lp, pnum, j); in send_packets_multi()
[all …]
H A Dl3fwd_em_hlm.h42 dst_port[i] = ((ret[i] < 0) ? in em_get_dst_port_ipv4xN()
47 dst_port[i] = portid; in em_get_dst_port_ipv4xN()
74 dst_port[i] = portid; in em_get_dst_port_ipv6xN()
80 uint16_t dst_port[]) in em_get_dst_port_ipv4xN_events() argument
101 dst_port[i] = m[i]->port; in em_get_dst_port_ipv4xN_events()
107 uint16_t dst_port[]) in em_get_dst_port_ipv6xN_events() argument
128 dst_port[i] = m[i]->port; in em_get_dst_port_ipv6xN_events()
224 &dst_port[j]); in l3fwd_em_send_packets()
229 &dst_port[j]); in l3fwd_em_send_packets()
291 &dst_port[j]); in l3fwd_em_process_events()
[all …]
H A Dl3fwd_lpm_neon.h92 uint16_t dst_port[MAX_PKT_BURST]; in l3fwd_lpm_send_packets() local
113 &pkts_burst[j], &dst_port[j]); in l3fwd_lpm_send_packets()
118 &dst_port[j]); in l3fwd_lpm_send_packets()
146 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], in l3fwd_lpm_send_packets()
151 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], in l3fwd_lpm_send_packets()
156 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], in l3fwd_lpm_send_packets()
161 send_packets_multi(qconf, pkts_burst, dst_port, nb_rx); in l3fwd_lpm_send_packets()
H A Dl3fwd_lpm_sse.h89 uint16_t dst_port[MAX_PKT_BURST]; in l3fwd_lpm_send_packets() local
100 ipv4_flag[j / FWDSTEP], portid, &pkts_burst[j], &dst_port[j]); in l3fwd_lpm_send_packets()
105 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
109 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
113 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
117 send_packets_multi(qconf, pkts_burst, dst_port, nb_rx); in l3fwd_lpm_send_packets()
H A Dl3fwd_lpm_altivec.h103 uint16_t dst_port[MAX_PKT_BURST]; in l3fwd_lpm_send_packets() local
115 portid, &pkts_burst[j], &dst_port[j]); in l3fwd_lpm_send_packets()
120 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
124 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
128 dst_port[j] = lpm_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_lpm_send_packets()
133 send_packets_multi(qconf, pkts_burst, dst_port, nb_rx); in l3fwd_lpm_send_packets()
H A Dl3fwd_em_sequential.h80 uint16_t dst_port[MAX_PKT_BURST]; in l3fwd_em_send_packets() local
93 dst_port[j] = em_get_dst_port(qconf, pkts_burst[j], portid); in l3fwd_em_send_packets()
96 send_packets_multi(qconf, pkts_burst, dst_port, nb_rx); in l3fwd_em_send_packets()
/f-stack/dpdk/drivers/net/enic/
H A Denic_clsf.c89 input->flow.udp4_flow.dst_port); in copy_fltr_v1()
120 if (input->flow.udp4_flow.dst_port) { in copy_fltr_v2()
122 udp_val.dst_port = input->flow.udp4_flow.dst_port; in copy_fltr_v2()
136 if (input->flow.tcp4_flow.dst_port) { in copy_fltr_v2()
138 tcp_val.dst_port = input->flow.tcp4_flow.dst_port; in copy_fltr_v2()
154 sctp_val.dst_port = input->flow.sctp4_flow.dst_port; in copy_fltr_v2()
216 if (input->flow.udp6_flow.dst_port) { in copy_fltr_v2()
218 udp_val.dst_port = input->flow.udp6_flow.dst_port; in copy_fltr_v2()
231 if (input->flow.tcp6_flow.dst_port) { in copy_fltr_v2()
233 tcp_val.dst_port = input->flow.tcp6_flow.dst_port; in copy_fltr_v2()
[all …]
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c897 uint16_t dst_port[8]; in simple_ipv4_fwd_8pkts() local
1027 dst_port[0] = portid; in simple_ipv4_fwd_8pkts()
1030 dst_port[1] = portid; in simple_ipv4_fwd_8pkts()
1033 dst_port[2] = portid; in simple_ipv4_fwd_8pkts()
1036 dst_port[3] = portid; in simple_ipv4_fwd_8pkts()
1124 uint16_t dst_port[8]; in simple_ipv6_fwd_8pkts() local
1242 uint16_t dst_port; in l3fwd_simple_forward() local
1263 dst_port = portid; in l3fwd_simple_forward()
1290 dst_port = portid; in l3fwd_simple_forward()
1401 dst_port[0] = dp; in process_packet()
[all …]
/f-stack/dpdk/examples/l2fwd-event/
H A Dl2fwd_poll.c12 uint32_t dst_port; in l2fwd_poll_simple_forward() local
15 dst_port = rsrc->dst_ports[portid]; in l2fwd_poll_simple_forward()
18 l2fwd_mac_updating(m, dst_port, &rsrc->eth_addr[dst_port]); in l2fwd_poll_simple_forward()
21 dst_port]; in l2fwd_poll_simple_forward()
22 sent = rte_eth_tx_buffer(dst_port, 0, buffer, m); in l2fwd_poll_simple_forward()
24 rsrc->port_stats[dst_port].tx += sent; in l2fwd_poll_simple_forward()
/f-stack/dpdk/lib/librte_ethdev/
H A Drte_eth_ctrl.h59 uint16_t dst_port; /**< Destination port in big endian. */ member
179 uint16_t dst_port; /**< UDP destination port in big endian. */ member
188 uint16_t dst_port; /**< TCP destination port in big endian. */ member
197 uint16_t dst_port; /**< SCTP destination port in big endian. */ member
218 uint16_t dst_port; /**< UDP destination port in big endian. */ member
227 uint16_t dst_port; /**< TCP destination port in big endian. */ member
236 uint16_t dst_port; /**< SCTP destination port in big endian. */ member
/f-stack/dpdk/drivers/net/ice/
H A Dice_acl_filter.c328 input->ip.v4.dst_port = filter->input.ip.v4.dst_port; in ice_acl_set_input_set()
333 input->mask.v4.dst_port = filter->input.mask.v4.dst_port; in ice_acl_set_input_set()
793 tcp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
796 tcp_spec->hdr.dst_port; in ice_acl_parse_pattern()
798 tcp_mask->hdr.dst_port; in ice_acl_parse_pattern()
839 udp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
842 udp_spec->hdr.dst_port; in ice_acl_parse_pattern()
844 udp_mask->hdr.dst_port; in ice_acl_parse_pattern()
875 sctp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
878 sctp_spec->hdr.dst_port; in ice_acl_parse_pattern()
[all …]
/f-stack/freebsd/netinet/libalias/
H A Dalias_db.c293 u_short dst_port; member
429 n += dst_port; in StartPointOut()
720 u_short dst_port, in FindNewPortGroup() argument
931 lnk->dst_port = dst_port; in AddLink()
972 if (dst_port == 0) in AddLink()
1055 u_short dst_port, in ReLink() argument
1082 u_short dst_port, in _FindLinkOut() argument
1095 lnk->dst_port == dst_port && in _FindLinkOut()
1186 if (dst_port == 0) in _FindLinkIn()
1199 && lnk->dst_port == dst_port in _FindLinkIn()
[all …]
/f-stack/dpdk/drivers/net/hinic/
H A Dhinic_pmd_ethdev.h49 uint16_t dst_port; member
113 uint16_t dst_port; member
169 u32 dst_port:16; member
192 u32 dst_port:16;
206 u32 dst_port:16; member
227 u32 dst_port:16;
/f-stack/dpdk/app/test/
H A Dtest_thash.c16 uint16_t dst_port; member
25 uint16_t dst_port; member
95 tuple.v4.dport = v4_tbl[i].dst_port; in test_thash()
122 tuple.v6.dport = v6_tbl[i].dst_port; in test_thash()
H A Dpacket_burst_generator.c95 uint16_t dst_port, uint16_t pkt_data_len) in initialize_udp_header() argument
102 udp_hdr->dst_port = rte_cpu_to_be_16(dst_port); in initialize_udp_header()
111 uint16_t dst_port, uint16_t pkt_data_len) in initialize_tcp_header() argument
119 tcp_hdr->dst_port = rte_cpu_to_be_16(dst_port); in initialize_tcp_header()
126 uint16_t dst_port, uint16_t pkt_data_len) in initialize_sctp_header() argument
133 sctp_hdr->dst_port = rte_cpu_to_be_16(dst_port); in initialize_sctp_header()
H A Dpacket_burst_generator.h39 uint16_t dst_port, uint16_t pkt_data_len);
43 uint16_t dst_port, uint16_t pkt_data_len);
47 uint16_t dst_port, uint16_t pkt_data_len);
/f-stack/dpdk/lib/librte_flow_classify/
H A Drte_flow_classify_parse.c360 filter->dst_port_mask = tcp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
375 filter->dst_port = tcp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
395 filter->dst_port_mask = udp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
399 filter->dst_port = udp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
418 filter->dst_port_mask = sctp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
422 filter->dst_port = sctp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
/f-stack/dpdk/examples/flow_classify/
H A Dflow_classify.c146 offsetof(struct rte_tcp_hdr, dst_port),
446 ntuple_filter->dst_port = (uint16_t)temp; in parse_ipv4_5tuple_rule()
558 udp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
563 udp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
584 tcp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
588 tcp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
606 sctp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
611 sctp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
/f-stack/dpdk/app/test-pmd/
H A D5tswap.c64 tcp_hdr->src_port = tcp_hdr->dst_port; in swap_tcp()
65 tcp_hdr->dst_port = port; in swap_tcp()
75 udp_hdr->src_port = udp_hdr->dst_port; in swap_udp()
76 udp_hdr->dst_port = port; in swap_udp()
/f-stack/dpdk/drivers/net/mlx4/
H A Dmlx4_flow.c424 (uint16_t)(mask->hdr.dst_port + 1) > UINT16_C(1))) { in mlx4_flow_merge_udp()
428 if (mask && mask->hdr.dst_port && flow->priority) { in mlx4_flow_merge_udp()
443 udp->val.dst_port = spec->hdr.dst_port; in mlx4_flow_merge_udp()
445 udp->mask.dst_port = mask->hdr.dst_port; in mlx4_flow_merge_udp()
449 udp->val.dst_port &= udp->mask.dst_port; in mlx4_flow_merge_udp()
489 (uint16_t)(mask->hdr.dst_port + 1) > UINT16_C(1))) { in mlx4_flow_merge_tcp()
503 tcp->val.dst_port = spec->hdr.dst_port; in mlx4_flow_merge_tcp()
505 tcp->mask.dst_port = mask->hdr.dst_port; in mlx4_flow_merge_tcp()
509 tcp->val.dst_port &= tcp->mask.dst_port; in mlx4_flow_merge_tcp()
621 .dst_port = RTE_BE16(0xffff),
[all …]
/f-stack/dpdk/drivers/net/ice/base/
H A Dice_fdir.c1052 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
1075 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
1089 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
1187 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
1192 input->ip.v6.dst_port); in ice_fdir_get_gen_prgm_pkt()
1206 input->ip.v6.dst_port); in ice_fdir_get_gen_prgm_pkt()
1219 input->ip.v6.dst_port); in ice_fdir_get_gen_prgm_pkt()
1232 input->ip.v6.dst_port); in ice_fdir_get_gen_prgm_pkt()
1389 a->ip.v4.dst_port == b->ip.v4.dst_port && in ice_fdir_comp_rules()
1405 if (a->ip.v6.dst_port == b->ip.v6.dst_port && in ice_fdir_comp_rules()
[all …]

123456