Home
last modified time | relevance | path

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

12

/f-stack/dpdk/lib/librte_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_()
392 mch = _M_I_(maskz_loadu_epi32)(msk, match); in _F_()
406 mch = _M_I_(maskz_loadu_epi32)(msk, pm); in _F_()
430 _T_mask msk; in _F_() local
433 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()
/f-stack/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);
/f-stack/dpdk/lib/librte_bpf/
H A Dbpf_validate.c287 uint64_t msk) in eval_lsh() argument
315 uint64_t msk) in eval_rsh() argument
337 uint64_t msk) in eval_arsh() argument
399 uint64_t msk) in eval_and() argument
425 uint64_t msk) in eval_or() argument
451 uint64_t msk) in eval_xor() argument
477 uint64_t msk) in eval_mul() argument
639 uint64_t msk; in eval_alu() local
702 uint64_t msk; in eval_bele() local
793 uint64_t msk; in eval_load() local
[all …]
/f-stack/dpdk/lib/librte_eal/common/
H A Deal_common_fbarray.c171 cur_msk = msk->data[msk_idx]; in find_next_n()
293 uint64_t cur = msk->data[idx]; in find_next()
343 uint64_t cur = msk->data[idx]; in find_contig()
434 cur_msk = msk->data[msk_idx]; in find_prev_n()
570 uint64_t cur = msk->data[idx]; in find_prev()
615 uint64_t cur = msk->data[idx]; in find_rev_contig()
658 struct used_mask *msk; in set_used() local
681 msk->data[msk_idx] |= msk_bit; in set_used()
714 struct used_mask *msk; in rte_fbarray_init() local
1095 struct used_mask *msk; in rte_fbarray_is_used() local
[all …]
/f-stack/freebsd/mips/ingenic/
H A Djz4780_clk_gen.c109 uint32_t reg, msk, parent_idx; in jz4780_clk_gen_init() local
115 msk = (1u << sc->clk_descr->clk_mux.mux_bits) - 1; in jz4780_clk_gen_init()
117 reg = (reg >> sc->clk_descr->clk_mux.mux_shift) & msk; in jz4780_clk_gen_init()
137 uint32_t msk; in jz4780_clk_gen_recalc_freq() local
139 msk = (1u << sc->clk_descr->clk_div.div_bits) - 1; in jz4780_clk_gen_recalc_freq()
141 reg = (reg >> sc->clk_descr->clk_div.div_shift) & msk; in jz4780_clk_gen_recalc_freq()
240 uint32_t reg, msk; in jz4780_clk_gen_set_mux() local
248 msk = (1u << sc->clk_descr->clk_mux.mux_bits) - 1; in jz4780_clk_gen_set_mux()
249 src = mux_to_reg(src & msk, sc->clk_descr->clk_mux.mux_map); in jz4780_clk_gen_set_mux()
253 reg &= ~(msk << sc->clk_descr->clk_mux.mux_shift); in jz4780_clk_gen_set_mux()
/f-stack/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()
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dradix_ipf.c1067 u_int *msk;
1070 msk[0] = 0;
1071 msk[1] = 0;
1072 msk[2] = 0;
1073 msk[3] = 0;
1085 msk[3] = htonl(msk[3] << (128 - bits));
1087 msk[3] = 0;
1088 msk[2] = htonl(msk[2] << (96 - bits));
1090 msk[3] = 0;
1092 msk[1] = htonl(msk[1] << (64 - bits));
[all …]
H A Dip_htable.c1186 u_32_t msk, ips; local
1193 msk = iph->iph_v4_masks.imt4_active[i];
1194 ips = addr->s_addr & msk;
1198 (ipe->ipe_mask.in4_addr != msk) ||
1393 i6addr_t *msk, ips; local
1400 msk = iph->iph_v6_masks.imt6_active + i;
1401 ips.i6[0] = addr->i6[0] & msk->i6[0];
1402 ips.i6[1] = addr->i6[1] & msk->i6[1];
1403 ips.i6[2] = addr->i6[2] & msk->i6[2];
1404 ips.i6[3] = addr->i6[3] & msk->i6[3];
[all …]
/f-stack/freebsd/contrib/openzfs/tests/zfs-tests/tests/functional/acl/posix/
H A Dposix_002_pos.ksh58 msk=$(ls -l $TESTDIR |grep "dir.0" | awk '{print $1}')
59 log_note "expected mask drwx-wx---+ but found $msk"
H A Dposix_001_pos.ksh75 msk=$(ls -l $TESTDIR |grep "dir.0" | awk '{print $1}')
76 log_note "expected mask drwxrw----+ but found $msk"
/f-stack/freebsd/contrib/ncsw/Peripherals/FM/
H A Dfman_ncsw.c353 uint32_t msk, timeout = 100; in fman_reset_mac() local
359 msk = FPM_RSTC_10G0_RESET; in fman_reset_mac()
370 msk = FPM_RSTC_1G0_RESET; in fman_reset_mac()
373 msk = FPM_RSTC_1G1_RESET; in fman_reset_mac()
376 msk = FPM_RSTC_1G2_RESET; in fman_reset_mac()
379 msk = FPM_RSTC_1G3_RESET; in fman_reset_mac()
382 msk = FPM_RSTC_1G4_RESET; in fman_reset_mac()
385 msk = FPM_RSTC_1G5_RESET; in fman_reset_mac()
388 msk = FPM_RSTC_1G6_RESET; in fman_reset_mac()
398 iowrite32be(msk, &fpm_rg->fm_rstc); in fman_reset_mac()
[all …]
/f-stack/dpdk/lib/librte_ipsec/
H A Dsa.c357 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in esp_sa_init() local
422 sa->tx_offload.msk = in esp_sa_init()
426 switch (sa->type & msk) { in esp_sa_init()
619 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in lksd_none_pkt_func_select() local
623 switch (sa->type & msk) { in lksd_none_pkt_func_select()
657 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in cpu_crypto_pkt_func_select() local
661 switch (sa->type & msk) { in cpu_crypto_pkt_func_select()
699 static const uint64_t msk = RTE_IPSEC_SATP_DIR_MASK | in inline_crypto_pkt_func_select() local
703 switch (sa->type & msk) { in inline_crypto_pkt_func_select()
H A Dsa.h95 uint64_t msk; member
/f-stack/freebsd/contrib/octeon-sdk/
H A Dcvmx-atomic.h537 : [msk] "r" (mask) in cvmx_atomic_fetch_and_bset64_nosync()
570 : [msk] "r" (mask) in cvmx_atomic_fetch_and_bset32_nosync()
603 : [val] "+m" (*ptr), [tmp] "=&r" (tmp), [ret] "=&r" (ret), [msk] "+r" (mask) in cvmx_atomic_fetch_and_bclr64_nosync()
636 : [val] "+m" (*ptr), [tmp] "=&r" (tmp), [ret] "=&r" (ret), [msk] "+r" (mask) in cvmx_atomic_fetch_and_bclr32_nosync()
/f-stack/freebsd/arm64/arm64/
H A Ddisassem.c307 int msk; in arm64_disasm_read_token_sign_ext() local
311 msk = (1 << insn->tokens[i].len) - 1; in arm64_disasm_read_token_sign_ext()
312 *val = ((opcode >> insn->tokens[i].pos) & msk); in arm64_disasm_read_token_sign_ext()
316 *val |= ~msk; in arm64_disasm_read_token_sign_ext()
/f-stack/freebsd/kern/
H A Dsys_generic.c1262 int msk; in selflags() local
1265 for (msk = 0; msk < 3; msk++) { in selflags()
1266 if (ibits[msk] == NULL) in selflags()
1268 if ((ibits[msk][idx] & bit) == 0) in selflags()
1270 flags |= select_flags[msk]; in selflags()
1282 int msk; in selsetbits() local
1286 for (msk = 0; msk < 3; msk++) { in selsetbits()
1289 if (ibits[msk] == NULL) in selsetbits()
1291 if ((ibits[msk][idx] & bit) == 0) in selsetbits()
1299 if ((obits[msk][idx] & bit) != 0) in selsetbits()
[all …]
/f-stack/freebsd/i386/conf/
H A DLINT-NOIP15 nodevice msk
/f-stack/freebsd/amd64/conf/
H A DLINT-NOIP16 nodevice msk
/f-stack/freebsd/contrib/device-tree/src/arm64/mediatek/
H A Dmt2712-evb.dts203 mediatek,u3p-dis-msk = <0x1>;
215 //mediatek,u3p-dis-msk = <0x1>;
/f-stack/dpdk/lib/librte_rib/
H A Drte_rib6.c83 uint8_t p_depth, msk; in get_dir() local
88 msk = 1 << (7 - p_depth); in get_dir()
89 return (ip[i] & msk) != 0; in get_dir()
/f-stack/freebsd/mips/conf/
H A Dstd.XLP77 device msk
/f-stack/freebsd/contrib/device-tree/Bindings/usb/
H A Dmediatek,mtk-xhci.txt47 - mediatek,u3p-dis-msk : mask to disable u3ports, bit0 for u3port0,

12