Home
last modified time | relevance | path

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

12

/openbsd/src/sys/dev/pci/drm/i915/
Di915_reg_defs.h98 #define REG_FIELD_PREP(__mask, __val) \ argument
99 ((u32)((((typeof(__mask))(__val) << __bf_shf(__mask)) & (__mask)) + \
100 BUILD_BUG_ON_ZERO(!__is_constexpr(__mask)) + \
101 BUILD_BUG_ON_ZERO((__mask) == 0 || (__mask) > U32_MAX) + \
102 BUILD_BUG_ON_ZERO(!IS_POWER_OF_2((__mask) + (1ULL << __bf_shf(__mask)))) + \
103 …D_BUG_ON_ZERO(__builtin_choose_expr(__is_constexpr(__val), (~((__mask) >> __bf_shf(__mask)) & (__v…
115 #define REG_FIELD_PREP8(__mask, __val) \ argument
116 ((u8)((((typeof(__mask))(__val) << __bf_shf(__mask)) & (__mask)) + \
117 BUILD_BUG_ON_ZERO(!__is_constexpr(__mask)) + \
118 BUILD_BUG_ON_ZERO((__mask) == 0 || (__mask) > U8_MAX) + \
[all …]
/openbsd/src/sys/dev/ic/
Dbwireg.h697 #define __LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
699 #define __SHIFTOUT(__x, __mask) (((__x) & (__mask)) / __LOWEST_SET_BIT(__mask)) argument
700 #define __SHIFTIN(__x, __mask) ((__x) * __LOWEST_SET_BIT(__mask)) argument
701 #define __SHIFTOUT_MASK(__mask) __SHIFTOUT((__mask), (__mask)) argument
Dbcmgenetreg.h40 #define __LOWEST_SET_BIT(__mask) ((((__mask) - 1) & (__mask)) ^ (__mask)) argument
41 #define __SHIFTOUT(__x, __mask) (((__x) & (__mask)) / __LOWEST_SET_BIT(__mask)) argument
42 #define __SHIFTIN(__x, __mask) ((__x) * __LOWEST_SET_BIT(__mask)) argument
/openbsd/src/gnu/llvm/clang/lib/Headers/ppc_wrappers/
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 …]
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()
Dsmmintrin.h320 _mm_blendv_epi8(__m128i __A, __m128i __B, __m128i __mask) { in _mm_blendv_epi8() argument
322 return (__m128i)vec_blendv((__v16qi)__A, (__v16qi)__B, (__v16qu)__mask); in _mm_blendv_epi8()
325 __v16qu __lmask = vec_sra((__v16qu)__mask, __seven); in _mm_blendv_epi8()
357 _mm_blendv_ps(__m128 __A, __m128 __B, __m128 __mask) { in _mm_blendv_ps() argument
359 return (__m128)vec_blendv((__v4sf)__A, (__v4sf)__B, (__v4su)__mask); in _mm_blendv_ps()
362 const __vector __bool int __boolmask = vec_cmplt((__v4si)__mask, __zero); in _mm_blendv_ps()
382 _mm_blendv_pd(__m128d __A, __m128d __B, __m128d __mask) { in _mm_blendv_pd() argument
384 return (__m128d)vec_blendv((__v2df)__A, (__v2df)__B, (__v2du)__mask); in _mm_blendv_pd()
388 vec_cmplt((__v2di)__mask, __zero); in _mm_blendv_pd()
Demmintrin.h1130 _mm_shuffle_pd(__m128d __A, __m128d __B, const int __mask) { in _mm_shuffle_pd() argument
1132 const int __litmsk = __mask & 0x3; in _mm_shuffle_pd()
2003 _mm_shufflehi_epi16(__m128i __A, const int __mask) { in _mm_shufflehi_epi16() argument
2004 unsigned long __element_selector_98 = __mask & 0x03; in _mm_shufflehi_epi16()
2005 unsigned long __element_selector_BA = (__mask >> 2) & 0x03; in _mm_shufflehi_epi16()
2006 unsigned long __element_selector_DC = (__mask >> 4) & 0x03; in _mm_shufflehi_epi16()
2007 unsigned long __element_selector_FE = (__mask >> 6) & 0x03; in _mm_shufflehi_epi16()
2036 _mm_shufflelo_epi16(__m128i __A, const int __mask) { in _mm_shufflelo_epi16() argument
2037 unsigned long __element_selector_10 = __mask & 0x03; in _mm_shufflelo_epi16()
2038 unsigned long __element_selector_32 = (__mask >> 2) & 0x03; in _mm_shufflelo_epi16()
[all …]
/openbsd/src/gnu/llvm/clang/lib/Headers/
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 …]
/openbsd/src/lib/libm/arch/arm/
Dfenv.c199 envp->__mask = 0; in fegetenv()
257 fpscr |= (envp->__mask & FE_ALL_EXCEPT) << 8; in fesetenv()
258 _softfloat_float_exception_mask = envp->__mask & FE_ALL_EXCEPT; in fesetenv()
/openbsd/src/gnu/lib/libstdc++/libstdc++/include/std/
Dstd_iomanip.h64 resetiosflags(ios_base::fmtflags __mask) in resetiosflags() argument
67 __x._M_mask = __mask; in resetiosflags()
98 setiosflags(ios_base::fmtflags __mask) in setiosflags() argument
101 __x._M_mask = __mask; in setiosflags()
/openbsd/src/gnu/gcc/libstdc++-v3/include/std/
Dstd_iomanip.h63 resetiosflags(ios_base::fmtflags __mask) in resetiosflags() argument
66 __x._M_mask = __mask; in resetiosflags()
97 setiosflags(ios_base::fmtflags __mask) in setiosflags() argument
100 __x._M_mask = __mask; in setiosflags()
/openbsd/src/gnu/gcc/libstdc++-v3/include/bits/
Dios_base.h591 setf(fmtflags __fmtfl, fmtflags __mask) in setf() argument
594 _M_flags &= ~__mask; in setf()
595 _M_flags |= (__fmtfl & __mask); in setf()
606 unsetf(fmtflags __mask) { _M_flags &= ~__mask; } in unsetf() argument
/openbsd/src/gnu/lib/libstdc++/libstdc++/include/bits/
Dios_base.h515 setf(fmtflags __fmtfl, fmtflags __mask) in setf() argument
518 _M_flags &= ~__mask; in setf()
519 _M_flags |= (__fmtfl & __mask); in setf()
530 unsetf(fmtflags __mask) { _M_flags &= ~__mask; } in unsetf() argument
/openbsd/src/sys/dev/pci/drm/i915/display/
Dintel_display.h119 #define for_each_dbuf_slice_in_mask(__dev_priv, __slice, __mask) \ argument
121 for_each_if((__mask) & BIT(__slice))
225 #define for_each_pipe_masked(__dev_priv, __p, __mask) \ argument
227 for_each_if((__mask) & BIT(__p))
233 #define for_each_cpu_transcoder_masked(__dev_priv, __t, __mask) \ argument
235 for_each_if ((__mask) & BIT(__t))
Dintel_display_power.h165 #define for_each_power_domain(__domain, __mask) \ argument
167 for_each_if(test_bit((__domain), (__mask)->bits))
/openbsd/src/gnu/gcc/libstdc++-v3/src/
Dlocalename.cc267 category __mask = 1; in _M_replace_categories() local
269 for (size_t __ix = 0; __ix < _S_categories_size; ++__ix, __mask <<= 1) in _M_replace_categories()
271 if (__mask & __cat) in _M_replace_categories()
/openbsd/src/lib/libm/arch/alpha/
Dfenv.c217 envp->__mask = sysarch(ALPHA_FPGETMASK, 0L) & FE_ALL_EXCEPT; in fegetenv()
274 a.mask = envp->__mask & FE_ALL_EXCEPT; in fesetenv()
/openbsd/src/gnu/gcc/libstdc++-v3/include/ext/
Dbitmap_allocator.h523 size_t __mask = 1 << __pos;
524 __mask = ~__mask;
525 *__pbmap &= __mask;
534 size_t __mask = 1 << __pos;
535 *__pbmap |= __mask;
/openbsd/src/gnu/llvm/libcxx/benchmarks/
Dunordered_set_operations.bench.cpp72 const __uint128_t __mask = static_cast<std::size_t>(-1); in operator ()() local
73 const std::size_t __a = (std::size_t)(data & __mask); in operator ()()
74 const std::size_t __b = (std::size_t)((data & (__mask << 64)) >> 64); in operator ()()
/openbsd/src/sys/arch/arm/include/
Dfenv.h65 unsigned int __mask; member
/openbsd/src/sys/arch/alpha/include/
Dfenv.h66 unsigned int __mask; member
/openbsd/src/gnu/lib/libstdc++/libstdc++/src/
Dlocalename.cc318 category __mask; in _M_replace_categories() local
321 __mask = 1 << __ix; in _M_replace_categories()
322 if (__mask & __cat) in _M_replace_categories()
/openbsd/src/gnu/usr.bin/gcc/gcc/config/i386/
Dxmmintrin.h688 _mm_shuffle_ps (__m128 __A, __m128 __B, int __mask)
690 return (__m128) __builtin_ia32_shufps ((__v4sf)__A, (__v4sf)__B, __mask);
804 _MM_SET_EXCEPTION_STATE(unsigned int __mask) in _MM_SET_EXCEPTION_STATE() argument
806 _mm_setcsr((_mm_getcsr() & ~_MM_EXCEPT_MASK) | __mask); in _MM_SET_EXCEPTION_STATE()
810 _MM_SET_EXCEPTION_MASK (unsigned int __mask) in _MM_SET_EXCEPTION_MASK() argument
812 _mm_setcsr((_mm_getcsr() & ~_MM_MASK_MASK) | __mask); in _MM_SET_EXCEPTION_MASK()
/openbsd/src/gnu/llvm/libcxx/include/
Dios299 _LIBCPP_INLINE_VISIBILITY fmtflags setf(fmtflags __fmtfl, fmtflags __mask);
300 _LIBCPP_INLINE_VISIBILITY void unsetf(fmtflags __mask);
495 ios_base::unsetf(fmtflags __mask)
497 __fmtflags_ &= ~__mask;
502 ios_base::setf(fmtflags __fmtfl, fmtflags __mask)
505 unsetf(__mask);
506 __fmtflags_ |= __fmtfl & __mask;
/openbsd/src/gnu/gcc/gcc/config/i386/
Dxmmintrin.h721 _mm_shuffle_ps (__m128 __A, __m128 __B, int __mask)
723 return (__m128) __builtin_ia32_shufps ((__v4sf)__A, (__v4sf)__B, __mask);
837 _MM_SET_EXCEPTION_STATE(unsigned int __mask) in _MM_SET_EXCEPTION_STATE() argument
839 _mm_setcsr((_mm_getcsr() & ~_MM_EXCEPT_MASK) | __mask); in _MM_SET_EXCEPTION_STATE()
843 _MM_SET_EXCEPTION_MASK (unsigned int __mask) in _MM_SET_EXCEPTION_MASK() argument
845 _mm_setcsr((_mm_getcsr() & ~_MM_MASK_MASK) | __mask); in _MM_SET_EXCEPTION_MASK()

12