1 # Copyright
(C
) 1997-2018 Free Software Foundation
, Inc.
3 # This
program is free software
; you can redistribute it and
/or modify
4 # it under the terms of the GNU General Public License as published by
5 # the Free Software Foundation
; either version
3 of the License
, or
6 #
(at your option
) any later version.
8 # This
program is distributed in the hope that it will be useful
,
9 # but WITHOUT
ANY WARRANTY
; without even the implied warranty of
10 # MERCHANTABILITY or FITNESS
FOR A PARTICULAR PURPOSE. See the
11 # GNU General Public License
for more details.
13 # You should have received a copy of the GNU General Public License
14 # along with GCC
; see the file COPYING3.
If not see
15 #
<http
://www.gnu.org
/licenses
/>.
17 # GCC testsuite that uses the `dg.exp
' driver.
19 # Exit immediately if this isn't a x86 target.
20 if { ![istarget i?
86*-*-*] && ![istarget x86_64
-*-*] } then {
29 #
Return 1 if attribute ms_hook_prologue is supported.
30 proc check_effective_target_ms_hook_prologue
{ } {
31 if { [check_no_compiler_messages ms_hook_prologue object
{
32 void __attribute__
((__ms_hook_prologue__
)) foo
();
40 #
Return 1 if 3dnow instructions can be compiled.
41 proc check_effective_target_3dnow
{ } {
42 return [check_no_compiler_messages
3dnow object
{
43 typedef
int __m64 __attribute__
((__vector_size__
(8)));
44 typedef float __v2sf __attribute__
((__vector_size__
(8)));
46 __m64 _m_pfadd
(__m64 __A
, __m64 __B
)
48 return (__m64
) __builtin_ia32_pfadd
((__v2sf
)__A
, (__v2sf
)__B
);
53 #
Return 1 if sse3 instructions can be compiled.
54 proc check_effective_target_sse3
{ } {
55 return [check_no_compiler_messages sse3 object
{
56 typedef double __m128d __attribute__
((__vector_size__
(16)));
57 typedef double __v2df __attribute__
((__vector_size__
(16)));
59 __m128d _mm_addsub_pd
(__m128d __X
, __m128d __Y
)
61 return (__m128d
) __builtin_ia32_addsubpd
((__v2df
)__X
, (__v2df
)__Y
);
66 #
Return 1 if ssse3 instructions can be compiled.
67 proc check_effective_target_ssse3
{ } {
68 return [check_no_compiler_messages ssse3 object
{
69 typedef long long __m128i __attribute__
((__vector_size__
(16)));
70 typedef
int __v4si __attribute__
((__vector_size__
(16)));
72 __m128i _mm_abs_epi32
(__m128i __X
)
74 return (__m128i
) __builtin_ia32_pabsd128
((__v4si
)__X
);
79 #
Return 1 if aes instructions can be compiled.
80 proc check_effective_target_aes
{ } {
81 return [check_no_compiler_messages aes object
{
82 typedef long long __m128i __attribute__
((__vector_size__
(16)));
83 typedef long long __v2di __attribute__
((__vector_size__
(16)));
85 __m128i _mm_aesimc_si128
(__m128i __X
)
87 return (__m128i
) __builtin_ia32_aesimc128
((__v2di
)__X
);
92 #
Return 1 if vaes instructions can be compiled.
93 proc check_effective_target_vaes
{ } {
94 return [check_no_compiler_messages vaes object
{
95 typedef long long __m128i __attribute__
((__vector_size__
(16)));
96 typedef long long __v2di __attribute__
((__vector_size__
(16)));
98 __m128i _mm_aesimc_si128
(__m128i __X
)
100 return (__m128i
) __builtin_ia32_aesimc128
((__v2di
)__X
);
102 } "-O2 -maes -mavx" ]
105 #
Return 1 if pclmul instructions can be compiled.
106 proc check_effective_target_pclmul
{ } {
107 return [check_no_compiler_messages pclmul object
{
108 typedef long long __m128i __attribute__
((__vector_size__
(16)));
109 typedef long long __v2di __attribute__
((__vector_size__
(16)));
111 __m128i pclmulqdq_test
(__m128i __X
, __m128i __Y
)
113 return (__m128i
) __builtin_ia32_pclmulqdq128
((__v2di
)__X
,
120 #
Return 1 if vpclmul instructions can be compiled.
121 proc check_effective_target_vpclmul
{ } {
122 return [check_no_compiler_messages vpclmul object
{
123 typedef long long __m128i __attribute__
((__vector_size__
(16)));
124 typedef long long __v2di __attribute__
((__vector_size__
(16)));
126 __m128i pclmulqdq_test
(__m128i __X
, __m128i __Y
)
128 return (__m128i
) __builtin_ia32_pclmulqdq128
((__v2di
)__X
,
132 } "-O2 -mpclmul -mavx" ]
135 #
Return 1 if sse4a instructions can be compiled.
136 proc check_effective_target_sse4a
{ } {
137 return [check_no_compiler_messages sse4a object
{
138 typedef long long __m128i __attribute__
((__vector_size__
(16)));
139 typedef long long __v2di __attribute__
((__vector_size__
(16)));
141 __m128i _mm_insert_si64
(__m128i __X
,__m128i __Y
)
143 return (__m128i
) __builtin_ia32_insertq
((__v2di
)__X
, (__v2di
)__Y
);
148 #
Return 1 if fma4 instructions can be compiled.
149 proc check_effective_target_fma4
{ } {
150 return [check_no_compiler_messages fma4 object
{
151 typedef float __m128 __attribute__
((__vector_size__
(16)));
152 typedef float __v4sf __attribute__
((__vector_size__
(16)));
153 __m128 _mm_macc_ps
(__m128 __A
, __m128 __B
, __m128 __C
)
155 return (__m128
) __builtin_ia32_vfmaddps
((__v4sf
)__A
,
162 #
Return 1 if fma instructions can be compiled.
163 proc check_effective_target_fma
{ } {
164 return [check_no_compiler_messages fma object
{
165 typedef float __m128 __attribute__
((__vector_size__
(16)));
166 typedef float __v4sf __attribute__
((__vector_size__
(16)));
167 __m128 _mm_macc_ps
(__m128 __A
, __m128 __B
, __m128 __C
)
169 return (__m128
) __builtin_ia32_vfmaddps
((__v4sf
)__A
,
176 #
Return 1 if xop instructions can be compiled.
177 proc check_effective_target_xop
{ } {
178 return [check_no_compiler_messages xop object
{
179 typedef long long __m128i __attribute__
((__vector_size__
(16)));
180 typedef short __v8hi __attribute__
((__vector_size__
(16)));
181 __m128i _mm_maccs_epi16
(__m128i __A
, __m128i __B
, __m128i __C
)
183 return (__m128i
) __builtin_ia32_vpmacssww
((__v8hi
)__A
,
190 #
Return 1 if lzcnt instruction can be compiled.
191 proc check_effective_target_lzcnt
{ } {
192 return [check_no_compiler_messages lzcnt object
{
193 unsigned short _lzcnt
(unsigned short __X
)
195 return __builtin_clzs
(__X
);
200 #
Return 1 if bmi instructions can be compiled.
201 proc check_effective_target_bmi
{ } {
202 return [check_no_compiler_messages bmi object
{
203 unsigned
int __bextr_u32
(unsigned
int __X
, unsigned
int __Y
)
205 return __builtin_ia32_bextr_u32
(__X
, __Y
);
210 #
Return 1 if ADX instructions can be compiled.
211 proc check_effective_target_adx
{ } {
212 return [check_no_compiler_messages adx object
{
214 _adxcarry_u32
(unsigned char __CF
, unsigned
int __X
,
215 unsigned
int __Y
, unsigned
int *__P
)
217 return __builtin_ia32_addcarryx_u32
(__CF
, __X
, __Y
, __P
);
222 #
Return 1 if rtm instructions can be compiled.
223 proc check_effective_target_rtm
{ } {
224 return [check_no_compiler_messages rtm object
{
228 return __builtin_ia32_xend
();
233 #
Return 1 if avx512f instructions can be compiled.
234 proc check_effective_target_avx512f
{ } {
235 return [check_no_compiler_messages avx512f object
{
236 typedef long long __v8di __attribute__
((__vector_size__
(64)));
238 mm512_and_epi64
(__v8di __X
, __v8di __Y
)
240 return __builtin_ia32_pandq512_mask
(__X
, __Y
, __X
, -1);
245 #
Return 1 if avx512vl instructions can be compiled.
246 proc check_effective_target_avx512vl
{ } {
247 return [check_no_compiler_messages avx512vl object
{
248 typedef long long __v4di __attribute__
((__vector_size__
(32)));
250 mm256_and_epi64
(__v4di __X
, __v4di __Y
)
253 return __builtin_ia32_pandq256_mask
(__X
, __Y
, __W
, -1);
258 #
Return 1 if avx512cd instructions can be compiled.
259 proc check_effective_target_avx512cd
{ } {
260 return [check_no_compiler_messages avx512cd_trans object
{
261 typedef long long __v8di __attribute__
((__vector_size__
(64)));
263 _mm512_conflict_epi64
(__v8di __W
, __v8di __A
)
265 return (__v8di
) __builtin_ia32_vpconflictdi_512_mask
((__v8di
) __A
,
269 } "-Wno-psabi -mavx512cd" ]
272 #
Return 1 if avx512er instructions can be compiled.
273 proc check_effective_target_avx512er
{ } {
274 return [check_no_compiler_messages avx512er_trans object
{
275 typedef float __v16sf __attribute__
((__vector_size__
(64)));
277 mm512_exp2a23_ps
(__v16sf __X
)
279 return __builtin_ia32_exp2ps_mask
(__X
, __X
, -1, 4);
281 } "-Wno-psabi -mavx512er" ]
284 #
Return 1 if sha instructions can be compiled.
285 proc check_effective_target_sha
{ } {
286 return [check_no_compiler_messages sha object
{
287 typedef long long __m128i __attribute__
((__vector_size__
(16)));
288 typedef
int __v4si __attribute__
((__vector_size__
(16)));
290 __m128i _mm_sha1msg1_epu32
(__m128i __X
, __m128i __Y
)
292 return (__m128i
) __builtin_ia32_sha1msg1
((__v4si
)__X
,
298 #
Return 1 if avx512dq instructions can be compiled.
299 proc check_effective_target_avx512dq
{ } {
300 return [check_no_compiler_messages avx512dq object
{
301 typedef long long __v8di __attribute__
((__vector_size__
(64)));
303 _mm512_mask_mullo_epi64
(__v8di __W
, __v8di __A
, __v8di __B
)
305 return (__v8di
) __builtin_ia32_pmullq512_mask
((__v8di
) __A
,
313 #
Return 1 if avx512bw instructions can be compiled.
314 proc check_effective_target_avx512bw
{ } {
315 return [check_no_compiler_messages avx512bw object
{
316 typedef short __v32hi __attribute__
((__vector_size__
(64)));
318 _mm512_mask_mulhrs_epi16
(__v32hi __W
, __v32hi __A
, __v32hi __B
)
320 return (__v32hi
) __builtin_ia32_pmulhrsw512_mask
((__v32hi
) __A
,
328 #
Return 1 if avx512ifma instructions can be compiled.
329 proc check_effective_target_avx512ifma
{ } {
330 return [check_no_compiler_messages avx512ifma object
{
331 typedef long long __v8di __attribute__
((__vector_size__
(64)));
333 _mm512_madd52lo_epu64
(__v8di __X
, __v8di __Y
, __v8di __Z
)
335 return (__v8di
) __builtin_ia32_vpmadd52luq512_mask
((__v8di
) __X
,
343 #
Return 1 if avx512vbmi instructions can be compiled.
344 proc check_effective_target_avx512vbmi
{ } {
345 return [check_no_compiler_messages avx512vbmi object
{
346 typedef char __v64qi __attribute__
((__vector_size__
(64)));
348 _mm512_multishift_epi64_epi8
(__v64qi __X
, __v64qi __Y
)
350 return (__v64qi
) __builtin_ia32_vpmultishiftqb512_mask
((__v64qi
) __X
,
358 #
Return 1 if avx512_4fmaps instructions can be compiled.
359 proc check_effective_target_avx5124fmaps
{ } {
360 return [check_no_compiler_messages avx5124fmaps object
{
361 typedef float __v16sf __attribute__
((__vector_size__
(64)));
362 typedef float __v4sf __attribute__
((__vector_size__
(16)));
365 _mm512_mask_4fmadd_ps
(__v16sf __DEST
, __v16sf __A
, __v16sf __B
, __v16sf __C
,
366 __v16sf __D
, __v16sf __E
, __v4sf
*__F
)
368 return (__v16sf
) __builtin_ia32_4fmaddps_mask
((__v16sf
) __A
,
373 (const __v4sf
*) __F
,
380 #
Return 1 if avx512_4vnniw instructions can be compiled.
381 proc check_effective_target_avx5124vnniw
{ } {
382 return [check_no_compiler_messages avx5124vnniw object
{
383 typedef
int __v16si __attribute__
((__vector_size__
(64)));
384 typedef
int __v4si __attribute__
((__vector_size__
(16)));
387 _mm512_4dpwssd_epi32
(__v16si __A
, __v16si __B
, __v16si __C
,
388 __v16si __D
, __v16si __E
, __v4si
*__F
)
390 return (__v16si
) __builtin_ia32_vp4dpwssd
((__v16si
) __B
,
395 (const __v4si
*) __F
);
400 #
Return 1 if avx512_vpopcntdq instructions can be compiled.
401 proc check_effective_target_avx512vpopcntdq
{ } {
402 return [check_no_compiler_messages avx512vpopcntdq object
{
403 typedef
int __v16si __attribute__
((__vector_size__
(64)));
406 _mm512_popcnt_epi32
(__v16si __A
)
408 return (__v16si
) __builtin_ia32_vpopcountd_v16si
((__v16si
) __A
);
410 } "-mavx512vpopcntdq" ]
413 #
Return 1 if 128 or
256-bit avx512_vpopcntdq instructions can be compiled.
414 proc check_effective_target_avx512vpopcntdqvl
{ } {
415 return [check_no_compiler_messages avx512vpopcntdqvl object
{
416 typedef
int __v8si __attribute__
((__vector_size__
(32)));
419 _mm256_popcnt_epi32
(__v8si __A
)
421 return (__v8si
) __builtin_ia32_vpopcountd_v8si
((__v8si
) __A
);
423 } "-mavx512vpopcntdq -mavx512vl" ]
426 #
Return 1 if gfni instructions can be compiled.
427 proc check_effective_target_gfni
{ } {
428 return [check_no_compiler_messages gfni object
{
429 typedef char __v16qi __attribute__
((__vector_size__
(16)));
432 _mm_gf2p8affineinv_epi64_epi8
(__v16qi __A
, __v16qi __B
, const
int __C
)
434 return (__v16qi
) __builtin_ia32_vgf2p8affineinvqb_v16qi
((__v16qi
) __A
,
441 #
Return 1 if avx512vbmi2 instructions can be compiled.
442 proc check_effective_target_avx512vbmi2
{ } {
443 return [check_no_compiler_messages avx512vbmi2 object
{
444 typedef char __v16qi __attribute__
((__vector_size__
(16)));
445 typedef unsigned long long __mmask16
;
448 _mm_mask_compress_epi8
(__v16qi __A
, __mmask16 __B
, __v16qi __C
)
450 return (__v16qi
) __builtin_ia32_compressqi128_mask
((__v16qi
)__C
,
454 } "-mavx512vbmi2 -mavx512vl" ]
457 #
Return 1 if avx512vbmi2 instructions can be compiled.
458 proc check_effective_target_avx512vnni
{ } {
459 return [check_no_compiler_messages avx512vnni object
{
460 typedef
int __v16si __attribute__
((__vector_size__
(64)));
463 _mm_mask_compress_epi8
(__v16si __A
, __v16si __B
, __v16si __C
)
465 return (__v16si
) __builtin_ia32_vpdpbusd_v16si
((__v16si
)__A
,
469 } "-mavx512vnni -mavx512f" ]
472 #
Return 1 if vaes instructions can be compiled.
473 proc check_effective_target_avx512vaes
{ } {
474 return [check_no_compiler_messages avx512vaes object
{
476 typedef
int __v16si __attribute__
((__vector_size__
(64)));
479 _mm256_aesdec_epi128
(__v32qi __A
, __v32qi __B
)
481 return (__v32qi
)__builtin_ia32_vaesdec_v32qi
((__v32qi
) __A
, (__v32qi
) __B
);
486 #
Return 1 if vpclmulqdq instructions can be compiled.
487 proc check_effective_target_vpclmulqdq
{ } {
488 return [check_no_compiler_messages vpclmulqdq object
{
489 typedef long long __v4di __attribute__
((__vector_size__
(32)));
492 _mm256_clmulepi64_epi128
(__v4di __A
, __v4di __B
)
494 return (__v4di
) __builtin_ia32_vpclmulqdq_v4di
(__A
, __B
, 0);
496 } "-mvpclmulqdq -mavx512vl" ]
499 #
Return 1 if avx512_bitalg instructions can be compiled.
500 proc check_effective_target_avx512bitalg
{ } {
501 return [check_no_compiler_messages avx512bitalg object
{
502 typedef
int __v32hi __attribute__
((__vector_size__
(64)));
505 _mm512_popcnt_epi16
(__v32hi __A
)
507 return (__v32hi
) __builtin_ia32_vpopcountd_v32hi
((__v32hi
) __A
);
512 #
If a testcase doesn
't have special options, use these.
513 global DEFAULT_CFLAGS
514 if ![info exists DEFAULT_CFLAGS] then {
515 set DEFAULT_CFLAGS " -ansi -pedantic-errors"
523 # Special case compilation of vect
-args.c so we don
't have to
524 # replicate it 16 times.
525 if [runtest_file_p $runtests $srcdir/$subdir/vect-args.c] {
526 foreach type { "" -mmmx -m3dnow -msse -msse2 -mavx -mavx2 -mavx512f } {
527 foreach level { "" -O } {
528 set flags "$type $level"
529 verbose -log "Testing vect-args, $flags" 1
530 dg-test $srcdir/$subdir/vect-args.c $flags ""
536 set tests [lsort [glob -nocomplain $srcdir/$subdir/*.\[cS\]]]
537 set tests [prune $tests $srcdir/$subdir/vect-args.c]
540 dg-runtest $tests "" $DEFAULT_CFLAGS