From 4924c7a2b5e3b32512914e9cb527122640964b3f Mon Sep 17 00:00:00 2001 From: Michael Zuckerman Date: Tue, 23 Feb 2016 14:23:53 +0000 Subject: [PATCH] [CLANG] [AVX512] [BUILTIN] Adding pro{lv|r}{d|q}{128|256|512} builtin to clang Adding closer to the end of macro }->}) Differential Revision: http://reviews.llvm.org/D17506 llvm-svn: 261638 --- clang/lib/Headers/avx512fintrin.h | 12 ++++++------ clang/lib/Headers/avx512vlintrin.h | 24 ++++++++++++------------ 2 files changed, 18 insertions(+), 18 deletions(-) diff --git a/clang/lib/Headers/avx512fintrin.h b/clang/lib/Headers/avx512fintrin.h index 8399731..db5380a 100644 --- a/clang/lib/Headers/avx512fintrin.h +++ b/clang/lib/Headers/avx512fintrin.h @@ -3426,40 +3426,40 @@ __builtin_ia32_prord512_mask ((__v16si)( __A),( __B),\ (__v16si)\ _mm512_setzero_si512 (),\ (__mmask16) -1);\ -} +}) #define _mm512_mask_ror_epi32( __W, __U, __A, __B) __extension__ ({ \ __builtin_ia32_prord512_mask ((__v16si)( __A),( __B),\ (__v16si)( __W),\ (__mmask16)( __U));\ -} +}) #define _mm512_maskz_ror_epi32( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prord512_mask ((__v16si)( __A),( __B),\ (__v16si)\ _mm512_setzero_si512 (),\ (__mmask16)( __U));\ -} +}) #define _mm512_ror_epi64( __A, __B) __extension__ ({ \ __builtin_ia32_prorq512_mask ((__v8di)( __A),( __B),\ (__v8di)\ _mm512_setzero_si512 (),\ (__mmask8) -1);\ -} +}) #define _mm512_mask_ror_epi64( __W, __U, __A, __B) __extension__ ({ \ __builtin_ia32_prorq512_mask ((__v8di)( __A),( __B),\ (__v8di)( __W),\ (__mmask8)( __U));\ -} +}) #define _mm512_maskz_ror_epi64( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prorq512_mask ((__v8di)( __A),( __B),\ (__v8di)\ _mm512_setzero_si512 (),\ (__mmask8)( __U));\ -} +}) #undef __DEFAULT_FN_ATTRS diff --git a/clang/lib/Headers/avx512vlintrin.h b/clang/lib/Headers/avx512vlintrin.h index 1c512d1..e08ccdc 100644 --- a/clang/lib/Headers/avx512vlintrin.h +++ b/clang/lib/Headers/avx512vlintrin.h @@ -5140,80 +5140,80 @@ __builtin_ia32_prord128_mask ((__v4si)( __A),( __B),\ (__v4si)\ _mm_setzero_si128 (),\ (__mmask8) -1);\ -} +}) #define _mm_mask_ror_epi32( __W, __U, __A ,__B) __extension__ ({ \ __builtin_ia32_prord128_mask ((__v4si) __A, __B,\ (__v4si)( __W),\ (__mmask8)( __U));\ -} +}) #define _mm_maskz_ror_epi32( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prord128_mask ((__v4si)( __A),( __B),\ (__v4si)\ _mm_setzero_si128 (),\ (__mmask8)( __U));\ -} +}) #define _mm256_ror_epi32( __A, __B) __extension__ ({ \ __builtin_ia32_prord256_mask ((__v8si)( __A),( __B),\ (__v8si)\ _mm256_setzero_si256 (),\ (__mmask8) -1);\ -} +}) #define _mm256_mask_ror_epi32( __W, __U, __A ,__B) __extension__ ({ \ __builtin_ia32_prord256_mask ((__v8si) __A, __B,\ (__v8si)( __W),\ (__mmask8)( __U));\ -} +}) #define _mm256_maskz_ror_epi32( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prord256_mask ((__v8si)( __A),( __B),\ (__v8si)\ _mm256_setzero_si256 (),\ (__mmask8)( __U));\ -} +}) #define _mm_ror_epi64( __A, __B) __extension__ ({ \ __builtin_ia32_prorq128_mask ((__v2di)( __A),( __B),\ (__v2di)\ _mm_setzero_di (),\ (__mmask8) -1);\ -} +}) #define _mm_mask_ror_epi64( __W, __U, __A ,__B) __extension__ ({ \ __builtin_ia32_prorq128_mask ((__v2di) __A, __B,\ (__v2di)( __W),\ (__mmask8)( __U));\ -} +}) #define _mm_maskz_ror_epi64( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prorq128_mask ((__v2di)( __A),( __B),\ (__v2di)\ _mm_setzero_di (),\ (__mmask8)( __U));\ -} +}) #define _mm256_ror_epi64( __A, __B) __extension__ ({ \ __builtin_ia32_prorq256_mask ((__v4di)( __A),( __B),\ (__v4di)\ _mm256_setzero_si256 (),\ (__mmask8) -1);\ -} +}) #define _mm256_mask_ror_epi64( __W, __U, __A ,__B) __extension__ ({ \ __builtin_ia32_prorq256_mask ((__v4di) __A, __B,\ (__v4di)( __W),\ (__mmask8)( __U));\ -} +}) #define _mm256_maskz_ror_epi64( __U, __A, __B) __extension__ ({ \ __builtin_ia32_prorq256_mask ((__v4di)( __A),( __B),\ (__v4di)\ _mm256_setzero_si256 (),\ (__mmask8)( __U));\ -} +}) #undef __DEFAULT_FN_ATTRS -- 2.7.4