| /dpdk/lib/acl/ |
| H A D | acl_run_neon.h | 148 transitions[0] = trans[vgetq_lane_u32(addr, 0)]; in transition4() 149 transitions[1] = trans[vgetq_lane_u32(addr, 1)]; in transition4() 150 transitions[2] = trans[vgetq_lane_u32(addr, 2)]; in transition4() 151 transitions[3] = trans[vgetq_lane_u32(addr, 3)]; in transition4() 198 input0 = transition4(input0, flows.trans, &index_array[0]); in search_neon_8() 199 input1 = transition4(input1, flows.trans, &index_array[4]); in search_neon_8() 201 input0 = transition4(input0, flows.trans, &index_array[0]); in search_neon_8() 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() [all …]
|
| H A D | acl_run_sse.h | 151 transition4(xmm_t next_input, const uint64_t *trans, in transition4() argument 167 trans0 = trans[_mm_cvtsi128_si32(addr)]; in transition4() 173 trans2 = trans[_mm_cvtsi128_si32(addr)]; in transition4() 249 input0 = transition4(input0, flows.trans, in search_sse_8() 251 input1 = transition4(input1, flows.trans, in search_sse_8() 254 input0 = transition4(input0, flows.trans, in search_sse_8() 256 input1 = transition4(input1, flows.trans, in search_sse_8() 259 input0 = transition4(input0, flows.trans, in search_sse_8() 261 input1 = transition4(input1, flows.trans, in search_sse_8() 264 input0 = transition4(input0, flows.trans, in search_sse_8() [all …]
|
| H A D | acl_run_altivec.h | 172 v.d64[0] = (uint64_t)trans[addr[0]]; in transition4() 173 v.d64[1] = (uint64_t)trans[addr[1]]; in transition4() 175 v.d64[0] = (uint64_t)trans[addr[2]]; in transition4() 176 v.d64[1] = (uint64_t)trans[addr[3]]; in transition4() 224 input0 = transition4(input0, flows.trans, in search_altivec_8() 226 input1 = transition4(input1, flows.trans, in search_altivec_8() 229 input0 = transition4(input0, flows.trans, in search_altivec_8() 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() [all …]
|
| H A D | acl_run_avx512_common.h | 74 _F_(trans)(_T_simd next_input, const uint64_t *trans, _T_simd *tr_lo, in _F_() argument 121 sizeof(flow->trans[0])); in _F_() 125 sizeof(flow->trans[0])); in _F_() 371 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_() 372 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_() 374 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_() 375 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_() 377 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_() 378 in[1] = _F_(trans)(in[1], flow->trans, &tr_lo[1], &tr_hi[1]); in _F_() 380 in[0] = _F_(trans)(in[0], flow->trans, &tr_lo[0], &tr_hi[0]); in _F_() [all …]
|
| H A D | acl_run_avx2.h | 66 tr = (const int32_t *)(uintptr_t)trans; in transition8() 74 *tr_lo = _mm256_i32gather_epi32(tr, addr, sizeof(trans[0])); in transition8() 79 *tr_hi = _mm256_i32gather_epi32(tr + 1, addr, sizeof(trans[0])); in transition8() 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.h | 47 const uint64_t *trans; member 149 flows->trans[parms[n].data[*parms[n].data_index++] + in acl_start_next_trie() 177 uint32_t data_num, uint32_t categories, const uint64_t *trans) in acl_set_flow() argument 189 flows->trans = trans; in acl_set_flow() 210 (flows->trans + ctx->match_index); in acl_match_check()
|
| H A D | acl_run_scalar.c | 146 transition0 = scalar_transition(flows.trans, in rte_acl_classify_scalar() 150 transition1 = scalar_transition(flows.trans, in rte_acl_classify_scalar()
|
| H A D | acl_run_avx512.c | 15 const uint64_t *trans; /* transition table */ member 30 flow->trans = ctx->trans_table; in acl_set_flow_avx512()
|
| /dpdk/doc/guides/sample_app_ug/ |
| H A D | ntb.rst | 13 * ``file-trans``: transmit files between two systems. The sample will 53 Set the packet forwarding mode as ``file-trans``, ``txonly``, 88 file-trans forwarding mode first. 92 * ``set fwd file-trans/rxonly/txonly/iofwd``: Set packet forwarding
|
| /dpdk/drivers/net/mlx5/ |
| H A D | mlx5_flow_flex.c | 758 struct mlx5_flex_pattern_field *trans; in mlx5_flex_map_sample() local 771 trans = &item->map[item->mapnum]; in mlx5_flex_map_sample() 772 trans->reg_id = MLX5_INVALID_SAMPLE_REG_ID; in mlx5_flex_map_sample() 773 trans->shift = 0; in mlx5_flex_map_sample() 774 trans->width = part; in mlx5_flex_map_sample() 807 trans = &item->map[item->mapnum]; in mlx5_flex_map_sample() 809 trans->reg_id = i; in mlx5_flex_map_sample() 810 trans->shift = cov_start - reg_start; in mlx5_flex_map_sample() 811 trans->width = cov_end - cov_start; in mlx5_flex_map_sample()
|