1 // REQUIRES: x86-registered-target
2 // RUN: %clang_cc1 %s -triple=x86_64-linux-gnu -S -o -
3 #define __MM_MALLOC_H
4
5 #include <x86intrin.h>
6
7 // No warnings.
8 extern __m256i a;
bar(void)9 int __attribute__((target("avx"))) bar(void) {
10 return _mm256_extract_epi32(a, 3);
11 }
12
baz(void)13 int baz(void) {
14 return bar();
15 }
16
qq_avx(void)17 int __attribute__((target("avx"))) qq_avx(void) {
18 return _mm256_extract_epi32(a, 3);
19 }
20
qq_noavx(void)21 int qq_noavx(void) {
22 return 0;
23 }
24
25 extern __m256i a;
qq(void)26 int qq(void) {
27 if (__builtin_cpu_supports("avx"))
28 return qq_avx();
29 else
30 return qq_noavx();
31 }
32
33 // Test that fma and fma4 are both separately and combined valid for an fma intrinsic.
fma_1(__m128 a,__m128 b,__m128 c)34 __m128 __attribute__((target("fma"))) fma_1(__m128 a, __m128 b, __m128 c) {
35 return __builtin_ia32_vfmaddps(a, b, c);
36 }
37
fma_2(__m128 a,__m128 b,__m128 c)38 __m128 __attribute__((target("fma4"))) fma_2(__m128 a, __m128 b, __m128 c) {
39 return __builtin_ia32_vfmaddps(a, b, c);
40 }
41
fma_3(__m128 a,__m128 b,__m128 c)42 __m128 __attribute__((target("fma,fma4"))) fma_3(__m128 a, __m128 b, __m128 c) {
43 return __builtin_ia32_vfmaddps(a, b, c);
44 }
45
verifyfeaturestrings(void)46 void verifyfeaturestrings(void) {
47 (void)__builtin_cpu_supports("cmov");
48 (void)__builtin_cpu_supports("mmx");
49 (void)__builtin_cpu_supports("popcnt");
50 (void)__builtin_cpu_supports("sse");
51 (void)__builtin_cpu_supports("sse2");
52 (void)__builtin_cpu_supports("sse3");
53 (void)__builtin_cpu_supports("ssse3");
54 (void)__builtin_cpu_supports("sse4.1");
55 (void)__builtin_cpu_supports("sse4.2");
56 (void)__builtin_cpu_supports("avx");
57 (void)__builtin_cpu_supports("avx2");
58 (void)__builtin_cpu_supports("sse4a");
59 (void)__builtin_cpu_supports("fma4");
60 (void)__builtin_cpu_supports("xop");
61 (void)__builtin_cpu_supports("fma");
62 (void)__builtin_cpu_supports("avx512f");
63 (void)__builtin_cpu_supports("bmi");
64 (void)__builtin_cpu_supports("bmi2");
65 (void)__builtin_cpu_supports("aes");
66 (void)__builtin_cpu_supports("pclmul");
67 (void)__builtin_cpu_supports("avx512vl");
68 (void)__builtin_cpu_supports("avx512bw");
69 (void)__builtin_cpu_supports("avx512dq");
70 (void)__builtin_cpu_supports("avx512cd");
71 (void)__builtin_cpu_supports("avx512er");
72 (void)__builtin_cpu_supports("avx512pf");
73 (void)__builtin_cpu_supports("avx512vbmi");
74 (void)__builtin_cpu_supports("avx512ifma");
75 (void)__builtin_cpu_supports("avx5124vnniw");
76 (void)__builtin_cpu_supports("avx5124fmaps");
77 (void)__builtin_cpu_supports("avx512vpopcntdq");
78 (void)__builtin_cpu_supports("avx512vbmi2");
79 (void)__builtin_cpu_supports("gfni");
80 (void)__builtin_cpu_supports("vpclmulqdq");
81 (void)__builtin_cpu_supports("avx512vnni");
82 (void)__builtin_cpu_supports("avx512bitalg");
83 (void)__builtin_cpu_supports("avx512bf16");
84 (void)__builtin_cpu_supports("avx512vp2intersect");
85 }
86
verifycpustrings(void)87 void verifycpustrings(void) {
88 (void)__builtin_cpu_is("alderlake");
89 (void)__builtin_cpu_is("amd");
90 (void)__builtin_cpu_is("amdfam10h");
91 (void)__builtin_cpu_is("amdfam15h");
92 (void)__builtin_cpu_is("amdfam17h");
93 (void)__builtin_cpu_is("atom");
94 (void)__builtin_cpu_is("barcelona");
95 (void)__builtin_cpu_is("bdver1");
96 (void)__builtin_cpu_is("bdver2");
97 (void)__builtin_cpu_is("bdver3");
98 (void)__builtin_cpu_is("bdver4");
99 (void)__builtin_cpu_is("bonnell");
100 (void)__builtin_cpu_is("broadwell");
101 (void)__builtin_cpu_is("btver1");
102 (void)__builtin_cpu_is("btver2");
103 (void)__builtin_cpu_is("cannonlake");
104 (void)__builtin_cpu_is("cascadelake");
105 (void)__builtin_cpu_is("cooperlake");
106 (void)__builtin_cpu_is("core2");
107 (void)__builtin_cpu_is("corei7");
108 (void)__builtin_cpu_is("goldmont");
109 (void)__builtin_cpu_is("goldmont-plus");
110 (void)__builtin_cpu_is("haswell");
111 (void)__builtin_cpu_is("icelake-client");
112 (void)__builtin_cpu_is("icelake-server");
113 (void)__builtin_cpu_is("intel");
114 (void)__builtin_cpu_is("istanbul");
115 (void)__builtin_cpu_is("ivybridge");
116 (void)__builtin_cpu_is("knl");
117 (void)__builtin_cpu_is("knm");
118 (void)__builtin_cpu_is("nehalem");
119 (void)__builtin_cpu_is("rocketlake");
120 (void)__builtin_cpu_is("sandybridge");
121 (void)__builtin_cpu_is("shanghai");
122 (void)__builtin_cpu_is("silvermont");
123 (void)__builtin_cpu_is("skylake");
124 (void)__builtin_cpu_is("skylake-avx512");
125 (void)__builtin_cpu_is("slm");
126 (void)__builtin_cpu_is("tigerlake");
127 (void)__builtin_cpu_is("sapphirerapids");
128 (void)__builtin_cpu_is("tremont");
129 (void)__builtin_cpu_is("westmere");
130 (void)__builtin_cpu_is("znver1");
131 (void)__builtin_cpu_is("znver2");
132 (void)__builtin_cpu_is("znver3");
133 }
134