PR inline-asm/84742

[official-gcc.git] / gcc / testsuite / gcc.target / i386 / i386.exp

# Copyright (C) 1997-2018 Free Software Foundation, Inc.

# This program is free software; you can redistribute it and/or modify
# it under the terms of the GNU General Public License as published by
# the Free Software Foundation; either version 3 of the License, or
# (at your option) any later version.
# 
# This program is distributed in the hope that it will be useful,
# but WITHOUT ANY WARRANTY; without even the implied warranty of
# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
# GNU General Public License for more details.
# 
# You should have received a copy of the GNU General Public License
# along with GCC; see the file COPYING3.  If not see
# <http://www.gnu.org/licenses/>.

# GCC testsuite that uses the `dg.exp' driver.

# Exit immediately if this isn't a x86 target.
if { ![istarget i?86*-*-*] && ![istarget x86_64-*-*] } then {
  return
}

# Load support procs.
load_lib gcc-dg.exp
load_lib clearcap.exp
load_lib mpx-dg.exp

# Return 1 if attribute ms_hook_prologue is supported.
proc check_effective_target_ms_hook_prologue { } {
    if { [check_no_compiler_messages ms_hook_prologue object {
             void __attribute__ ((__ms_hook_prologue__)) foo ();
         } ""] } {
        return 1
    } else {
        return 0
    }
}

# Return 1 if 3dnow instructions can be compiled.
proc check_effective_target_3dnow { } {
    return [check_no_compiler_messages 3dnow object {
        typedef int __m64 __attribute__ ((__vector_size__ (8)));
        typedef float __v2sf __attribute__ ((__vector_size__ (8)));

        __m64 _m_pfadd (__m64 __A, __m64 __B)
        {
            return (__m64) __builtin_ia32_pfadd ((__v2sf)__A, (__v2sf)__B);
        }
    } "-O2 -m3dnow" ]
}

# Return 1 if sse3 instructions can be compiled.
proc check_effective_target_sse3 { } {
    return [check_no_compiler_messages sse3 object {
        typedef double __m128d __attribute__ ((__vector_size__ (16)));
        typedef double __v2df __attribute__ ((__vector_size__ (16)));

        __m128d _mm_addsub_pd (__m128d __X, __m128d __Y)
        {
            return (__m128d) __builtin_ia32_addsubpd ((__v2df)__X, (__v2df)__Y);
        }
    } "-O2 -msse3" ]
}

# Return 1 if ssse3 instructions can be compiled.
proc check_effective_target_ssse3 { } {
    return [check_no_compiler_messages ssse3 object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef int __v4si __attribute__ ((__vector_size__ (16)));

        __m128i _mm_abs_epi32 (__m128i __X)
        {
            return (__m128i) __builtin_ia32_pabsd128 ((__v4si)__X);
        }
    } "-O2 -mssse3" ]
}

# Return 1 if aes instructions can be compiled.
proc check_effective_target_aes { } {
    return [check_no_compiler_messages aes object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef long long __v2di __attribute__ ((__vector_size__ (16)));

        __m128i _mm_aesimc_si128 (__m128i __X)
        {
            return (__m128i) __builtin_ia32_aesimc128 ((__v2di)__X);
        }
    } "-O2 -maes" ]
}

# Return 1 if vaes instructions can be compiled.
proc check_effective_target_vaes { } {
    return [check_no_compiler_messages vaes object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef long long __v2di __attribute__ ((__vector_size__ (16)));

        __m128i _mm_aesimc_si128 (__m128i __X)
        {
            return (__m128i) __builtin_ia32_aesimc128 ((__v2di)__X);
        }
    } "-O2 -maes -mavx" ]
}

# Return 1 if pclmul instructions can be compiled.
proc check_effective_target_pclmul { } {
    return [check_no_compiler_messages pclmul object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef long long __v2di __attribute__ ((__vector_size__ (16)));

        __m128i pclmulqdq_test (__m128i __X, __m128i __Y)
        {
            return (__m128i) __builtin_ia32_pclmulqdq128 ((__v2di)__X,
                                                          (__v2di)__Y,
                                                          1);
        }
    } "-O2 -mpclmul" ]
}

