Home
last modified time | relevance | path

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

123456

/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()
155 uint16_t dst_port[MAX_PKT_BURST], int nb_rx) in send_packets_multi()
174 processx4_step3(pkts_burst, dst_port); in send_packets_multi()
177 dp1 = *(__vector unsigned short *)dst_port; in send_packets_multi()
187 &dst_port[j - FWDSTEP + 1]); in send_packets_multi()
211 dlp = dst_port[j - 1]; in send_packets_multi()
221 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_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_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_em_hlm.h47 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()
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()
296 &dst_port[j]); in l3fwd_em_process_events()
359 &dst_port[j]); in l3fwd_em_process_event_vector()
[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()
/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()
/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()
804 tcp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
807 tcp_spec->hdr.dst_port; in ice_acl_parse_pattern()
809 tcp_mask->hdr.dst_port; in ice_acl_parse_pattern()
850 udp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
853 udp_spec->hdr.dst_port; in ice_acl_parse_pattern()
855 udp_mask->hdr.dst_port; in ice_acl_parse_pattern()
886 sctp_mask->hdr.dst_port) { in ice_acl_parse_pattern()
889 sctp_spec->hdr.dst_port; in ice_acl_parse_pattern()
[all …]
/dpdk/lib/ethdev/
H A Drte_eth_ctrl.h60 uint16_t dst_port; /**< Destination port in big endian. */ member
180 uint16_t dst_port; /**< UDP destination port in big endian. */ member
189 uint16_t dst_port; /**< TCP destination port in big endian. */ member
198 uint16_t dst_port; /**< SCTP destination port in big endian. */ member
219 uint16_t dst_port; /**< UDP destination port in big endian. */ member
228 uint16_t dst_port; /**< TCP destination port in big endian. */ member
237 uint16_t dst_port; /**< SCTP destination port in big endian. */ member
/dpdk/app/test/
H A Dpacket_burst_generator.c96 uint16_t dst_port, uint16_t pkt_data_len) in initialize_udp_header() argument
103 udp_hdr->dst_port = rte_cpu_to_be_16(dst_port); in initialize_udp_header()
112 uint16_t dst_port, uint16_t pkt_data_len) in initialize_tcp_header() argument
120 tcp_hdr->dst_port = rte_cpu_to_be_16(dst_port); in initialize_tcp_header()
128 uint16_t dst_port, uint16_t pkt_data_len) in initialize_sctp_header() argument
135 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);
/dpdk/lib/flow_classify/
H A Drte_flow_classify_parse.c359 filter->dst_port_mask = tcp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
374 filter->dst_port = tcp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
394 filter->dst_port_mask = udp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
398 filter->dst_port = udp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
417 filter->dst_port_mask = sctp_mask->hdr.dst_port; in classify_parse_ntuple_filter()
421 filter->dst_port = sctp_spec->hdr.dst_port; in classify_parse_ntuple_filter()
/dpdk/drivers/net/hinic/
H A Dhinic_pmd_ethdev.h65 uint16_t dst_port; member
129 uint16_t dst_port; member
185 u32 dst_port:16; member
208 u32 dst_port:16;
222 u32 dst_port:16; member
243 u32 dst_port:16;
H A Dhinic_pmd_flow.c660 filter->dst_port = tcp_spec->hdr.dst_port; in hinic_ntuple_item_check_l4()
1115 rule->hinic_fdir.dst_port = tcp_spec->hdr.dst_port; in hinic_tcam_normal_item_check_l4()
1150 rule->hinic_fdir.dst_port = udp_spec->hdr.dst_port; in hinic_tcam_normal_item_check_l4()
1302 tcp_mask->hdr.dst_port; in hinic_tunnel_inner_item_check_l4()
1312 tcp_spec->hdr.dst_port; in hinic_tunnel_inner_item_check_l4()
1342 udp_mask->hdr.dst_port; in hinic_tunnel_inner_item_check_l4()
1352 udp_spec->hdr.dst_port; in hinic_tunnel_inner_item_check_l4()
1706 hinic_filter_info->dst_port = filter->dst_port; in ntuple_port_filter()
2537 tcam_key->key_info.dst_port = rule->hinic_fdir.dst_port; in hinic_fdir_tcam_ipv4_init()
2563 tcam_key->key_info.dst_port = in hinic_fdir_tcam_ipv4_init()
[all …]
/dpdk/examples/flow_classify/
H A Dflow_classify.c143 offsetof(struct rte_tcp_hdr, dst_port),
452 ntuple_filter->dst_port = (uint16_t)temp; in parse_ipv4_5tuple_rule()
564 udp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
569 udp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
590 tcp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
594 tcp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
612 sctp_spec.hdr.dst_port = ntuple_filter->dst_port; in add_classify_rule()
617 sctp_mask.hdr.dst_port = ntuple_filter->dst_port_mask; in add_classify_rule()
/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 …]
/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()
/dpdk/drivers/net/mlx5/
H A Dmlx5_flow_verbs.c677 tcp.val.dst_port = spec->hdr.dst_port; in flow_verbs_translate_item_tcp()
679 tcp.mask.dst_port = mask->hdr.dst_port; in flow_verbs_translate_item_tcp()
683 tcp.val.dst_port &= tcp.mask.dst_port; in flow_verbs_translate_item_tcp()
716 udp.val.dst_port = spec->hdr.dst_port; in flow_verbs_translate_item_udp()
718 udp.mask.dst_port = mask->hdr.dst_port; in flow_verbs_translate_item_udp()
722 udp.val.dst_port &= udp.mask.dst_port; in flow_verbs_translate_item_udp()
727 if (!(udp.val.dst_port & udp.mask.dst_port)) { in flow_verbs_translate_item_udp()
731 udp.mask.dst_port = 0xffff; in flow_verbs_translate_item_udp()
735 udp.mask.dst_port = 0xffff; in flow_verbs_translate_item_udp()
1361 (spec->hdr.dst_port & in flow_verbs_validate()
[all …]
/dpdk/drivers/net/qede/
H A Dqede_filter.c367 udp->dst_port = arfs->tuple.dst_port; in qede_arfs_construct_pkt()
377 tcp->dst_port = arfs->tuple.dst_port; in qede_arfs_construct_pkt()
403 udp->dst_port = arfs->tuple.dst_port; in qede_arfs_construct_pkt()
409 tcp->dst_port = arfs->tuple.dst_port; in qede_arfs_construct_pkt()
844 flow->entry.tuple.dst_port = in qede_flow_parse_pattern()
845 spec->hdr.dst_port; in qede_flow_parse_pattern()
859 flow->entry.tuple.dst_port = in qede_flow_parse_pattern()
860 spec->hdr.dst_port; in qede_flow_parse_pattern()
/dpdk/drivers/net/ice/base/
H A Dice_fdir.c3508 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3531 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3545 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3579 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3604 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3632 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3743 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
3766 input->ip.v4.dst_port); in ice_fdir_get_gen_prgm_pkt()
4240 a->ip.v4.dst_port == b->ip.v4.dst_port && in ice_fdir_comp_rules()
4256 if (a->ip.v6.dst_port == b->ip.v6.dst_port && in ice_fdir_comp_rules()
[all …]
/dpdk/examples/l2fwd-keepalive/
H A Dmain.c172 unsigned dst_port; in l2fwd_simple_forward() local
175 dst_port = l2fwd_dst_ports[portid]; in l2fwd_simple_forward()
180 *((uint64_t *)tmp) = 0x000000000002 + ((uint64_t)dst_port << 40); in l2fwd_simple_forward()
183 rte_ether_addr_copy(&l2fwd_ports_eth_addr[dst_port], &eth->src_addr); in l2fwd_simple_forward()
185 buffer = tx_buffer[dst_port]; in l2fwd_simple_forward()
186 sent = rte_eth_tx_buffer(dst_port, 0, buffer, m); in l2fwd_simple_forward()
188 port_statistics[dst_port].tx += sent; in l2fwd_simple_forward()

123456