Home
last modified time | relevance | path

Searched refs:__mask (Results 1 – 25 of 40) sorted by relevance

12

/freebsd/sys/dev/bwi/
H A Dbitops.h76 #define __LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
78 #define __SHIFTOUT(__x, __mask) (((__x) & (__mask)) / __LOWEST_SET_BIT(__mask)) argument
79 #define __SHIFTIN(__x, __mask) ((__x) * __LOWEST_SET_BIT(__mask)) argument
80 #define __SHIFTOUT_MASK(__mask) __SHIFTOUT((__mask), (__mask)) argument
/freebsd/lib/msun/arm/
H A Dfenv.c84 extern inline int feenableexcept(int __mask);
85 extern inline int fedisableexcept(int __mask);
103 int __softfp_feenableexcept(int __mask);
104 int __softfp_fedisableexcept(int __mask);
118 int __vfp_feenableexcept(int __mask);
119 int __vfp_fedisableexcept(int __mask);
276 int feenableexcept(int __mask) in feenableexcept() argument
282 __unmasked = __vfp_feenableexcept(__mask); in feenableexcept()
283 __unmasked |= __softfp_feenableexcept(__mask); in feenableexcept()
288 int fedisableexcept(int __mask) in fedisableexcept() argument
[all …]
H A Dfenv.h101 int feenableexcept(int __mask);
102 int fedisableexcept(int __mask);
229 feenableexcept(int __mask) in feenableexcept() argument
235 ((__mask & FE_ALL_EXCEPT) << _FPU_MASK_SHIFT); in feenableexcept()
241 fedisableexcept(int __mask) in fedisableexcept() argument
247 ~((__mask & FE_ALL_EXCEPT) << _FPU_MASK_SHIFT); in fedisableexcept()
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h107 inline __device__ int __FnName(unsigned int __mask, int __val, \
109 return __IntIntrinsic(__mask, __val, __offset, \
112 inline __device__ float __FnName(unsigned int __mask, float __val, \
114 return __FloatIntrinsic(__mask, __val, __offset, \
117 inline __device__ unsigned int __FnName(unsigned int __mask, \
121 ::__FnName(__mask, static_cast<int>(__val), __offset, __width)); \
123 inline __device__ long long __FnName(unsigned int __mask, long long __val, \
133 __tmp.__a = ::__FnName(__mask, __tmp.__a, __offset, __width); \
134 __tmp.__b = ::__FnName(__mask, __tmp.__b, __offset, __width); \
140 unsigned int __mask, unsigned long long __val, __Type __offset, \
[all …]
/freebsd/sys/arm/freescale/imx/
H A Dimx_iomuxreg.h30 #define IMX_IOMUXREG_LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
31 #define IMX_IOMUXREG_SHIFTIN(__x, __mask) ((__x) * IMX_IOMUXREG_LOWEST_SET_BIT(__mask)) argument
/freebsd/contrib/llvm-project/clang/lib/Headers/ppc_wrappers/
H A Dxmmintrin.h199 static const __vector unsigned int __mask = {0xffffffff, 0, 0, 0}; in _mm_move_ss() local
201 return (vec_sel((__v4sf)__A, (__v4sf)__B, __mask)); in _mm_move_ss()
227 static const __vector unsigned int __mask = {0xffffffff, 0, 0, 0}; in _mm_add_ss() local
237 return (vec_sel(__A, __c, __mask)); in _mm_add_ss()
249 static const __vector unsigned int __mask = {0xffffffff, 0, 0, 0}; in _mm_sub_ss() local
259 return (vec_sel(__A, __c, __mask)); in _mm_sub_ss()
271 static const __vector unsigned int __mask = {0xffffffff, 0, 0, 0}; in _mm_mul_ss() local
281 return (vec_sel(__A, __c, __mask)); in _mm_mul_ss()
293 static const __vector unsigned int __mask = {0xffffffff, 0, 0, 0}; in _mm_div_ss() local
303 return (vec_sel(__A, __c, __mask)); in _mm_div_ss()
[all …]
H A Dbmi2intrin.h54 const unsigned long __mask = 0x8000000000000000UL; in _pdep_u64() local
69 __m ^= (__mask >> __c); in _pdep_u64()
70 __result |= (__t & (__mask >> __c)); in _pdep_u64()
80 const unsigned long __mask = 0x8000000000000000UL; in _pext_u64() local
95 __m ^= (__mask >> __c); in _pext_u64()
109 __t = (__X & (__mask >> __c)) >> (__p - __c); in _pext_u64()
110 __m ^= (__mask >> __c); in _pext_u64()
H A Demmintrin.h1131 _mm_shuffle_pd(__m128d __A, __m128d __B, const int __mask) { in _mm_shuffle_pd() argument
1133 const int __litmsk = __mask & 0x3; in _mm_shuffle_pd()
2004 _mm_shufflehi_epi16(__m128i __A, const int __mask) { in _mm_shufflehi_epi16() argument
2005 unsigned long __element_selector_98 = __mask & 0x03; in _mm_shufflehi_epi16()
2006 unsigned long __element_selector_BA = (__mask >> 2) & 0x03; in _mm_shufflehi_epi16()
2007 unsigned long __element_selector_DC = (__mask >> 4) & 0x03; in _mm_shufflehi_epi16()
2008 unsigned long __element_selector_FE = (__mask >> 6) & 0x03; in _mm_shufflehi_epi16()
2037 _mm_shufflelo_epi16(__m128i __A, const int __mask) { in _mm_shufflelo_epi16() argument
2038 unsigned long __element_selector_10 = __mask & 0x03; in _mm_shufflelo_epi16()
2039 unsigned long __element_selector_32 = (__mask >> 2) & 0x03; in _mm_shufflelo_epi16()
[all …]
/freebsd/contrib/llvm-project/libcxx/src/include/ryu/
H A Dryu.h71 _LIBCPP_HIDE_FROM_ABI inline unsigned char _BitScanForward64(unsigned long* __index, unsigned long long __mask) {
72 if (__mask == 0) { in _BitScanForward64() argument
75 *__index = __builtin_ctzll(__mask); in _BitScanForward64()
79 _LIBCPP_HIDE_FROM_ABI inline unsigned char _BitScanForward(unsigned long* __index, unsigned int __mask) {
80 if (__mask == 0) { in _BitScanForward() argument
83 *__index = __builtin_ctz(__mask); in _BitScanForward()
/freebsd/lib/msun/src/
H A Dfenv-softfloat.h160 feenableexcept(int __mask) in feenableexcept() argument
164 __softfloat_float_exception_mask |= __mask; in feenableexcept()
169 fedisableexcept(int __mask) in fedisableexcept() argument
173 __softfloat_float_exception_mask &= ~__mask; in fedisableexcept()
/freebsd/sys/arm/allwinner/
H A Daw_usb3phy.c73 #define __LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
74 #define __SHIFTIN(__x, __mask) ((__x) * __LOWEST_SET_BIT(__mask)) argument
/freebsd/lib/msun/aarch64/
H A Dfenv.h214 feenableexcept(int __mask) in feenableexcept() argument
219 __new_r = __old_r | ((__mask & FE_ALL_EXCEPT) << _FPUSW_SHIFT); in feenableexcept()
225 fedisableexcept(int __mask) in fedisableexcept() argument
230 __new_r = __old_r & ~((__mask & FE_ALL_EXCEPT) << _FPUSW_SHIFT); in fedisableexcept()
H A Dfenv.c52 extern inline int feenableexcept(int __mask);
53 extern inline int fedisableexcept(int __mask);
/freebsd/lib/msun/riscv/
H A Dfenv.c51 extern inline int feenableexcept(int __mask);
52 extern inline int fedisableexcept(int __mask);
H A Dfenv.h200 feenableexcept(int __mask __unused) in feenableexcept()
209 fedisableexcept(int __mask __unused) in fedisableexcept()
/freebsd/lib/msun/powerpc/
H A Dfenv.h266 feenableexcept(int __mask) in feenableexcept() argument
273 __r.__bits.__reg |= (__mask & FE_ALL_EXCEPT) >> _FPUSW_SHIFT; in feenableexcept()
279 fedisableexcept(int __mask) in fedisableexcept() argument
286 __r.__bits.__reg &= ~((__mask & FE_ALL_EXCEPT) >> _FPUSW_SHIFT); in fedisableexcept()
H A Dfenv.c59 extern inline int feenableexcept(int __mask);
60 extern inline int fedisableexcept(int __mask);
/freebsd/sys/compat/linux/
H A Dlinux.h187 uint64_t __mask; member
191 #define LINUX_SIGEMPTYSET(set) (set).__mask = 0
192 #define LINUX_SIGISMEMBER(set, sig) (1ULL & ((set).__mask >> _SIG_IDX(sig)))
193 #define LINUX_SIGADDSET(set, sig) (set).__mask |= 1ULL << _SIG_IDX(sig)
H A Dlinux_signal.c322 lset.__mask = mask; in linux_sigprocmask()
339 mask = oset.__mask; in linux_sigprocmask()
383 td->td_retval[0] = mask.__mask; in linux_sgetmask()
400 td->td_retval[0] = lset.__mask; in linux_ssetmask()
402 lset.__mask = args->mask; in linux_ssetmask()
433 mask = lset.__mask; in linux_sigpending()
/freebsd/contrib/llvm-project/libcxx/include/__pstl/internal/
H A Dunseq_backend_simd.h
H A Dalgorithm_impl.h
/freebsd/sys/dev/qat_c2xxx/
H A Dqatreg.h70 #define __LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
71 #define __SHIFTOUT(__x, __mask) (((__x) & (__mask)) / __LOWEST_SET_BIT(__mask)) argument
72 #define __SHIFTIN(__x, __mask) ((__x) * __LOWEST_SET_BIT(__mask)) argument
/freebsd/sys/sys/
H A Dbitset.h240 long __bit, __mask; \
242 __mask = ~0UL << ((start) % _BITSET_BITS); \
247 if (((p)->__bits[__i] & __mask) != 0) { \
248 __bit = ffsl((p)->__bits[__i] & __mask); \
252 __mask = ~0UL; \
/freebsd/lib/msun/x86/
H A Dfenv.h127 int feenableexcept(int __mask);
128 int fedisableexcept(int __mask);
/freebsd/contrib/llvm-project/libcxx/include/__random/
H A Dmersenne_twister_engine.h679 const result_type __mask = __r == _Dt ? result_type(~0) : (result_type(1) << __r) - result_type(1);
681 if ((__x_[0] & ~__mask) == 0) {
711 const result_type __mask = __r == _Dt ? result_type(~0) : (result_type(1) << __r) - result_type(1);
713 if ((__x_[0] & ~__mask) == 0) {
738 const result_type __mask = __r == _Dt ? result_type(~0) : (result_type(1) << __r) - result_type(1);
739 const result_type __yp = (__x_[__i_] & ~__mask) | (__x_[__j] & __mask);
357 const result_type __mask = __r == _Dt ? result_type(~0) : __seed() local
383 const result_type __mask = __r == _Dt ? result_type(~0) : __seed() local
403 const result_type __mask = __r == _Dt ? result_type(~0) : operator() local

12