# Return 1 if vpclmul instructions can be compiled.
proc check_effective_target_vpclmul { } {
    return [check_no_compiler_messages vpclmul object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef long long __v2di __attribute__ ((__vector_size__ (16)));

        __m128i pclmulqdq_test (__m128i __X, __m128i __Y)
        {
            return (__m128i) __builtin_ia32_pclmulqdq128 ((__v2di)__X,
                                                          (__v2di)__Y,
                                                          1);
        }
    } "-O2 -mpclmul -mavx" ]
}

# Return 1 if sse4a instructions can be compiled.
proc check_effective_target_sse4a { } {
    return [check_no_compiler_messages sse4a object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef long long __v2di __attribute__ ((__vector_size__ (16)));

        __m128i _mm_insert_si64 (__m128i __X,__m128i __Y)
        {
            return (__m128i) __builtin_ia32_insertq ((__v2di)__X, (__v2di)__Y);
        }
    } "-O2 -msse4a" ]
}

# Return 1 if fma4 instructions can be compiled.
proc check_effective_target_fma4 { } {
    return [check_no_compiler_messages fma4 object {
        typedef float __m128 __attribute__ ((__vector_size__ (16)));
        typedef float __v4sf __attribute__ ((__vector_size__ (16)));
        __m128 _mm_macc_ps(__m128 __A, __m128 __B, __m128 __C)
        {
            return (__m128) __builtin_ia32_vfmaddps ((__v4sf)__A,
                                                     (__v4sf)__B,
                                                     (__v4sf)__C);
        }
    } "-O2 -mfma4" ]
}

# Return 1 if fma instructions can be compiled.
proc check_effective_target_fma { } {
    return [check_no_compiler_messages fma object {
        typedef float __m128 __attribute__ ((__vector_size__ (16)));
        typedef float __v4sf __attribute__ ((__vector_size__ (16)));
        __m128 _mm_macc_ps(__m128 __A, __m128 __B, __m128 __C)
        {
            return (__m128) __builtin_ia32_vfmaddps ((__v4sf)__A,
                                                     (__v4sf)__B,
                                                     (__v4sf)__C);
        }
    } "-O2 -mfma" ]
}

# Return 1 if xop instructions can be compiled.
proc check_effective_target_xop { } {
    return [check_no_compiler_messages xop object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef short __v8hi __attribute__ ((__vector_size__ (16)));
        __m128i _mm_maccs_epi16(__m128i __A, __m128i __B, __m128i __C)
        {
            return (__m128i) __builtin_ia32_vpmacssww ((__v8hi)__A,
                                                       (__v8hi)__B,
                                                       (__v8hi)__C);
        }
    } "-O2 -mxop" ]
}

# Return 1 if lzcnt instruction can be compiled.
proc check_effective_target_lzcnt { } {
    return [check_no_compiler_messages lzcnt object {
        unsigned short _lzcnt (unsigned short __X)
        {
           return __builtin_clzs (__X);
        }
    } "-mlzcnt" ]
}

# Return 1 if bmi instructions can be compiled.
proc check_effective_target_bmi { } {
    return [check_no_compiler_messages bmi object {
        unsigned int __bextr_u32 (unsigned int __X, unsigned int __Y)
        {
          return __builtin_ia32_bextr_u32 (__X, __Y);
        }
    } "-mbmi" ]
}

# Return 1 if ADX instructions can be compiled.
proc check_effective_target_adx { } {
    return [check_no_compiler_messages adx object {
        unsigned char
        _adxcarry_u32 (unsigned char __CF, unsigned int __X,
                   unsigned int __Y, unsigned int *__P)
        {
            return __builtin_ia32_addcarryx_u32 (__CF, __X, __Y, __P);
        }
    } "-madx" ]
}

