Home
last modified time | relevance | path

Searched refs:__bits (Results 1 – 25 of 72) sorted by relevance

123

/netbsd-src/sys/sys/
H A Dsigtypes.h61 __uint32_t __bits[4]; member
69 #define __sigaddset(s, n) ((s)->__bits[__sigword(n)] |= __sigmask(n))
70 #define __sigdelset(s, n) ((s)->__bits[__sigword(n)] &= ~__sigmask(n))
71 #define __sigismember(s, n) (((s)->__bits[__sigword(n)] & __sigmask(n)) != 0)
72 #define __sigemptyset(s) ((s)->__bits[0] = 0x00000000, \
73 (s)->__bits[1] = 0x00000000, \
74 (s)->__bits[2] = 0x00000000, \
75 (s)->__bits[3] = 0x00000000)
76 #define __sigsetequal(s1,s2) ((s1)->__bits[0] == (s2)->__bits[0] && \
77 (s1)->__bits[1] == (s2)->__bits[1] && \
[all …]
H A Dsignalvar.h216 sig = ffs(ss->__bits[0]); in firstsig()
220 sig = ffs(ss->__bits[1]); in firstsig()
225 sig = ffs(ss->__bits[2]); in firstsig()
230 sig = ffs(ss->__bits[3]); in firstsig()
/netbsd-src/tests/lib/libc/sys/
H A Dt_ptrace_exec_wait.h104 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in traceme_vfork_exec()
105 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in traceme_vfork_exec()
109 kp.p_sigmask.__bits[0], kp.p_sigmask.__bits[1], in traceme_vfork_exec()
110 kp.p_sigmask.__bits[2], kp.p_sigmask.__bits[3]); in traceme_vfork_exec()
119 kp_sigignore.__bits[0], kp_sigignore.__bits[1], in traceme_vfork_exec()
120 kp_sigignore.__bits[2], kp_sigignore.__bits[3]); in traceme_vfork_exec()
124 kp.p_sigignore.__bits[0], kp.p_sigignore.__bits[1], in traceme_vfork_exec()
125 kp.p_sigignore.__bits[2], kp.p_sigignore.__bits[3]); in traceme_vfork_exec()
250 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in TRACEME_VFORK_EXEC()
251 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in TRACEME_VFORK_EXEC()
[all …]
H A Dt_ptrace_clone_wait.h442 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in CLONE_TEST()
443 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in CLONE_TEST()
448 kp.p_sigmask.__bits[0], kp.p_sigmask.__bits[1], in CLONE_TEST()
449 kp.p_sigmask.__bits[2], kp.p_sigmask.__bits[3]); in CLONE_TEST()
459 kp_sigignore.__bits[0], kp_sigignore.__bits[1], in CLONE_TEST()
460 kp_sigignore.__bits[2], kp_sigignore.__bits[3]); in CLONE_TEST()
465 kp.p_sigignore.__bits[0], kp.p_sigignore.__bits[1], in CLONE_TEST()
466 kp.p_sigignore.__bits[2], kp.p_sigignore.__bits[3]); in CLONE_TEST()
501 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in CLONE_TEST()
502 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in CLONE_TEST()
[all …]
H A Dt_ptrace_step_wait.h155 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in ptrace_step()
156 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in ptrace_step()
161 kp.p_sigmask.__bits[0], kp.p_sigmask.__bits[1], in ptrace_step()
162 kp.p_sigmask.__bits[2], kp.p_sigmask.__bits[3]); in ptrace_step()
172 kp_sigignore.__bits[0], kp_sigignore.__bits[1], in ptrace_step()
173 kp_sigignore.__bits[2], kp_sigignore.__bits[3]); in ptrace_step()
178 kp.p_sigignore.__bits[0], kp.p_sigignore.__bits[1], in ptrace_step()
179 kp.p_sigignore.__bits[2], kp.p_sigignore.__bits[3]); in ptrace_step()
H A Dt_ptrace_fork_wait.h1425 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in TRACEME_VFORK_FORK_TEST()
1426 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in TRACEME_VFORK_FORK_TEST()
1431 kp.p_sigmask.__bits[0], kp.p_sigmask.__bits[1], in TRACEME_VFORK_FORK_TEST()
1432 kp.p_sigmask.__bits[2], kp.p_sigmask.__bits[3]); in TRACEME_VFORK_FORK_TEST()
1442 kp_sigignore.__bits[0], kp_sigignore.__bits[1], in TRACEME_VFORK_FORK_TEST()
1443 kp_sigignore.__bits[2], kp_sigignore.__bits[3]); in TRACEME_VFORK_FORK_TEST()
1448 kp.p_sigignore.__bits[0], kp.p_sigignore.__bits[1], in TRACEME_VFORK_FORK_TEST()
1449 kp.p_sigignore.__bits[2], kp.p_sigignore.__bits[3]); in TRACEME_VFORK_FORK_TEST()
1488 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in TRACEME_VFORK_FORK_TEST()
1489 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in TRACEME_VFORK_FORK_TEST()
[all …]
H A Dt_ptrace_signal_wait.h583 kp_sigmask.__bits[0], kp_sigmask.__bits[1], kp_sigmask.__bits[2], in TRACEME_CRASH()
584 kp_sigmask.__bits[3]); in TRACEME_CRASH()
588 kp.p_sigmask.__bits[0], kp.p_sigmask.__bits[1], in TRACEME_CRASH()
589 kp.p_sigmask.__bits[2], kp.p_sigmask.__bits[3]); in TRACEME_CRASH()
766 kp_sigignore.__bits[0], kp_sigignore.__bits[1], in TRACEME_SIGNALMASKED_CRASH()
767 kp_sigignore.__bits[2], kp_sigignore.__bits[3]); in TRACEME_SIGNALMASKED_CRASH()
771 kp.p_sigignore.__bits[0], kp.p_sigignore.__bits[1], in TRACEME_SIGNALMASKED_CRASH()
772 kp.p_sigignore.__bits[2], kp.p_sigignore.__bits[3]); in TRACEME_SIGNALMASKED_CRASH()
1851 kp_sigmask.__bits[0], kp_sigmask.__bits[1], in TRACEME_VFORK_SIGNALIGNORED_CRASH()
1852 kp_sigmask.__bits[2], kp_sigmask.__bits[3]); in TRACEME_VFORK_SIGNALIGNORED_CRASH()
[all …]
H A Dt_select.c78 for (size_t i = __arraycount(m->__bits); i > 0; i--) { in prmask()
79 uint32_t p = m->__bits[i - 1]; in prmask()
/netbsd-src/sys/arch/powerpc/include/
H A Dfenv.h144 } __bits;
160 __r.__bits.__reg &= ~__excepts; in feclearexcept()
171 *__flagp = __r.__bits.__reg & __excepts; in fegetexceptflag()
183 __r.__bits.__reg &= ~__excepts; in fesetexceptflag()
184 __r.__bits.__reg |= *__flagp & __excepts; in fesetexceptflag()
197 __r.__bits.__reg |= __excepts; in feraiseexcept()
208 return (__r.__bits.__reg & __excepts); in fetestexcept()
217 return (__r.__bits.__reg & _ROUND_MASK); in fegetround()
228 __r.__bits.__reg &= ~_ROUND_MASK; in fesetround()
229 __r.__bits in fesetround()
143 } __bits; global() member
[all...]
/netbsd-src/sys/crypto/arch/arm/
H A Darm_neon.h490 vshlq_n_s32(int32x4_t __v, uint8_t __bits) in vshlq_n_s32() argument
493 return (int32x4_t)__builtin_aarch64_ashlv4si(__v, __bits); in vshlq_n_s32()
495 return (int32x4_t)__builtin_neon_vshl_nv4si(__v, __bits); in vshlq_n_s32()
499 #define vshlq_n_s32(__v, __bits) \ argument
500 (int32x4_t)__builtin_neon_vshlq_n_v((int32x4_t)(__v), (__bits), 34)
506 vshlq_n_u32(uint32x4_t __v, uint8_t __bits) in vshlq_n_u32() argument
509 return (uint32x4_t)__builtin_aarch64_ashlv4si((int32x4_t)__v, __bits); in vshlq_n_u32()
511 return (uint32x4_t)__builtin_neon_vshl_nv4si((int32x4_t)__v, __bits); in vshlq_n_u32()
515 #define vshlq_n_u32(__v, __bits) \ argument
516 (uint32x4_t)__builtin_neon_vshlq_n_v((int32x4_t)(__v), (__bits), 50)
[all …]
/netbsd-src/sys/arch/alpha/include/
H A Dfenv.h67 fenv_t __bits;
88 __r.__bits &= ~((fenv_t)__excepts << _FPUSW_SHIFT); in feclearexcept()
102 *__flagp = (__r.__bits >> _FPUSW_SHIFT) & __excepts; in fegetexceptflag()
116 __r.__bits &= ~__xexcepts; in fesetexceptflag()
117 __r.__bits |= __xflag & __xexcepts; in fesetexceptflag()
146 return (__r.__bits >> _FPUSW_SHIFT) & __excepts; in fetestexcept()
159 return (int)(__r.__bits >> _ROUND_SHIFT) & _ROUND_MASK; in fegetround()
171 __r.__bits &= ~((fenv_t)_ROUND_MASK << _ROUND_SHIFT); in fesetround()
172 __r.__bits |= (fenv_t)__round << _ROUND_SHIFT; in fesetround()
66 fenv_t __bits; global() member
/netbsd-src/lib/libc/compat-43/
H A Dsigcompat.c52 sa->sa_mask.__bits[0] = sv->sv_mask; in sv2sa()
60 sv->sv_mask = sa->sa_mask.__bits[0]; in sa2sv()
89 nmask.__bits[0] = mask; in sigsetmask()
94 return (omask.__bits[0]); in sigsetmask()
104 nmask.__bits[0] = mask; in sigblock()
109 return (omask.__bits[0]); in sigblock()
118 nmask.__bits[0] = mask; in sigpause()
/netbsd-src/sys/coda/
H A Dcoda_psdev.c630 p->p_sigpend.sp_set.__bits[0], p->p_sigpend.sp_set.__bits[1], in coda_call()
631 p->p_sigpend.sp_set.__bits[2], p->p_sigpend.sp_set.__bits[3], in coda_call()
632 l->l_sigmask.__bits[0], l->l_sigmask.__bits[1], in coda_call()
633 l->l_sigmask.__bits[2], l->l_sigmask.__bits[3], in coda_call()
634 tmp.__bits[0], tmp.__bits[1], tmp.__bits[2], tmp.__bits[3]); in coda_call()
641 p->p_sigpend.sp_set.__bits[0], p->p_sigpend.sp_set.__bits[1], in coda_call()
642 p->p_sigpend.sp_set.__bits[2], p->p_sigpend.sp_set.__bits[3], in coda_call()
643 l->l_sigmask.__bits[0], l->l_sigmask.__bits[1], in coda_call()
644 l->l_sigmask.__bits[2], l->l_sigmask.__bits[3]); in coda_call()
/netbsd-src/lib/libm/arch/alpha/
H A Dfenv.c68 *envp = r.__bits | p.mask; in fegetenv()
81 *envp = r.__bits | p.mask; in feholdexcept()
82 r.__bits &= ~((fenv_t)FE_ALL_EXCEPT << _FPUSW_SHIFT); in feholdexcept()
100 r.__bits = *envp & ~FE_ALL_EXCEPT; in fesetenv()
115 newr.__bits = *envp & ~FE_ALL_EXCEPT; in feupdateenv()
118 feraiseexcept((oldr.__bits >> _FPUSW_SHIFT) & FE_ALL_EXCEPT); in feupdateenv()
/netbsd-src/external/gpl3/gcc.old/dist/libstdc++-v3/include/parallel/
H A Drandom_number.h109 __genrand_bits(int __bits) in __genrand_bits() argument
111 unsigned long __res = __cache & ((1 << __bits) - 1); in __genrand_bits()
112 __cache = __cache >> __bits; in __genrand_bits()
113 __bits_left -= __bits; in __genrand_bits()
/netbsd-src/external/gpl3/gcc/dist/libstdc++-v3/include/parallel/
H A Drandom_number.h109 __genrand_bits(int __bits) in __genrand_bits() argument
111 unsigned long __res = __cache & ((1 << __bits) - 1); in __genrand_bits()
112 __cache = __cache >> __bits; in __genrand_bits()
113 __bits_left -= __bits; in __genrand_bits()
/netbsd-src/sys/compat/common/
H A Dkern_sig_13.c77 ss->__bits[0] = *oss; in native_sigset13_to_sigset()
78 ss->__bits[1] = 0; in native_sigset13_to_sigset()
79 ss->__bits[2] = 0; in native_sigset13_to_sigset()
80 ss->__bits[3] = 0; in native_sigset13_to_sigset()
87 *oss = ss->__bits[0]; in native_sigset_to_sigset13()
H A Dkern_sig_43.c90 ss->__bits[0] = *sm; in compat_43_sigmask_to_sigset()
91 ss->__bits[1] = 0; in compat_43_sigmask_to_sigset()
92 ss->__bits[2] = 0; in compat_43_sigmask_to_sigset()
93 ss->__bits[3] = 0; in compat_43_sigmask_to_sigset()
100 *sm = ss->__bits[0]; in compat_43_sigset_to_sigmask()
/netbsd-src/sys/crypto/arch/x86/
H A Dimmintrin.h254 _mm_slli_epi32(__m128i __v, uint8_t __bits) in _mm_slli_epi32() argument
256 return (__m128i)__builtin_ia32_pslldi128((__v4si)__v, (int)__bits); in _mm_slli_epi32()
261 _mm_slli_epi64(__m128i __v, uint8_t __bits) in _mm_slli_epi64() argument
263 return (__m128i)__builtin_ia32_psllqi128((__v2di)__v, (int)__bits); in _mm_slli_epi64()
278 _mm_srli_epi32(__m128i __v, uint8_t __bits) in _mm_srli_epi32() argument
280 return (__m128i)__builtin_ia32_psrldi128((__v4si)__v, (int)__bits); in _mm_srli_epi32()
285 _mm_srli_epi64(__m128i __v, uint8_t __bits) in _mm_srli_epi64() argument
287 return (__m128i)__builtin_ia32_psrlqi128((__v2di)__v, (int)__bits); in _mm_srli_epi64()
/netbsd-src/external/gpl3/gcc/dist/libphobos/libdruntime/core/sys/linux/
H A Dsched.d73 cpusetp.__bits[__CPUELT(cpu)] |= __CPUMASK(cpu); in version()
83 return (cpusetp.__bits[__CPUELT(cpu)] & __CPUMASK(cpu)) != 0; in version()
90 foreach (i; cpusetp.__bits[0 .. (setsize / cpu_mask.sizeof)]) in version()
102 cpu_mask[__CPU_SETSIZE / __NCPUBITS] __bits;
/netbsd-src/external/gpl3/gcc/dist/libgomp/config/linux/
H A Dproc.c62 extern int check[sizeof (cpusetp->__bits[0]) == sizeof (unsigned long int) in gomp_cpuset_popcount()
65 for (i = 0; i < cpusetsize / sizeof (cpusetp->__bits[0]); i++) in gomp_cpuset_popcount()
67 unsigned long int mask = cpusetp->__bits[i]; in gomp_cpuset_popcount()
/netbsd-src/external/gpl3/gcc.old/dist/libgomp/config/linux/
H A Dproc.c62 extern int check[sizeof (cpusetp->__bits[0]) == sizeof (unsigned long int) in gomp_cpuset_popcount()
65 for (i = 0; i < cpusetsize / sizeof (cpusetp->__bits[0]); i++) in gomp_cpuset_popcount()
67 unsigned long int mask = cpusetp->__bits[i]; in gomp_cpuset_popcount()
/netbsd-src/external/gpl3/gcc/dist/libstdc++-v3/include/experimental/bits/
H A Dsimd_fixed_size.h170 _S_submask(_BitMask<_Np, _Sanitized> __bits)
171 { return __bits.template _M_extract<_Offset, _S_size()>(); }
175 _S_make_mask(_BitMask<_Np, _Sanitized> __bits)
178 __bits.template _M_extract<_Offset, _S_size()>()._M_sanitized());
1292 const _MaskMember __bits, const _Up* __mem) noexcept
1296 if (__meta._S_submask(__bits).any())
1304 = __meta._S_masked_load(__native, __meta._S_make_mask(__bits),
1325 const _MaskMember __bits) noexcept
1328 if (__meta._S_submask(__bits).any())
1336 __meta._S_make_mask(__bits));
[all …]
/netbsd-src/sys/compat/ultrix/
H A Dultrix_misc.c552 mask = ss.__bits[0]; in ultrix_sys_sigpending()
586 ss.__bits[0] = mask; in ultrix_sys_sigsuspend()
587 ss.__bits[1] = 0; in ultrix_sys_sigsuspend()
588 ss.__bits[2] = 0; in ultrix_sys_sigsuspend()
589 ss.__bits[3] = 0; in ultrix_sys_sigsuspend()
/netbsd-src/sys/kern/
H A Dsys_ptrace_common.c819 pls.pl_sigpend.__bits[0], pls.pl_sigpend.__bits[1], in ptrace_lwpstatus()
820 pls.pl_sigpend.__bits[2], pls.pl_sigpend.__bits[3], in ptrace_lwpstatus()
821 pls.pl_sigmask.__bits[0], pls.pl_sigmask.__bits[1], in ptrace_lwpstatus()
822 pls.pl_sigmask.__bits[2], pls.pl_sigmask.__bits[3], in ptrace_lwpstatus()

123