Home
last modified time | relevance | path

Searched refs:__asm__ (Results 1 – 25 of 240) sorted by relevance

12345678910

/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 Dasm_64.c5 __asm__ ("mov r8w, 100;"); in t1()
7 __asm__ ("mov r8d, 100;"); in t1()
9 __asm__ ("mov r8b, 100;"); in t1()
11 __asm__ ("mov r9w, 100;"); in t1()
13 __asm__ ("mov r9d, 100;"); in t1()
15 __asm__ ("mov r9b, 100;"); in t1()
17 __asm__ ("mov r10w, 100;"); in t1()
19 __asm__ ("mov r10d, 100;"); in t1()
21 __asm__ ("mov r10b, 100;"); in t1()
23 __asm__ ("mov r11w, 100;"); in t1()
[all …]
H A Dasm.c4 __asm__ ("foo1");
5 __asm__ ("foo2");
6 __asm__ ("foo3");
16 __asm__ volatile("" : "+m"(t)); in t2()
69 __asm__("xyz" in t11()
78 __asm__("xyz" in t12()
86 __asm__("xyz %1" in t13()
97 __asm__("xyz " in t15()
125 __asm__ ( "nop": "=m"(i)); in t17()
253 __asm__ volatile("" in t30()
[all …]
H A Dmangle.c19 void foo() __asm__("bar");
20 void foo2() __asm__("bar");
22 int nux __asm__("foo");
23 extern float nux2 __asm__("foo");
34 void foo3() __asm__("var");
39 int foo4 __asm__("var") = 4;
43 extern int foo5 __asm__("var2");
49 void foo6() __asm__("var2");
56 float foo8 __asm__("foo7") = 42;
60 extern int func (void) __asm__ ("FUNC");
[all …]
H A Dasm-attrs.c24 __asm__ ("foo0" : "=r"(g1) : "r"(a)); in test_attrs()
25 __asm__ ("foo1" : "=r"(g1) : "r"(a) : "cc"); in test_attrs()
26 __asm__ ("foo2" : "=r"(g1) : "r"(a) : "memory"); in test_attrs()
27 __asm__ volatile("foo3" : "=r"(g1) : "r"(a)); in test_attrs()
28 __asm__ ("foo4" : "=r"(g1) : "r"(a), "m"(g0)); in test_attrs()
29 __asm__ ("foo5" : "=r"(g1) : "r"(a), "Q"(g0)); in test_attrs()
30 __asm__ ("foo6" : "=r"(g1), "=m"(g0) : "r"(a)); in test_attrs()
31 __asm__ ("foo7" : : "r"(a)); in test_attrs()
32 __asm__ ("foo8" : "=r"(g2) : "r"(a)); in test_attrs()
H A D2006-01-23-FileScopeAsm.c4 __asm__ ("foo1");
6 __asm__ ("foo2");
8 __asm__ ("foo3");
10 __asm__ ("foo4");
12 __asm__ ("foo5");
H A Dm68k-asm.c8 __asm__ ("move%.l #66, %%d1" ::); in escaped()
11 __asm__ ("move.l %#66, %%d1" ::); in escaped()
14 __asm__ ("move.l #66, %/d1" ::); in escaped()
17 __asm__ ("mul%$ %%d0, %%d1" ::); in escaped()
20 __asm__ ("move.l %%%&0, %%d1" ::); in escaped()
/llvm-project-15.0.7/clang/test/CodeGen/X86/
H A Dx86_32-inline-asm.c26 __asm__ volatile("wrmsr" in func1()
66 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error. in func1()
67 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error. in func1()
75 __asm__ volatile("foo1 %0" : : "x" (val128)); // No error. in _func2()
76 __asm__ volatile("foo1 %0" : "=x" (val128)); // No error. in _func2()
78 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error. in _func2()
79 __asm__ volatile("foo1 %0" : "=x" (val256)); // No error. in _func2()
89 __asm__ volatile("foo1 %0" : : "x" (val128)); // No error. in _func3()
90 __asm__ volatile("foo1 %0" : "=x" (val128)); // No error. in _func3()
91 __asm__ volatile("foo1 %0" : : "x" (val256)); // No error. in _func3()
[all …]
H A Dx86-inline-asm-v-constraint.c12 __asm__("vmovhlps %1, %2, %0" :"=v"(_xmm0) : "v"(_l), "v"(_xmm0)); in testXMM()
19 __asm__("vmovsldup %1, %0" :"=v"(_ymm0) : "v"(_ymm0)); in testYMM()
27 __asm__("vpternlogd $0, %1, %2, %0" :"=v"(_zmm0) : "v"(_zmm1), "v"(_zmm0)); in testZMM()
35 __asm__("pcmpeqd %0, %0" :"=Yz"(xmm0)); in testXMM0()
43 __asm__("vpcmpeqd %0, %0, %0" :"=Yz"(ymm0)); in testYMM0()
52 __asm__("vpternlogd $255, %0, %0, %0" :"=Yz"(zmm0)); in testZMM0()
H A Dx86-inline-asm-min-vector-width.c10 __asm__("vmovdqu %1, %0" :"=v"(xmm0) : "m"(*(__m128i*)p)); in testXMMout()
17 __asm__("vmovdqu %1, %0" :"=v"(ymm0) : "m"(*(__m256i*)p)); in testYMMout()
24 __asm__("vmovdqu64 %1, %0" :"=v"(zmm0) : "m"(*(__m512i*)p)); in testZMMout()
30 __asm__("vmovdqu %0, %1" : : "v"(xmm0), "m"(*(__m128i*)p)); in testXMMin()
35 __asm__("vmovdqu %0, %1" : : "v"(ymm0), "m"(*(__m256i*)p)); in testYMMin()
40 __asm__("vmovdqu64 %0, %1" : : "v"(zmm0), "m"(*(__m512i*)p)); in testZMMin()
H A Dx86-GCC-inline-asm-Y-constraints.c12 __asm__ volatile ("movq %0, %%mm1\n\t" in f_Ym()
21 __asm__ volatile ("vpaddq %0, %1, %2\n\t" in f_Yi()
31 __asm__ volatile ("vpaddq %0, %1, %2\n\t" in f_Yt()
41 __asm__ volatile ("vpaddq %0, %1, %2\n\t" in f_Y2()
52 __asm__ volatile ("vpaddq %0,%2,%1\n\t" in f_Yz()
/llvm-project-15.0.7/clang/test/Sema/
H A Dinline-asm-validate-x86.c7 __asm__("xorl %0,%2" in I()
10 __asm__("xorl %0,%2" in I()
13 __asm__("xorl %0,%2" in I()
21 __asm__("xorl %0,%2" in J()
24 __asm__("xorl %0,%2" in J()
27 __asm__("xorl %0,%2" in J()
35 __asm__("xorl %0,%2" in K()
38 __asm__("xorl %0,%2" in K()
41 __asm__("xorl %0,%2" in K()
54 __asm__("xorl %0,%2" in L()
[all …]
H A Dasm-label.c4 void f(void) __asm__("fish");
10 void g(void) __asm__("gold"); // expected-error{{cannot apply asm label to function after its firs…
12 void h(void) __asm__("hose"); // expected-note{{previous declaration is here}}
13 void h(void) __asm__("hair"); // expected-error{{conflicting asm label}}
16 int x __asm__("xenon");
21 int y __asm__("yacht"); // expected-error{{cannot apply asm label to variable after its first use}}
23 int z __asm__("zebra"); // expected-note{{previous declaration is here}}
24 int z __asm__("zooms"); // expected-error{{conflicting asm label}}
H A Dasm.c214 __asm__("" in fn1()
221 __asm__("" in fn2()
227 __asm__("" in fn3()
233 __asm__("" in fn4()
240 __asm__("" in fn5()
247 __asm__("" in fn6()
266 __asm__("movl $5, %0" in test16()
268 __asm__("movl $5, %0" in test16()
271 __asm__("movl $5, %0" in test16()
273 __asm__("movl $5, %0" in test16()
[all …]
H A Dinline-asm-validate-amdgpu.cl11 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "s" (imm) : );
19 __asm__ ("v_mov_b32 %0, %1" : "=v" (vgpr) : "v" (imm) : );
22 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "I" (imm) : );
23 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "I" (-16) : );
24 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "I" (64) : );
29 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "J" (imm) : );
31 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "J" (32767) : );
36 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "A" (imm) : );
39 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "B" (imm) : );
42 __asm__ ("s_mov_b32 %0, %1" : "=s" (sgpr) : "C" (imm) : );
[all …]
/llvm-project-15.0.7/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_syscall_linux_hexagon.inc37 register u32 r6 __asm__("r6") = n;
38 register u32 r0 __asm__("r0");
45 register u32 r6 __asm__("r6") = n;
46 register u32 r0 __asm__("r0") = a;
54 register u32 r6 __asm__("r6") = n;
55 register u32 r0 __asm__("r0") = a;
56 register u32 r1 __asm__("r1") = b;
64 register u32 r6 __asm__("r6") = n;
65 register u32 r0 __asm__("r0") = a;
66 register u32 r1 __asm__("r1") = b;
[all …]
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_linux_s390.cpp76 register uptr res __asm__("r2"); in internal_clone() local
77 register void *__cstack __asm__("r2") = child_stack; in internal_clone() local
78 register long __flags __asm__("r3") = flags; in internal_clone() local
79 register int * __ptidptr __asm__("r4") = parent_tidptr; in internal_clone() local
80 register int * __ctidptr __asm__("r5") = child_tidptr; in internal_clone() local
81 register void * __newtls __asm__("r6") = newtls; in internal_clone() local
83 __asm__ __volatile__( in internal_clone()
/llvm-project-15.0.7/compiler-rt/lib/crt/
H A Dcrtbegin.c52 __asm__(".pushsection .init,\"ax\",@progbits\n\t"
56 __asm__(".pushsection .init,\"ax\",%progbits\n\t"
60 __asm__(".pushsection .init,\"ax\",%progbits\n\t"
64 __asm__(".pushsection .init,\"ax\",@progbits\n\t"
69 __asm__(".pushsection .init,\"ax\",@progbits\n\t"
105 __asm__(".pushsection .fini,\"ax\",@progbits\n\t"
109 __asm__(".pushsection .fini,\"ax\",%progbits\n\t"
113 __asm__(".pushsection .fini,\"ax\",@progbits\n\t"
118 __asm__(".pushsection .fini,\"ax\",@progbits\n\t"
122 __asm__(".pushsection .fini,\"ax\",@progbits\n\t"
/llvm-project-15.0.7/clang/test/Parser/
H A Dasm-qualifiers.c19 __asm__(""); in underscores()
20 __asm__ __volatile__(""); in underscores()
21 __asm__ __inline__(""); in underscores()
23 __asm__ goto("" ::::foo); in underscores()
44 __asm__ __volatile__ __volatile__(""); // expected-error {{duplicate asm qualifier 'volatile'}} in duplicates()
46 __asm__ __inline__ __inline__(""); // expected-error {{duplicate asm qualifier 'inline'}} in duplicates()
48 __asm__ goto goto("" ::::foo); // expected-error {{duplicate asm qualifier 'goto'}} in duplicates()
/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/libc/src/__support/OSUtil/linux/aarch64/
H A Dsyscall.h15 register long x8 __asm__("x8") = number; \
16 register long x0 __asm__("x0");
18 register long x8 __asm__("x8") = number; \
19 register long x0 __asm__("x0") = arg1;
20 #define REGISTER_DECL_2 REGISTER_DECL_1 register long x1 __asm__("x1") = arg2;
23 register long x2 __asm__("x2") = arg3;
26 register long x3 __asm__("x3") = arg4;
29 register long x4 __asm__("x4") = arg5;
32 register long x5 __asm__("x5") = arg6;
/llvm-project-15.0.7/clang/test/OpenMP/
H A Dnvptx_asm_delayed_diags.c21 __asm__("PR3908 %[lf] %[xx] %[li] %[r]" in bar()
36 __asm__("PR3908 %[lf] %[xx] %[li] %[r]" in foo()
51 __asm__("PR3908 %[lf] %[xx] %[li] %[r]" in t1()
61 __asm__("xyz" in t2()
86 __asm__("0:\n1:\n" in t4()
98 __asm__ __volatile__( in t5()
112 __asm__ volatile("vmovaps %0, %%ymm0" ::"m"(*(__m256i *)p) in t6()
/llvm-project-15.0.7/clang/lib/Headers/
H A D__clang_cuda_device_functions.h41 __asm__ __volatile__("brkpt;"); in __brkpt()
1183 __asm__("vset2.u32.u32.eq %0,%1,%2,%3;" in __vseteq2()
1193 __asm__("vset4.u32.u32.eq %0,%1,%2,%3;" in __vseteq4()
1203 __asm__("vset2.s32.s32.ge %0,%1,%2,%3;" in __vsetges2()
1213 __asm__("vset4.s32.s32.ge %0,%1,%2,%3;" in __vsetges4()
1223 __asm__("vset2.u32.u32.ge %0,%1,%2,%3;" in __vsetgeu2()
1233 __asm__("vset4.u32.u32.ge %0,%1,%2,%3;" in __vsetgeu4()
1243 __asm__("vset2.s32.s32.gt %0,%1,%2,%3;" in __vsetgts2()
1253 __asm__("vset4.s32.s32.gt %0,%1,%2,%3;" in __vsetgts4()
1263 __asm__("vset2.u32.u32.gt %0,%1,%2,%3;" in __vsetgtu2()
[all …]
/llvm-project-15.0.7/clang/test/SemaCUDA/
H A Dasm_delayed_diags.cu17 __asm__("PR3908 %[lf] %[xx] %[li] %[r]" in t1()
24 __asm__("xyz" in t2()
43 __asm__("0:\n1:\n" in t4()
52 __asm__ __volatile__( in t5()
63 __asm__ volatile("vmovaps %0, %%ymm0" ::"m"(*(__m256i *)p) in t6()
68 __asm__ volatile("vmovaps %0, %%ymm0" ::"m"(*(__m256i *)p) in t7()

12345678910