# Return 1 if rtm instructions can be compiled.
proc check_effective_target_rtm { } {
    return [check_no_compiler_messages rtm object {
        void
        _rtm_xend (void)
        {
            return __builtin_ia32_xend ();
        }
    } "-mrtm" ]
}

# Return 1 if avx512vl instructions can be compiled.
proc check_effective_target_avx512vl { } {
    return [check_no_compiler_messages avx512vl object {
        typedef long long __v4di __attribute__ ((__vector_size__ (32)));
        __v4di
        mm256_and_epi64  (__v4di __X, __v4di __Y)
        {
            __v4di __W;
            return __builtin_ia32_pandq256_mask (__X, __Y, __W, -1);
        }
    } "-mavx512vl" ]
}

# Return 1 if avx512cd instructions can be compiled.
proc check_effective_target_avx512cd { } {
    return [check_no_compiler_messages avx512cd_trans object {
        typedef long long __v8di __attribute__ ((__vector_size__ (64)));
        __v8di
        _mm512_conflict_epi64 (__v8di __W, __v8di __A)
        {
          return (__v8di) __builtin_ia32_vpconflictdi_512_mask ((__v8di) __A,
                                                                 (__v8di) __W,
                                                                 -1);
        }
   } "-Wno-psabi -mavx512cd" ]
}

# Return 1 if avx512er instructions can be compiled.
proc check_effective_target_avx512er { } {
    return [check_no_compiler_messages avx512er_trans object {
        typedef float __v16sf __attribute__ ((__vector_size__ (64)));
        __v16sf
        mm512_exp2a23_ps  (__v16sf __X)
        {
            return __builtin_ia32_exp2ps_mask (__X, __X, -1, 4);
        }
   } "-Wno-psabi -mavx512er" ]
}

# Return 1 if sha instructions can be compiled.
proc check_effective_target_sha { } {
    return [check_no_compiler_messages sha object {
        typedef long long __m128i __attribute__ ((__vector_size__ (16)));
        typedef int __v4si __attribute__ ((__vector_size__ (16)));

        __m128i _mm_sha1msg1_epu32 (__m128i __X, __m128i __Y)
        {
            return (__m128i) __builtin_ia32_sha1msg1 ((__v4si)__X,
                                                      (__v4si)__Y);
        }
    } "-O2 -msha" ]
}

# Return 1 if avx512dq instructions can be compiled.
proc check_effective_target_avx512dq { } {
    return [check_no_compiler_messages avx512dq object {
        typedef long long __v8di __attribute__ ((__vector_size__ (64)));
        __v8di
        _mm512_mask_mullo_epi64 (__v8di __W, __v8di __A, __v8di __B)
        {
            return (__v8di) __builtin_ia32_pmullq512_mask ((__v8di) __A,
                                                            (__v8di) __B,
                                                            (__v8di) __W,
                                                            -1);
        }
    } "-mavx512dq" ]
}

# Return 1 if avx512bw instructions can be compiled.
proc check_effective_target_avx512bw { } {
    return [check_no_compiler_messages avx512bw object {
        typedef short __v32hi __attribute__ ((__vector_size__ (64)));
        __v32hi
        _mm512_mask_mulhrs_epi16 (__v32hi __W, __v32hi __A, __v32hi __B)
        {
            return (__v32hi) __builtin_ia32_pmulhrsw512_mask ((__v32hi) __A,
                                                            (__v32hi) __B,
                                                            (__v32hi) __W,
                                                            -1);
        }
    } "-mavx512bw" ]
}

# Return 1 if avx512ifma instructions can be compiled.
proc check_effective_target_avx512ifma { } {
    return [check_no_compiler_messages avx512ifma object {
        typedef long long __v8di __attribute__ ((__vector_size__ (64)));
        __v8di
        _mm512_madd52lo_epu64 (__v8di __X, __v8di __Y, __v8di __Z)
        {
          return (__v8di) __builtin_ia32_vpmadd52luq512_mask ((__v8di) __X,
                                                               (__v8di) __Y,
                                                               (__v8di) __Z,
                                                               -1);
        }
    } "-mavx512ifma" ]
}

