| /dpdk/drivers/common/sfc_efx/base/ |
| H A D | efx_hash.c | 104 a += input[0]; in efx_hash_dwords()
105 b += input[1]; in efx_hash_dwords()
106 c += input[2]; in efx_hash_dwords()
110 input += 3; in efx_hash_dwords()
116 c += input[2]; in efx_hash_dwords()
119 b += input[1]; in efx_hash_dwords()
122 a += input[0]; in efx_hash_dwords()
155 a += ((uint32_t)input[3]); in efx_hash_bytes()
159 b += ((uint32_t)input[7]); in efx_hash_bytes()
166 input += 12; in efx_hash_bytes()
[all …]
|
| /dpdk/drivers/net/ice/base/ |
| H A D | ice_fdir.c | 3056 if (input->dest_ctl == in ice_fdir_get_prgm_desc()
3341 flow = input->flow_type; in ice_fdir_get_gen_prgm_pkt()
3558 input->ip.v4.proto); in ice_fdir_get_gen_prgm_pkt()
3658 input->ip.v4.proto); in ice_fdir_get_gen_prgm_pkt()
3690 input->ip.v4.proto); in ice_fdir_get_gen_prgm_pkt()
3789 input->ip.v6.proto); in ice_fdir_get_gen_prgm_pkt()
3957 input->ip.v4.tos); in ice_fdir_get_gen_prgm_pkt()
3972 input->ip.v4.tos); in ice_fdir_get_gen_prgm_pkt()
3985 input->ip.v4.tos); in ice_fdir_get_gen_prgm_pkt()
4102 if (input->flex_fltr) in ice_fdir_get_gen_prgm_pkt()
[all …]
|
| /dpdk/drivers/net/ice/ |
| H A D | ice_acl_filter.c | 315 if (!input) in ice_acl_set_input_set()
318 input->q_index = filter->input.q_index; in ice_acl_set_input_set()
319 input->dest_vsi = filter->input.dest_vsi; in ice_acl_set_input_set()
320 input->dest_ctl = filter->input.dest_ctl; in ice_acl_set_input_set()
322 input->flow_type = filter->input.flow_type; in ice_acl_set_input_set()
328 input->ip.v4.dst_port = filter->input.ip.v4.dst_port; in ice_acl_set_input_set()
330 input->ip.v4.dst_ip = filter->input.ip.v4.dst_ip; in ice_acl_set_input_set()
331 input->ip.v4.src_ip = filter->input.ip.v4.src_ip; in ice_acl_set_input_set()
359 ice_memcpy(&input->ip.v4, &filter->input.ip.v4, in ice_acl_set_input_set()
362 ice_memcpy(&input->mask.v4, &filter->input.mask.v4, in ice_acl_set_input_set()
[all …]
|
| H A D | ice_switch_filter.c | 547 uint64_t *input = NULL; in ice_switch_parse_pattern() local
990 input = &inner_input_set; in ice_switch_parse_pattern()
1028 input = &inner_input_set; in ice_switch_parse_pattern()
1072 input = &outer_input_set; in ice_switch_parse_pattern()
1078 *input |= in ice_switch_parse_pattern()
1082 *input |= in ice_switch_parse_pattern()
1125 input = &outer_input_set; in ice_switch_parse_pattern()
1167 input = &outer_input_set; in ice_switch_parse_pattern()
1214 input = &outer_input_set; in ice_switch_parse_pattern()
1275 input = &outer_input_set; in ice_switch_parse_pattern()
[all …]
|
| H A D | ice_fdir_filter.c | 1241 struct ice_fdir_fltr *input = &filter->input; in ice_fdir_extract_fltr_key() local
1416 if (filter->input.cnt_ena) { in ice_fdir_create_filter()
1698 if (filter->input.q_index >= in ice_fdir_parse_action()
1706 filter->input.dest_ctl = in ice_fdir_parse_action()
1712 filter->input.dest_ctl = in ice_fdir_parse_action()
1718 filter->input.dest_ctl = in ice_fdir_parse_action()
1783 filter->input.dest_ctl = in ice_fdir_parse_action()
1998 &filter->input.ext_data; in ice_fdir_parse_pattern()
2014 &filter->input.ip.v4; in ice_fdir_parse_pattern()
2099 &filter->input.ip.v6; in ice_fdir_parse_pattern()
[all …]
|
| /dpdk/drivers/net/dpaa2/base/ |
| H A D | dpaa2_tlu_hash.c | 37 static unsigned int stage(unsigned int input) in stage() argument
44 input ^= input >> 16; /* xor lower */ in stage()
45 input ^= input << 16; /* move original lower to upper */ in stage()
48 sbox_out |= (sbox_tbl[(input >> i) & 0xf]) << i; in stage()
57 static unsigned int fast_stage(unsigned int input) in fast_stage() argument
63 input ^= input >> 16; /* xor lower */ in fast_stage()
64 input ^= input << 16; /* move original lower to upper */ in fast_stage()
67 pbox_out |= mix_tbl[i >> 2][(input >> i) & 0xf]; in fast_stage()
139 input ^= input << 16; /* (X^Y,Y) */ in hash_init()
140 input ^= input >> 16; /* (X^Y,X) */ in hash_init()
[all …]
|
| /dpdk/drivers/bus/dpaa/base/qbman/ |
| H A D | process.c | 243 input.index = portal->index; in qman_allocate_raw_portal()
245 input.cpu = portal->cpu; in qman_allocate_raw_portal()
254 portal->cinh = input.cinh; in qman_allocate_raw_portal()
255 portal->cena = input.cena; in qman_allocate_raw_portal()
265 input.cinh = portal->cinh; in qman_free_raw_portal()
266 input.cena = portal->cena; in qman_free_raw_portal()
278 input.enable_stash = 0; in bman_allocate_raw_portal()
284 portal->cinh = input.cinh; in bman_allocate_raw_portal()
285 portal->cena = input.cena; in bman_allocate_raw_portal()
295 input.cinh = portal->cinh; in bman_free_raw_portal()
[all …]
|
| /dpdk/lib/acl/ |
| H A D | acl_run_avx2.h | 168 ymm_t input[2], tr_lo[2], tr_hi[2]; in search_avx2x16() local
212 input[0] = _mm256_set_epi32(in[7], in[6], in[5], in[4], in search_avx2x16()
224 input[1] = _mm256_set_epi32(in[7], in[6], in[5], in[4], in search_avx2x16()
227 input[0] = transition8(input[0], flows.trans, in search_avx2x16()
229 input[1] = transition8(input[1], flows.trans, in search_avx2x16()
232 input[0] = transition8(input[0], flows.trans, in search_avx2x16()
234 input[1] = transition8(input[1], flows.trans, in search_avx2x16()
237 input[0] = transition8(input[0], flows.trans, in search_avx2x16()
239 input[1] = transition8(input[1], flows.trans, in search_avx2x16()
242 input[0] = transition8(input[0], flows.trans, in search_avx2x16()
[all …]
|
| H A D | acl_run_neon.h | 230 int32x4_t input; in search_neon_4() local
245 input = vdupq_n_s32(GET_NEXT_4BYTES(parms, 0)); in search_neon_4()
246 input = vsetq_lane_s32(GET_NEXT_4BYTES(parms, 1), input, 1); in search_neon_4()
247 input = vsetq_lane_s32(GET_NEXT_4BYTES(parms, 2), input, 2); in search_neon_4()
248 input = vsetq_lane_s32(GET_NEXT_4BYTES(parms, 3), input, 3); in search_neon_4()
251 input = transition4(input, flows.trans, index_array); in search_neon_4()
252 input = transition4(input, flows.trans, index_array); in search_neon_4()
253 input = transition4(input, flows.trans, index_array); in search_neon_4()
254 input = transition4(input, flows.trans, index_array); in search_neon_4()
|
| H A D | acl_run_sse.h | 291 xmm_t input, indices1, indices2; in search_sse_4() local
311 input = _mm_cvtsi32_si128(GET_NEXT_4BYTES(parms, 0)); in search_sse_4()
312 input = _mm_insert_epi32(input, GET_NEXT_4BYTES(parms, 1), 1); in search_sse_4()
313 input = _mm_insert_epi32(input, GET_NEXT_4BYTES(parms, 2), 2); in search_sse_4()
314 input = _mm_insert_epi32(input, GET_NEXT_4BYTES(parms, 3), 3); in search_sse_4()
317 input = transition4(input, flows.trans, &indices1, &indices2); in search_sse_4()
318 input = transition4(input, flows.trans, &indices1, &indices2); in search_sse_4()
319 input = transition4(input, flows.trans, &indices1, &indices2); in search_sse_4()
320 input = transition4(input, flows.trans, &indices1, &indices2); in search_sse_4()
|
| H A D | acl_run_scalar.c | 69 scan_forward(uint32_t input, uint32_t max) in scan_forward() argument
71 return (input == 0) ? max : rte_bsf32(input); in scan_forward()
76 uint8_t input) in scalar_transition() argument
87 c = (uint32_t)input * SCALAR_QRANGE_MULT; in scalar_transition()
96 x = ranges >> (input / in scalar_transition()
99 x = input - x; in scalar_transition()
|
| H A D | acl_run_altivec.h | 266 xmm_t input; in search_altivec_4() local
282 input = (xmm_t){GET_NEXT_4BYTES(parms, 0), in search_altivec_4()
288 input = transition4(input, flows.trans, in search_altivec_4()
290 input = transition4(input, flows.trans, in search_altivec_4()
292 input = transition4(input, flows.trans, in search_altivec_4()
294 input = transition4(input, flows.trans, in search_altivec_4()
|
| /dpdk/drivers/net/txgbe/ |
| H A D | txgbe_fdir.c | 528 bucket_hash = txgbe_atr_compute_hash(input, in atr_compute_perfect_hash()
571 bucket_hash = txgbe_atr_compute_hash(input, in atr_compute_signature_hash()
580 sig_hash = txgbe_atr_compute_hash(input, in atr_compute_signature_hash()
594 struct txgbe_atr_input *input, uint8_t queue, in fdir_write_perfect_filter() argument
634 fdircmd |= TXGBE_FDIRPICMD_FT(input->flow_type); in fdir_write_perfect_filter()
731 struct txgbe_atr_input *input) in txgbe_fdir_filter_lookup() argument
765 struct txgbe_atr_input *input) in txgbe_remove_fdir_filter() argument
863 rte_memcpy(&node->input, &rule->input, in txgbe_fdir_filter_program()
886 txgbe_remove_fdir_filter(info, &rule->input); in txgbe_fdir_filter_program()
932 &node->input, in txgbe_fdir_filter_restore()
[all …]
|
| /dpdk/examples/fips_validation/ |
| H A D | fips_dev_self_test.c | 55 } input; member
79 .input = {
124 .input = {
176 .input = {
226 .input = {
279 .input = {
338 .input = {
391 .input = {
438 .input = {
480 .input = {
[all …]
|
| /dpdk/examples/vm_power_manager/ |
| H A D | parse.c | 19 parse_set(const char *input, uint16_t set[], unsigned int num) in parse_set() argument
22 const char *str = input; in parse_set()
80 return str - input; in parse_set()
84 parse_branch_ratio(const char *input, float *branch_ratio) in parse_branch_ratio() argument
86 const char *str = input; in parse_branch_ratio()
118 return str - input; in parse_branch_ratio()
|
| /dpdk/drivers/net/i40e/ |
| H A D | i40e_flow.c | 2320 if (filter->input.flow_ext.is_udp) in i40e_flow_set_filter_spi()
2329 if (filter->input.flow_ext.is_udp) in i40e_flow_set_filter_spi()
2424 filter->input.flow.l2_flow.dst = in i40e_flow_parse_fdir_pattern()
2429 filter->input.flow.l2_flow.src = in i40e_flow_parse_fdir_pattern()
2434 filter->input.flow.l2_flow.dst = in i40e_flow_parse_fdir_pattern()
2436 filter->input.flow.l2_flow.src = in i40e_flow_parse_fdir_pattern()
2499 filter->input.flow_ext.vlan_tci = in i40e_flow_parse_fdir_pattern()
3082 filter->input.flow_ext.is_vf = 1; in i40e_flow_parse_fdir_pattern()
3155 filter->input.pctype = pctype; in i40e_flow_parse_fdir_pattern()
4791 filter->input.ether_type, in i40e_flow_destroy_ethertype_filter()
[all …]
|
| H A D | i40e_fdir.c | 1306 if (input->input.flow_ext.pkt_template) { in i40e_fdir_filter_convert()
1309 rte_hash_crc(input->input.flow.raw_flow.packet, in i40e_fdir_filter_convert()
1310 input->input.flow.raw_flow.length, in i40e_fdir_filter_convert()
1311 input->input.flow.raw_flow.pctype); in i40e_fdir_filter_convert()
1325 (const void *)input, in i40e_sw_fdir_filter_lookup()
1329 (const void *)input); in i40e_sw_fdir_filter_lookup()
1346 &filter->fdir.input, in i40e_sw_fdir_filter_insert()
1350 &filter->fdir.input); in i40e_sw_fdir_filter_insert()
1379 input, in i40e_sw_fdir_filter_del()
1758 pctype = filter->input.pctype; in i40e_flow_add_del_fdir_filter()
[all …]
|
| /dpdk/drivers/net/ixgbe/ |
| H A D | ixgbe_fdir.c | 97 union ixgbe_atr_input *input, uint8_t queue,
813 return ixgbe_atr_compute_hash_82599(input, in atr_compute_perfect_hash_82599()
817 return ixgbe_atr_compute_hash_82599(input, in atr_compute_perfect_hash_82599()
821 return ixgbe_atr_compute_hash_82599(input, in atr_compute_perfect_hash_82599()
870 sig_hash = ixgbe_atr_compute_hash_82599(input, in atr_compute_sig_hash_82599()
884 union ixgbe_atr_input *input, uint8_t queue, in fdir_write_perfect_filter_82599() argument
899 *reg = input->formatted.src_ip[0]; in fdir_write_perfect_filter_82599()
901 *reg = input->formatted.dst_ip[0]; in fdir_write_perfect_filter_82599()
924 if (input->formatted.tunnel_type) in fdir_write_perfect_filter_82599()
930 input->formatted.tni_vni); in fdir_write_perfect_filter_82599()
[all …]
|
| /dpdk/drivers/net/ixgbe/base/ |
| H A D | ixgbe_82599.c | 1596 hi_dword ^= input->dword_stream[i]; in ixgbe_atr_compute_perfect_hash_82599()
1841 union ixgbe_atr_input *input, in ixgbe_fdir_write_perfect_filter_82599() argument
1854 input->formatted.src_ip[0]); in ixgbe_fdir_write_perfect_filter_82599()
1856 input->formatted.src_ip[1]); in ixgbe_fdir_write_perfect_filter_82599()
1858 input->formatted.src_ip[2]); in ixgbe_fdir_write_perfect_filter_82599()
1862 input->formatted.src_ip[0]); in ixgbe_fdir_write_perfect_filter_82599()
1867 input->formatted.dst_ip[0]); in ixgbe_fdir_write_perfect_filter_82599()
1931 union ixgbe_atr_input *input, in ixgbe_fdir_erase_perfect_filter_82599() argument
1979 union ixgbe_atr_input *input, in ixgbe_fdir_add_perfect_filter_82599() argument
1996 if (input->formatted.dst_port || input->formatted.src_port) { in ixgbe_fdir_add_perfect_filter_82599()
[all …]
|
| /dpdk/doc/guides/compressdevs/ |
| H A D | overview.rst | 17 to let input buffers pass-through it, copying the input to the output,
22 which means PMD supports different scatter-gather styled input and output buffers
27 which means PMD supports input from scatter-gathered styled buffers, outputting linear buffers
32 which means PMD supports input from linear buffer, outputting scatter-gathered styled buffers.
|
| /dpdk/doc/guides/cryptodevs/ |
| H A D | overview.rst | 17 which means that an input buffer can consist of multiple segments,
18 being the operation in-place (input address = output address).
22 which means PMD supports different scatter-gather styled input and output buffers
27 which means PMD supports input from scatter-gathered styled buffers,
32 which means PMD supports input from linear buffer, outputting
38 with linear input and output buffers.
|
| /dpdk/drivers/baseband/fpga_lte_fec/ |
| H A D | fpga_lte_fec.c | 1102 length = turbo_enc->input.length; in get_num_cbs_in_op_enc()
1343 if (turbo_enc->input.length > in validate_enc_op()
1346 turbo_enc->input.length, in validate_enc_op()
1500 struct rte_mbuf *input; in enqueue_enc_one_op_cb() local
1514 input = op->turbo_enc.input.data; in enqueue_enc_one_op_cb()
1580 input = op->turbo_enc.input.data; in enqueue_enc_one_op_tb()
1633 input = input->next; in enqueue_enc_one_op_tb()
1784 struct rte_mbuf *input; in enqueue_dec_one_op_cb() local
1798 input = op->turbo_dec.input.data; in enqueue_dec_one_op_cb()
1859 input = op->turbo_dec.input.data; in enqueue_dec_one_op_tb()
[all …]
|
| /dpdk/examples/vm_power_manager/guest_cli/ |
| H A D | parse.c | 20 parse_set(const char *input, uint16_t set[], unsigned int num) in parse_set() argument
23 const char *str = input; in parse_set()
81 return str - input; in parse_set()
|
| /dpdk/drivers/baseband/acc100/ |
| H A D | rte_acc100_pmd.c | 1491 *input = m; in acc100_dma_fill_blk_type_in()
2308 input = op->turbo_enc.input.data; in enqueue_enc_one_op_cb()
2424 input = op->ldpc_enc.input.data; in enqueue_ldpc_enc_one_op_cb()
2482 input = op->turbo_enc.input.data; in enqueue_enc_one_op_tb()
2517 input = input->next; in enqueue_enc_one_op_tb()
2701 input = op->turbo_dec.input.data; in enqueue_dec_one_op_cb()
2926 input = op->ldpc_dec.input.data; in enqueue_ldpc_dec_one_op_cb()
3032 input = op->ldpc_dec.input.data; in enqueue_ldpc_dec_one_op_tb()
3072 input = input->next; in enqueue_ldpc_dec_one_op_tb()
3121 input = op->turbo_dec.input.data; in enqueue_dec_one_op_tb()
[all …]
|
| /dpdk/lib/pci/ |
| H A D | rte_pci.c | 42 pci_bdf_parse(const char *input, struct rte_pci_addr *dev_addr) in pci_bdf_parse() argument
44 const char *in = input; in pci_bdf_parse()
60 pci_dbdf_parse(const char *input, struct rte_pci_addr *dev_addr) in pci_dbdf_parse() argument
62 const char *in = input; in pci_dbdf_parse()
|