Home
last modified time | relevance | path

Searched refs:__volatile__ (Results 1 – 25 of 93) sorted by relevance

1234

/freebsd/sys/i386/linux/
H A Dlinux_vdso_gtod.c61 __asm__ __volatile__ in write()
76 __asm__ __volatile__ in __vdso_clock_gettime_fallback()
91 __asm__ __volatile__ in __vdso_clock_gettime64_fallback()
106 __asm__ __volatile__ in __vdso_gettimeofday_fallback()
121 __asm__ __volatile__ in __vdso_clock_getres_fallback()
136 __asm__ __volatile__ in __vdso_getcpu_fallback()
151 __asm__ __volatile__ in __vdso_time_fallback()
/freebsd/sys/amd64/linux32/
H A Dlinux32_vdso_gtod.c61 __asm__ __volatile__ in write()
76 __asm__ __volatile__ in __vdso_clock_gettime_fallback()
91 __asm__ __volatile__ in __vdso_clock_gettime64_fallback()
106 __asm__ __volatile__ in __vdso_gettimeofday_fallback()
121 __asm__ __volatile__ in __vdso_clock_getres_fallback()
136 __asm__ __volatile__ in __vdso_getcpu_fallback()
151 __asm__ __volatile__ in __vdso_time_fallback()
/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/loongarch/
H A Dfp_mode.c24 __asm__ __volatile__("movfcsr2gr %0, $fcsr0" : "=r" (fcsr)); in __fe_getround()
26 __asm__ __volatile__("movfcsr2gr %0, $r0" : "=r" (fcsr)); in __fe_getround()
49 __asm__ __volatile__("movfcsr2gr %0, $fcsr0" : "=r" (fcsr)); in __fe_raise_inexact()
50 __asm__ __volatile__( in __fe_raise_inexact()
53 __asm__ __volatile__("movfcsr2gr %0, $r0" : "=r" (fcsr)); in __fe_raise_inexact()
54 __asm__ __volatile__( in __fe_raise_inexact()
/freebsd/sys/contrib/ck/include/gcc/ppc64/
H A Dck_pr.h57 __asm__ __volatile__("or 1, 1, 1;" in ck_pr_stall()
66 __asm__ __volatile__(I ::: "memory"); \
96 __asm__ __volatile__(I "%U1%X1 %0, %1" \
126 __asm__ __volatile__(I "%U0%X0 %1, %0" \
157 __asm__ __volatile__("1:" in ck_pr_cas_64_value()
179 __asm__ __volatile__("1:" in ck_pr_cas_ptr_value()
201 __asm__ __volatile__("1:" in ck_pr_cas_64()
222 __asm__ __volatile__("1:" in ck_pr_cas_ptr()
243 __asm__ __volatile__("1:" \
262 __asm__ __volatile__("1:" \
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A Dintrin.h243 __asm__ __volatile__("rep movsb" in __movsb()
248 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsb()
260 __asm__ __volatile__("rep movs{l|d}" in __movsd()
265 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsd()
277 __asm__ __volatile__("rep movsw" in __movsw()
282 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsw()
293 __asm__ __volatile__("rep stos{l|d}" in __stosd()
301 __asm__ __volatile__("rep stosw" in __stosw()
310 __asm__ __volatile__("rep movsq" in __movsq()
318 __asm__ __volatile__("rep stosq" : "+D"(__dst), "+c"(__n) : "a"(__x) in __stosq()
[all …]
H A Dimmintrin.h535 __asm__ __volatile__(".byte 0xf2 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange_HLEAcquire()
541 __asm__ __volatile__(".byte 0xf3 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange_HLERelease()
549 __asm__ __volatile__(".byte 0xf2 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange64_HLEAcquire()
555 __asm__ __volatile__(".byte 0xf3 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange64_HLERelease()
567 __asm__ __volatile__(".byte 0xf2 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange_HLEAcquire()
575 __asm__ __volatile__(".byte 0xf3 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange_HLERelease()
585 __asm__ __volatile__(".byte 0xf2 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange64_HLEAcquire()
593 __asm__ __volatile__(".byte 0xf3 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange64_HLERelease()
/freebsd/sys/amd64/linux/
H A Dlinux_vdso_gtod.c62 __asm__ __volatile__ in write()
77 __asm__ __volatile__ in __vdso_clock_gettime_fallback()
92 __asm__ __volatile__ in __vdso_gettimeofday_fallback()
107 __asm__ __volatile__ in __vdso_clock_getres_fallback()
122 __asm__ __volatile__ in __vdso_getcpu_fallback()
137 __asm__ __volatile__ in __vdso_time_fallback()
/freebsd/sys/contrib/ncsw/Peripherals/QM/
H A Dqman_private.h61 __asm__ __volatile__ ("dcbf 0, %0" : : "r" (addr)); \
67 __asm__ __volatile__ ("dcbt 0, %0" : : "r" (addr)); \
72 __asm__ __volatile__ ("dcbtst 0, %0" : : "r" (addr)); \
77 __asm__ __volatile__ ("dcbzl 0,%0" : : "r" (p)); \
101 __asm__ __volatile__ ("dcbt 0,%0" : : "r" (p)); \
106 __asm__ __volatile__ ("dcbtst 0,%0" : : "r" (p)); \
110 __asm__ __volatile__ ("dcbz 0,%0" : : "r" (p)); \
/freebsd/sys/contrib/ck/include/gcc/sparcv9/
H A Dck_pr.h55 __asm__ __volatile__("membar #LoadLoad" ::: "memory"); in ck_pr_stall()
63 __asm__ __volatile__(I ::: "memory"); \
93 __asm__ __volatile__(I " [%1], %0" \
117 __asm__ __volatile__(I " %0, [%1]" \
158 __asm__ __volatile__(CK_PR_INS_CASX " [%1] " CK_PR_ASI_ATOMIC ", %2, %0" in ck_pr_cas_64_value()
172 __asm__ __volatile__(CK_PR_INS_CASX " [%1] " CK_PR_ASI_ATOMIC ", %2, %0" in ck_pr_cas_64()
199 __asm__ __volatile__(CK_PR_INS_CAS " [%1] " CK_PR_ASI_ATOMIC ", %2, %0" \
210 __asm__ __volatile__(CK_PR_INS_CAS " [%1] " CK_PR_ASI_ATOMIC ", %2, %0" \
229 __asm__ __volatile__(CK_PR_INS_SWAP " [%1] " CK_PR_ASI_ATOMIC ", %0" \
/freebsd/sys/contrib/ck/include/gcc/x86/
H A Dck_pr.h55 __asm__ __volatile__("pause" ::: "memory"); in ck_pr_stall()
65 __asm__ __volatile__("" ::: "memory"); \
74 __asm__ __volatile__(I ::: "memory"); \
115 __asm__ __volatile__(I " %0, %1" \
142 __asm__ __volatile__(I " %1, %0" \
167 __asm__ __volatile__(I " %1, %0" \
195 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %1, %0" \
228 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %0" \
240 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %0; setz %1" \
281 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %1, %0" \
[all …]
/freebsd/sys/contrib/ck/include/gcc/x86_64/
H A Dck_pr.h67 __asm__ __volatile__("pause" ::: "memory"); in ck_pr_stall()
75 __asm__ __volatile__(I ::: "memory"); \
128 __asm__ __volatile__("prefetchw (%0)" in ck_pr_rfo()
144 __asm__ __volatile__(I " %0, %1" \
178 __asm__ __volatile__(I " %1, %0" \
206 __asm__ __volatile__("movq %%rdx, %%rcx;" in ck_pr_load_64_2()
249 __asm__ __volatile__(I " %1, %0" \
260 __asm__ __volatile__(I " %1, %0" \
293 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %1, %0" \
327 __asm__ __volatile__(CK_PR_LOCK_PREFIX I " %0" \
[all …]
H A Dck_pr_rtm.h69 __asm__ __volatile__(".byte 0xc7,0xf8;" in ck_pr_rtm_begin()
82 __asm__ __volatile__(".byte 0x0f,0x01,0xd5" ::: "memory"); in ck_pr_rtm_end()
90 __asm__ __volatile__(".byte 0xc6,0xf8,%P0" :: "i" (status) : "memory"); in ck_pr_rtm_abort()
99 __asm__ __volatile__(".byte 0x0f,0x01,0xd6;" in ck_pr_rtm_test()
/freebsd/sys/contrib/ncsw/Peripherals/BM/
H A Dbman_private.h60 __asm__ __volatile__ ("dcbf 0, %0" : : "r" (addr)); \
66 __asm__ __volatile__ ("dcbt 0, %0" : : "r" (addr)); \
71 __asm__ __volatile__ ("dcbtst 0, %0" : : "r" (addr)); \
76 __asm__ __volatile__ ("dcbzl 0,%0" : : "r" (p)); \
100 __asm__ __volatile__ ("dcbt 0,%0" : : "r" (p)); \
105 __asm__ __volatile__ ("dcbz 0,%0" : : "r" (p)); \
/freebsd/sys/contrib/ck/include/gcc/ppc/
H A Dck_pr.h58 __asm__ __volatile__("or 1, 1, 1;" in ck_pr_stall()
67 __asm__ __volatile__(I ::: "memory"); \
101 __asm__ __volatile__(I "%U1%X1 %0, %1" \ in CK_PR_FENCE()
127 __asm__ __volatile__(I "%U0%X0 %1, %0" \
154 __asm__ __volatile__("1:" \
173 __asm__ __volatile__("1:" \
202 __asm__ __volatile__("1:" \
225 __asm__ __volatile__("1:" \
259 __asm__ __volatile__("1:" \
296 __asm__ __volatile__("1:"
[all …]
/freebsd/sys/contrib/ck/include/gcc/arm/
H A Dck_pr.h53 __asm__ __volatile__("" ::: "memory"); in ck_pr_stall()
113 __asm__ __volatile__(I " %0, [%1];" \ in CK_PR_FENCE()
161 __asm__ __volatile__(I " %1, [%0]" \
217 __asm__ __volatile__("1:" \
261 __asm__ __volatile__("1:" \
302 __asm__ __volatile__("1:" in ck_pr_cas_ptr_value()
323 __asm__ __volatile__("1:" in ck_pr_cas_ptr()
344 __asm__ __volatile__("1:" \
368 __asm__ __volatile__("1:" \
401 __asm__ __volatile__("1:" \
[all …]
/freebsd/sys/contrib/ck/include/gcc/aarch64/
H A Dck_pr_llsc.h40 __asm__ __volatile__("1:" in ck_pr_cas_64_2_value()
74 __asm__ __volatile__("1:" in ck_pr_cas_64_2()
106 __asm__ __volatile__("1:\n" \
127 __asm__ __volatile__( \
169 __asm__ __volatile__("1:" \
200 __asm__ __volatile__("1:" \
241 __asm__ __volatile__("1:" \
288 __asm__ __volatile__("1:" in ck_pr_faa_ptr()
308 __asm__ __volatile__("1:" in ck_pr_faa_64()
328 __asm__ __volatile__("1:" \
H A Dck_pr_lse.h47 __asm__ __volatile__("casp %0, %1, %4, %5, [%6]\n" in ck_pr_cas_64_2_value()
78 __asm__ __volatile__("casp %0, %1, %2, %3, [%4]\n" in ck_pr_cas_64_2()
102 __asm__ __volatile__( \
114 __asm__ __volatile__( \
147 __asm__ __volatile__( \
173 __asm__ __volatile__(I "\n" \
208 __asm__ __volatile__(I "\n" \
250 __asm__ __volatile__( in ck_pr_faa_ptr()
265 __asm__ __volatile__( in ck_pr_faa_64()
280 __asm__ __volatile__( \
H A Dck_pr.h53 __asm__ __volatile__("" ::: "memory"); in ck_pr_stall()
95 __asm__ __volatile__(I " %w0, [%1]\n" \
106 __asm__ __volatile__(I " %0, [%1]\n" \
140 __asm__ __volatile__(I " %w2, [%1]" \
151 __asm__ __volatile__(I " %2, [%1]" \
197 __asm__ __volatile__("1:" \
/freebsd/contrib/llvm-project/libc/src/__support/FPUtil/x86_64/
H A Dsqrt.h28 __asm__ __volatile__("sqrtss %x1, %x0" : "=x"(result) : "x"(x));
34 __asm__ __volatile__("sqrtsd %x1, %x0" : "=x"(result) : "x"(x));
41 __asm__ __volatile__("sqrtsd %x1, %x0" : "=x"(result) : "x"(x));
46 __asm__ __volatile__("fsqrt" : "+t"(x));
/freebsd/tools/regression/tls/ttls3/
H A Dtls-test-lib.c38 __asm__ __volatile__ ( \
49 __asm__ __volatile__ ( \
60 __asm__ __volatile__ ( \
73 __asm__ __volatile__ ( \
/freebsd/sys/contrib/openzfs/module/zfs/
H A Dvdev_raidz_math_powerpc_altivec_common.h132 __asm__ __volatile__( \
162 __asm__ __volatile__( \
179 __asm__ __volatile__( \
198 __asm__ __volatile__( \
207 __asm__ __volatile__( \
222 __asm__ __volatile__( \
235 __asm__ __volatile__( \
243 __asm__ __volatile__( \
257 __asm__ __volatile__( \
266 __asm__ __volatile__( \
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/scudo/standalone/
H A Dmemtag.h131 __asm__ __volatile__( in active()
143 __asm__ __volatile__( in ~ScopedDisableMemoryTagChecks()
156 __asm__ __volatile__( in selectRandomTag()
175 __asm__ __volatile__( in storeTags()
239 __asm__ __volatile__(R"( in storeTag()
251 __asm__ __volatile__( in loadTag()
/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/aarch64/
H A Dfp_mode.c33 __asm__ __volatile__("mrs %0, fpcr" : "=r" (fpcr)); in __fe_getround()
54 __asm__ __volatile__("mrs %0, fpsr" : "=r" (fpsr)); in __fe_raise_inexact()
55 __asm__ __volatile__("msr fpsr, %0" : : "ri" (fpsr | AARCH64_INEXACT)); in __fe_raise_inexact()
/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/arm/
H A Dfp_mode.c33 __asm__ __volatile__("vmrs %0, fpscr" : "=r" (fpscr)); in __fe_getround()
54 __asm__ __volatile__("vmrs %0, fpscr" : "=r" (fpscr)); in __fe_raise_inexact()
55 __asm__ __volatile__("vmsr fpscr, %0" : : "ri" (fpscr | ARM_INEXACT)); in __fe_raise_inexact()
/freebsd/sys/contrib/libsodium/src/libsodium/sodium/
H A Druntime.c78 __asm__ __volatile__( in _cpuid()
91 __asm__ __volatile__("xchgl %%ebx, %k1; cpuid; xchgl %%ebx, %k1" in _cpuid()
96 __asm__ __volatile__("xchgq %%rbx, %q1; cpuid; xchgq %%rbx, %q1" in _cpuid()
101 __asm__ __volatile__("cpuid" in _cpuid()
173 __asm__ __volatile__(".byte 0x0f, 0x01, 0xd0" /* XGETBV */ in _sodium_runtime_intel_cpu_features()

1234