# Return 1 if avx512vbmi instructions can be compiled.
proc check_effective_target_avx512vbmi { } {
    return [check_no_compiler_messages avx512vbmi object {
        typedef char __v64qi __attribute__ ((__vector_size__ (64)));
        __v64qi
        _mm512_multishift_epi64_epi8 (__v64qi __X, __v64qi __Y)
        {
          return (__v64qi) __builtin_ia32_vpmultishiftqb512_mask ((__v64qi) __X,
                                                                 (__v64qi) __Y,
                                                                 (__v64qi) __Y,
                                                                 -1);
        }
    } "-mavx512vbmi" ]
}

# Return 1 if avx512_4fmaps instructions can be compiled.
proc check_effective_target_avx5124fmaps { } {
    return [check_no_compiler_messages avx5124fmaps object {
        typedef float __v16sf __attribute__ ((__vector_size__ (64)));
        typedef float __v4sf __attribute__ ((__vector_size__ (16)));

        __v16sf
        _mm512_mask_4fmadd_ps (__v16sf __DEST, __v16sf __A, __v16sf __B, __v16sf __C,
                               __v16sf __D, __v16sf __E, __v4sf *__F)
        {
            return (__v16sf) __builtin_ia32_4fmaddps_mask ((__v16sf) __A,
                                                          (__v16sf) __B,
                                                          (__v16sf) __C,
                                                          (__v16sf) __D,
                                                          (__v16sf) __E,
                                                          (const __v4sf *) __F,
                                                          (__v16sf) __DEST,
                                                          0xffff);
        }
    } "-mavx5124fmaps" ]
}

# Return 1 if avx512_4vnniw instructions can be compiled.
proc check_effective_target_avx5124vnniw { } {
    return [check_no_compiler_messages avx5124vnniw object {
        typedef int __v16si __attribute__ ((__vector_size__ (64)));
        typedef int __v4si __attribute__ ((__vector_size__ (16)));

        __v16si
        _mm512_4dpwssd_epi32 (__v16si __A, __v16si __B, __v16si __C,
                              __v16si __D, __v16si __E, __v4si *__F)
        {
            return (__v16si) __builtin_ia32_vp4dpwssd ((__v16si) __B,
                                                       (__v16si) __C,
                                                       (__v16si) __D,
                                                       (__v16si) __E,
                                                       (__v16si) __A,
                                                       (const __v4si *) __F);
        }
    } "-mavx5124vnniw" ]
}

# Return 1 if avx512_vpopcntdq instructions can be compiled.
proc check_effective_target_avx512vpopcntdq { } {
    return [check_no_compiler_messages avx512vpopcntdq object {
        typedef int __v16si __attribute__ ((__vector_size__ (64)));

        __v16si
        _mm512_popcnt_epi32 (__v16si __A)
        {
            return (__v16si) __builtin_ia32_vpopcountd_v16si ((__v16si) __A);
        }
    } "-mavx512vpopcntdq" ]
}

# Return 1 if 128 or 256-bit avx512_vpopcntdq instructions can be compiled.
proc check_effective_target_avx512vpopcntdqvl { } {
    return [check_no_compiler_messages avx512vpopcntdqvl object {
        typedef int __v8si __attribute__ ((__vector_size__ (32)));

        __v8si
        _mm256_popcnt_epi32 (__v8si __A)
        {
            return (__v8si) __builtin_ia32_vpopcountd_v8si ((__v8si) __A);
        }
    } "-mavx512vpopcntdq -mavx512vl" ]
}

# Return 1 if gfni instructions can be compiled.
proc check_effective_target_gfni { } {
    return [check_no_compiler_messages gfni object {
        typedef char __v16qi __attribute__ ((__vector_size__ (16)));

        __v16qi
        _mm_gf2p8affineinv_epi64_epi8 (__v16qi __A, __v16qi __B, const int __C)
        {
            return (__v16qi) __builtin_ia32_vgf2p8affineinvqb_v16qi ((__v16qi) __A,
                                                                     (__v16qi) __B,
                                                                      0);
        }
    } "-mgfni" ]
}

