Home
last modified time | relevance | path

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

12345

/llvm-project-15.0.7/clang/test/CodeGen/
H A Dmips-clobber-reg.c19 __asm__ __volatile__ ("addi $7,$v0,77":::"v0"); in main()
20 __asm__ __volatile__ ("addi $7,$v1,77":::"v1"); in main()
21 __asm__ __volatile__ ("addi $7,$a0,77":::"a0"); in main()
22 __asm__ __volatile__ ("addi $7,$a1,77":::"a1"); in main()
23 __asm__ __volatile__ ("addi $7,$a2,77":::"a2"); in main()
24 __asm__ __volatile__ ("addi $7,$a3,77":::"a3"); in main()
25 __asm__ __volatile__ ("addi $7,$t0,77":::"t0"); in main()
26 __asm__ __volatile__ ("addi $7,$t1,77":::"t1"); in main()
27 __asm__ __volatile__ ("addi $7,$t2,77":::"t2"); in main()
28 __asm__ __volatile__ ("addi $7,$t3,77":::"t3"); in main()
[all …]
H A Dinline-asm-immediate-ubsan.c18 __asm__ __volatile__("int %0" :: "i"(1 + 1)); in test_inlineasm_i()
25 __asm__ __volatile__("int %0" :: "I"(1 + 1)); in test_inlineasm_I()
29 __asm__ __volatile__("int %0" :: "I"(N + 2)); in test_inlineasm_I()
H A Dmips-constraint-regs.c15 __asm__ __volatile__( in main()
26 __asm__ __volatile__( in main()
39 __asm__ __volatile__( in main()
/llvm-project-15.0.7/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_atomic_clang_x86.h20 __asm__ __volatile__("" ::: "memory"); in proc_yield()
22 __asm__ __volatile__("pause"); in proc_yield()
23 __asm__ __volatile__("" ::: "memory"); in proc_yield()
41 __asm__ __volatile__("" ::: "memory"); in atomic_load()
43 __asm__ __volatile__("" ::: "memory"); in atomic_load()
45 __asm__ __volatile__("" ::: "memory"); in atomic_load()
48 __asm__ __volatile__("" ::: "memory"); in atomic_load()
51 __asm__ __volatile__("" ::: "memory"); in atomic_load()
53 __asm__ __volatile__("" ::: "memory"); in atomic_load()
57 __asm__ __volatile__( in atomic_load()
[all …]
H A Dsanitizer_atomic_clang_other.h21 __asm__ __volatile__("" ::: "memory"); in proc_yield()
39 __asm__ __volatile__("" ::: "memory"); in atomic_load()
41 __asm__ __volatile__("" ::: "memory"); in atomic_load()
43 __asm__ __volatile__("" ::: "memory"); in atomic_load()
72 __asm__ __volatile__("" ::: "memory"); in atomic_store()
/llvm-project-15.0.7/bolt/runtime/
H A Dcommon.h323 __asm__ __volatile__("movq $2, %%rax\n" in __open()
342 __asm__ __volatile__("movq $78, %%rax\n" in __getdents()
352 __asm__ __volatile__("movq $89, %%rax\n" in __readlink()
362 __asm__ __volatile__("movq $8, %%rax\n" in __lseek()
372 __asm__ __volatile__("movq $3, %%rax\n" in __close()
382 __asm__ __volatile__("movq $28, %%rax\n" in __madvise()
397 __asm__ __volatile__("movq $35, %%rax\n" in __nanosleep()
407 __asm__ __volatile__("movq $57, %%rax\n" in __fork()
417 __asm__ __volatile__("movq $10, %%rax\n" in __mprotect()
427 __asm__ __volatile__("movq $39, %%rax\n" in __getpid()
[all …]
/llvm-project-15.0.7/clang/test/CodeGen/X86/
H A Dx86-64-inline-asm.c24 __asm__ __volatile__("\n#define S_A abcd%0\n" : : "n"(&((struct s*)0)->a)); in pr40890()
25 __asm__ __volatile__("\n#define S_B abcd%0\n" : : "n"(&((struct s*)0)->b)); in pr40890()
26 __asm__ __volatile__("\n#define BEEF abcd%0\n" : : "n"((int*)0xdeadbeeeeeef)); in pr40890()
27 __asm__ __volatile__("movabsq %0, %%rax" : : "n"(4624529908474429119)); in pr40890()
/llvm-project-15.0.7/libc/src/__support/FPUtil/x86_64/
H A Dsqrt.h25 __asm__ __volatile__("sqrtss %x1, %x0" : "=x"(result) : "x"(x));
31 __asm__ __volatile__("sqrtsd %x1, %x0" : "=x"(result) : "x"(x));
38 __asm__ __volatile__("sqrtsd %x1, %x0" : "=x"(result) : "x"(x));
43 __asm__ __volatile__("fsqrt" : "+t"(x));
H A DFEnvImpl.h106 __asm__ __volatile__("fnstcw %0" : "=m"(w)::); in get_x87_control_word()
112 __asm__ __volatile__("fldcw %0" : : "m"(w) :); in write_x87_control_word()
117 __asm__ __volatile__("fnstsw %0" : "=m"(w)::); in get_x87_status_word()
123 __asm__ __volatile__("fnclex" : : :); in clear_x87_exceptions()
128 __asm__ __volatile__("stmxcsr %0" : "=m"(w)::); in get_mxcsr()
134 __asm__ __volatile__("ldmxcsr %0" : : "m"(w) :); in write_mxcsr()
138 __asm__ __volatile__("fnstenv %0" : "=m"(s)); in get_x87_state_descriptor()
143 __asm__ __volatile__("fldenv %0" : : "m"(s) :); in write_x87_state_descriptor()
146 static inline void fwait() { __asm__ __volatile__("fwait"); } in fwait()
/llvm-project-15.0.7/compiler-rt/lib/scudo/standalone/
H A Dmemtag.h128 __asm__ __volatile__( in ScopedDisableMemoryTagChecks()
138 __asm__ __volatile__( in ~ScopedDisableMemoryTagChecks()
151 __asm__ __volatile__( in selectRandomTag()
170 __asm__ __volatile__( in storeTags()
234 __asm__ __volatile__(R"( in storeTag()
246 __asm__ __volatile__( in loadTag()
H A Dcommon.h106 __asm__ __volatile__("" ::: "memory"); in yieldProcessor()
108 __asm__ __volatile__("pause"); in yieldProcessor()
110 __asm__ __volatile__("" ::: "memory"); in yieldProcessor()
112 __asm__ __volatile__("yield"); in yieldProcessor()
114 __asm__ __volatile__("" ::: "memory"); in yieldProcessor()
/llvm-project-15.0.7/clang/test/Parser/
H A Dasm-qualifiers.c20 __asm__ __volatile__(""); in underscores()
44 __asm__ __volatile__ __volatile__(""); // expected-error {{duplicate asm qualifier 'volatile'}} in duplicates()
/llvm-project-15.0.7/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()
/llvm-project-15.0.7/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()
/llvm-project-15.0.7/clang/lib/Headers/
H A Dintrin.h453 __asm__ __volatile__("rep movsb" in __movsb()
458 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsb()
470 __asm__ __volatile__("rep movs{l|d}" in __movsd()
475 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsd()
487 __asm__ __volatile__("rep movsw" in __movsw()
492 __asm__ __volatile__("xchg {%%esi, %1|%1, esi}\n" in __movsw()
503 __asm__ __volatile__("rep stos{l|d}" in __stosd()
511 __asm__ __volatile__("rep stosw" in __stosw()
520 __asm__ __volatile__("rep movsq" in __movsq()
528 __asm__ __volatile__("rep stosq" : "+D"(__dst), "+c"(__n) : "a"(__x) in __stosq()
[all …]
H A Dimmintrin.h546 __asm__ __volatile__(".byte 0xf2 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange_HLEAcquire()
552 __asm__ __volatile__(".byte 0xf3 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange_HLERelease()
560 __asm__ __volatile__(".byte 0xf2 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange64_HLEAcquire()
566 __asm__ __volatile__(".byte 0xf3 ; lock ; xchg {%0, %1|%1, %0}" in _InterlockedExchange64_HLERelease()
578 __asm__ __volatile__(".byte 0xf2 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange_HLEAcquire()
586 __asm__ __volatile__(".byte 0xf3 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange_HLERelease()
596 __asm__ __volatile__(".byte 0xf2 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange64_HLEAcquire()
604 __asm__ __volatile__(".byte 0xf3 ; lock ; cmpxchg {%2, %1|%1, %2}" in _InterlockedCompareExchange64_HLERelease()
/llvm-project-15.0.7/llvm/lib/Support/BLAKE3/
H A Dblake3_dispatch.c25 __asm__ __volatile__("xgetbv\n" : "=a"(eax), "=d"(edx) : "c"(0)); in xgetbv()
34 __asm__ __volatile__("movl %%ebx, %1\n" in cpuid()
40 __asm__ __volatile__("cpuid\n" in cpuid()
50 __asm__ __volatile__("movl %%ebx, %1\n" in cpuidex()
56 __asm__ __volatile__("cpuid\n" in cpuidex()
/llvm-project-15.0.7/libc/src/math/x86_64/
H A Dtan.cpp18 __asm__ __volatile__("fptan" : "+t"(x)); variable
19 __asm__ __volatile__("fstpl %0" : "=m"(result)); variable
/llvm-project-15.0.7/clang/test/Sema/
H A Dinline-asm-validate-x86.c125 __asm__ __volatile__("\n#define S_A abcd%0\n" : : "n"(&((struct s*)0)->a)); in pr40890()
127 __asm__ __volatile__("\n#define S_B abcd%0\n" : : "n"(&((struct s*)0)->b)); in pr40890()
130 __asm__ __volatile__("\n#define BEEF abcd%0\n" : : "n"((int*)0xdeadbeeeeeef)); in pr40890()
/llvm-project-15.0.7/lldb/test/API/commands/watchpoints/watch_tagged_addr/
H A Dmain.c13 __asm__ __volatile__("pacdza %0" : "=r"(tagged_ptr) : "r"(tagged_ptr)); in main()
23 __asm__ __volatile__("autdza %0" : "=r"(tagged_ptr) : "r"(tagged_ptr)); in main()
/llvm-project-15.0.7/libc/src/__support/FPUtil/aarch64/
H A Dnearest_integer.h23 __asm__ __volatile__("frintn %s0, %s1\n\t" : "=w"(result) : "w"(x)); in nearest_integer()
29 __asm__ __volatile__("frintn %d0, %d1\n\t" : "=w"(result) : "w"(x)); in nearest_integer()
H A Dsqrt.h25 __asm__ __volatile__("fsqrt %s0, %s1\n\t" : "=w"(y) : "w"(x));
31 __asm__ __volatile__("fsqrt %d0, %d1\n\t" : "=w"(y) : "w"(x));
H A DFMA.h30 __asm__ __volatile__("fmadd %s0, %s1, %s2, %s3\n\t" in fma()
39 __asm__ __volatile__("fmadd %d0, %d1, %d2, %d3\n\t" in fma()
/llvm-project-15.0.7/compiler-rt/lib/builtins/i386/
H A Dfp_mode.c20 __asm__ __volatile__ ("fnstcw %0" : "=m" (cw)); in __fe_getround()
37 __asm__ __volatile__ ("fdivs %1" : "+t" (f) : "m" (g)); in __fe_raise_inexact()
/llvm-project-15.0.7/libc/AOR_v20.02/math/
H A Dmath_config.h194 __asm__ __volatile__ ("" : "+w" (x)); in opt_barrier_float()
200 __asm__ __volatile__ ("" : "+w" (x)); in opt_barrier_double()
207 __asm__ __volatile__ ("" : "+w" (x)); in force_eval_float()
212 __asm__ __volatile__ ("" : "+w" (x)); in force_eval_double()

12345