Home
last modified time | relevance | path

Searched refs:msk (Results 1 – 23 of 23) sorted by relevance

/dpdk/lib/acl/
H A Dacl_run_avx512_common.h106 _T_mask msk, _T_simd *tr_lo, _T_simd *tr_hi) in _F_()
136 uint32_t msk, _T_simd *di, uint32_t bnum) in _F_()
169 m[0] = msk & _SIMD_PTR_MSK_; in _F_()
170 m[1] = msk >> _SIMD_PTR_NUM_; in _F_()
191 m[0] = msk & _SIMD_PTR_MSK_; in _F_()
192 m[1] = msk >> _SIMD_PTR_NUM_; in _F_()
416 mch = _M_I_(maskz_loadu_epi32)(msk, match); in _F_()
430 mch = _M_I_(maskz_loadu_epi32)(msk, pm); in _F_()
454 _T_mask msk; in _F_() local
457 msk = (1 << nb_pkt) - 1; in _F_()
[all …]
H A Dacl_run_avx512.c77 __mmask8 msk; in resolve_mcle8_avx512x1() local
100 msk = _mm_cmpgt_epi32_mask(cp, np); in resolve_mcle8_avx512x1()
101 cr = _mm_mask_mov_epi32(nr, msk, cr); in resolve_mcle8_avx512x1()
102 cp = _mm_mask_mov_epi32(np, msk, cp); in resolve_mcle8_avx512x1()
H A Dacl_run_avx2.h138 uint32_t msk; in acl_match_check_avx2x8() local
144 msk = _mm256_movemask_epi8(matches); in acl_match_check_avx2x8()
146 while (msk != 0) { in acl_match_check_avx2x8()
152 msk = _mm256_movemask_epi8(matches); in acl_match_check_avx2x8()
H A Dacl_bld.c925 const uint8_t *msk = mask; in acl_gen_mask_trie() local
932 acl_gen_mask(&bits, val[n] & msk[n], msk[n]); in acl_gen_mask_trie()
/dpdk/lib/bpf/
H A Dbpf_validate.c284 uint64_t msk) in eval_lsh() argument
312 uint64_t msk) in eval_rsh() argument
334 uint64_t msk) in eval_arsh() argument
396 uint64_t msk) in eval_and() argument
422 uint64_t msk) in eval_or() argument
448 uint64_t msk) in eval_xor() argument
474 uint64_t msk) in eval_mul() argument
636 uint64_t msk; in eval_alu() local
706 uint64_t msk; in eval_bele() local
797 uint64_t msk; in eval_load() local
[all …]
/dpdk/lib/eal/common/
H A Deal_common_fbarray.c167 cur_msk = msk->data[msk_idx]; in find_next_n()
289 uint64_t cur = msk->data[idx]; in find_next()
339 uint64_t cur = msk->data[idx]; in find_contig()
430 cur_msk = msk->data[msk_idx]; in find_prev_n()
566 uint64_t cur = msk->data[idx]; in find_prev()
611 uint64_t cur = msk->data[idx]; in find_rev_contig()
654 struct used_mask *msk; in set_used() local
677 msk->data[msk_idx] |= msk_bit; in set_used()
710 struct used_mask *msk; in rte_fbarray_init() local
1091 struct used_mask *msk; in rte_fbarray_is_used() local
[all …]
/dpdk/drivers/net/atlantic/
H A Datl_hw_regs.c13 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit() argument
16 if (msk ^ ~0) { in aq_hw_write_reg_bit()
20 reg_new = (reg_old & (~msk)) | (val << shift); in aq_hw_write_reg_bit()
29 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) in aq_hw_read_reg_bit() argument
31 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift); in aq_hw_read_reg_bit()
H A Datl_hw_regs.h46 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk,
48 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift);
/dpdk/examples/multi_process/client_server_mp/mp_server/
H A Dargs.c61 unsigned long msk = 1u << id; in parse_portmask() local
63 if ((pm & msk) == 0) in parse_portmask()
66 pm &= ~msk; in parse_portmask()
/dpdk/lib/ipsec/
H A Dsa.c386 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in esp_sa_init() local
479 sa->tx_offload.msk = in esp_sa_init()
483 switch (sa->type & msk) { in esp_sa_init()
696 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in lksd_none_pkt_func_select() local
700 switch (sa->type & msk) { in lksd_none_pkt_func_select()
734 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in cpu_crypto_pkt_func_select() local
738 switch (sa->type & msk) { in cpu_crypto_pkt_func_select()
776 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in inline_crypto_pkt_func_select() local
780 switch (sa->type & msk) { in inline_crypto_pkt_func_select()
H A Dsa.h100 uint64_t msk; member
H A Desp_inb.c621 tun_process_step3(mb[i], sa->tx_offload.msk, in tun_process()
H A Desp_outb.c190 mb->tx_offload = (mb->tx_offload & sa->tx_offload.msk) | in outb_tun_pkt_prepare()
/dpdk/drivers/net/ice/base/
H A Dice_parser_rt.c190 u64 msk; in _hv_bit_sel() local
204 msk = (1ul << len) - 1; in _hv_bit_sel()
206 return _bit_rev_u32((u32)((bit_sel.d64 >> (start % 16)) & msk), len); in _hv_bit_sel()
449 u32 msk; in _reg_bit_sel() local
463 msk = (1u << len) - 1; in _reg_bit_sel()
465 return _bit_rev_u16((u16)((bit_sel.d32 >> (start % 16)) & msk), len); in _reg_bit_sel()
H A Dice_parser.h94 u16 msk; /* 16 bits pattern mask */ member
H A Dice_parser.c526 prof->fv[prof->fv_num].msk = *(const u16 *)&msk_buf[off]; in ice_parser_profile_init()
550 prof->fv[i].spec, prof->fv[i].msk); in ice_parser_profile_dump()
H A Dice_flow.c2572 params->mask[idx] = CPU_TO_BE16(prof->fv[i].msk); in ice_flow_set_hw_prof()
/dpdk/lib/rib/
H A Drte_rib6.c80 uint8_t index, msk; in get_dir() local
95 msk = 1 << (7 - (depth & 7)); in get_dir()
97 return (ip[index] & msk) != 0; in get_dir()
/dpdk/drivers/net/mlx5/
H A Dmlx5_flow_flex.c145 #define SET_FP_MATCH_SAMPLE_ID(x, def, msk, val, sid) \ argument
155 tmp = (tmp & ~out) | (msk); \
242 uint32_t val, msk; in mlx5_flex_flow_translate_item() local
250 msk = mlx5_flex_get_bitfield(mask, pos, map->width, map->shift); in mlx5_flex_flow_translate_item()
261 def, msk & def, val & msk & def, in mlx5_flex_flow_translate_item()
/dpdk/drivers/raw/ifpga/base/
H A Dopae_intel_max10.c55 unsigned int msk, unsigned int val) in max10_sys_update_bits() argument
64 temp &= ~msk; in max10_sys_update_bits()
65 temp |= val & msk; in max10_sys_update_bits()
H A Dopae_intel_max10.h197 unsigned int offset, unsigned int msk, unsigned int val);
/dpdk/drivers/net/ice/
H A Dice_fdir_filter.c1341 pi->prof.fv[i].msk != in ice_fdir_create_filter()
1342 filter->prof->fv[i].msk) in ice_fdir_create_filter()
1367 pi->prof.fv[i].msk = filter->prof->fv[i].msk; in ice_fdir_create_filter()
/dpdk/doc/guides/prog_guide/
H A Drte_flow.rst3726 struct rte_flow_action msk[] = {
3736 rte_flow_actions_template_create(port, &attr, &act, &msk, &err);