# Return 1 if avx512vbmi2 instructions can be compiled.
proc check_effective_target_avx512vbmi2 { } {
    return [check_no_compiler_messages avx512vbmi2 object {
        typedef char __v16qi __attribute__ ((__vector_size__ (16)));
        typedef unsigned long long __mmask16;

        __v16qi
        _mm_mask_compress_epi8 (__v16qi __A, __mmask16 __B, __v16qi __C)
        {
                return (__v16qi) __builtin_ia32_compressqi128_mask((__v16qi)__C,
                                                                   (__v16qi)__A,
                                                                   (__mmask16)__B);
        }
    } "-mavx512vbmi2 -mavx512vl" ]
}

# Return 1 if avx512vbmi2 instructions can be compiled.
proc check_effective_target_avx512vnni { } {
    return [check_no_compiler_messages avx512vnni object {
        typedef int __v16si __attribute__ ((__vector_size__ (64)));

        __v16si
        _mm_mask_compress_epi8 (__v16si __A, __v16si __B, __v16si __C)
        {
                return (__v16si) __builtin_ia32_vpdpbusd_v16si ((__v16si)__A,
                                                                (__v16si)__B,
                                                                (__v16si)__C);
        }
    } "-mavx512vnni -mavx512f" ]
}

# Return 1 if vaes instructions can be compiled.
proc check_effective_target_avx512vaes { } {
    return [check_no_compiler_messages avx512vaes object {

        typedef int __v16si __attribute__ ((__vector_size__ (64)));

        __v32qi
        _mm256_aesdec_epi128 (__v32qi __A, __v32qi __B)
        {
          return (__v32qi)__builtin_ia32_vaesdec_v32qi ((__v32qi) __A, (__v32qi) __B);
        }
    } "-mvaes" ]
}

# Return 1 if vpclmulqdq instructions can be compiled.
proc check_effective_target_vpclmulqdq { } {
    return [check_no_compiler_messages vpclmulqdq object {
        typedef long long __v4di __attribute__ ((__vector_size__ (32)));

        __v4di
        _mm256_clmulepi64_epi128 (__v4di __A, __v4di __B)
        {
            return (__v4di) __builtin_ia32_vpclmulqdq_v4di (__A, __B, 0);
        }
    } "-mvpclmulqdq -mavx512vl" ]
}

# Return 1 if avx512_bitalg instructions can be compiled.
proc check_effective_target_avx512bitalg { } {
    return [check_no_compiler_messages avx512bitalg object {
        typedef short int __v32hi __attribute__ ((__vector_size__ (64)));

        __v32hi
        _mm512_popcnt_epi16 (__v32hi __A)
        {
            return (__v32hi) __builtin_ia32_vpopcountw_v32hi ((__v32hi) __A);
        }
    } "-mavx512bitalg" ]
}

# If a testcase doesn't have special options, use these.
global DEFAULT_CFLAGS
if ![info exists DEFAULT_CFLAGS] then {
    set DEFAULT_CFLAGS " -ansi -pedantic-errors"
}

# Initialize `dg'.
dg-init
clearcap-init

global runtests
# Special case compilation of vect-args.c so we don't have to
# replicate it 16 times.
if [runtest_file_p $runtests $srcdir/$subdir/vect-args.c] {
  foreach type { "" -mmmx -m3dnow -msse -msse2 -mavx -mavx2 -mavx512f } {
    foreach level { "" -O } {
      set flags "$type $level"
      verbose -log "Testing vect-args, $flags" 1
      dg-test $srcdir/$subdir/vect-args.c $flags ""
    }
  }
}

# Everything else.
set tests [lsort [glob -nocomplain $srcdir/$subdir/*.\[cS\]]]
set tests [prune $tests $srcdir/$subdir/vect-args.c]

# Main loop.
dg-runtest $tests "" $DEFAULT_CFLAGS

# All done.
clearcap-finish
dg-finish