Commit b5fd0b71 by Jakub Jelinek Committed by Jakub Jelinek

rdseedintrin.h (_rdseed16_step, [...]): Uglify argument names and/or local…

rdseedintrin.h (_rdseed16_step, [...]): Uglify argument names and/or local variable names in inline functions.

	* config/i386/rdseedintrin.h (_rdseed16_step, _rdseed32_step,
	_rdseed64_step): Uglify argument names and/or local variable names
	in inline functions.
	* config/i386/rtmintrin.h (_xabort): Likewise.
	* config/i386/avx512vlintrin.h (_mm256_ternarylogic_epi64,
	_mm256_mask_ternarylogic_epi64, _mm256_maskz_ternarylogic_epi64,
	_mm256_ternarylogic_epi32, _mm256_mask_ternarylogic_epi32,
	_mm256_maskz_ternarylogic_epi32, _mm_ternarylogic_epi64,
	_mm_mask_ternarylogic_epi64, _mm_maskz_ternarylogic_epi64,
	_mm_ternarylogic_epi32, _mm_mask_ternarylogic_epi32,
	_mm_maskz_ternarylogic_epi32): Likewise.
	* config/i386/lwpintrin.h (__llwpcb, __lwpval32, __lwpval64,
	__lwpins32, __lwpins64): Likewise.
	* config/i386/avx2intrin.h (_mm_i32gather_pd, _mm_mask_i32gather_pd,
	_mm256_i32gather_pd, _mm256_mask_i32gather_pd, _mm_i64gather_pd,
	_mm_mask_i64gather_pd, _mm256_i64gather_pd, _mm256_mask_i64gather_pd,
	_mm_i32gather_ps, _mm_mask_i32gather_ps, _mm256_i32gather_ps,
	_mm256_mask_i32gather_ps, _mm_i64gather_ps, _mm_mask_i64gather_ps,
	_mm256_i64gather_ps, _mm256_mask_i64gather_ps, _mm_i32gather_epi64,
	_mm_mask_i32gather_epi64, _mm256_i32gather_epi64,
	_mm256_mask_i32gather_epi64, _mm_i64gather_epi64,
	_mm_mask_i64gather_epi64, _mm256_i64gather_epi64,
	_mm256_mask_i64gather_epi64, _mm_i32gather_epi32,
	_mm_mask_i32gather_epi32, _mm256_i32gather_epi32,
	_mm256_mask_i32gather_epi32, _mm_i64gather_epi32,
	_mm_mask_i64gather_epi32, _mm256_i64gather_epi32,
	_mm256_mask_i64gather_epi32): Likewise.
	* config/i386/pmm_malloc.h (_mm_malloc, _mm_free): Likewise.
	* config/i386/ia32intrin.h (__writeeflags): Likewise.
	* config/i386/pkuintrin.h (_wrpkru): Likewise.
	* config/i386/avx512pfintrin.h (_mm512_mask_prefetch_i32gather_pd,
	_mm512_mask_prefetch_i32gather_ps, _mm512_mask_prefetch_i64gather_pd,
	_mm512_mask_prefetch_i64gather_ps, _mm512_prefetch_i32scatter_pd,
	_mm512_prefetch_i32scatter_ps, _mm512_mask_prefetch_i32scatter_pd,
	_mm512_mask_prefetch_i32scatter_ps, _mm512_prefetch_i64scatter_pd,
	_mm512_prefetch_i64scatter_ps, _mm512_mask_prefetch_i64scatter_pd,
	_mm512_mask_prefetch_i64scatter_ps): Likewise.
	* config/i386/gmm_malloc.h (_mm_malloc, _mm_free): Likewise.
	* config/i386/avx512fintrin.h (_mm512_ternarylogic_epi64,
	_mm512_mask_ternarylogic_epi64, _mm512_maskz_ternarylogic_epi64,
	_mm512_ternarylogic_epi32, _mm512_mask_ternarylogic_epi32,
	_mm512_maskz_ternarylogic_epi32, _mm512_i32gather_ps,
	_mm512_mask_i32gather_ps, _mm512_i32gather_pd, _mm512_i64gather_ps,
	_mm512_i64gather_pd, _mm512_i32gather_epi32, _mm512_i32gather_epi64,
	_mm512_i64gather_epi32, _mm512_i64gather_epi64): Likewise.

From-SVN: r239617
parent 31c2bc2e
2016-08-19 Jakub Jelinek <jakub@redhat.com> 2016-08-19 Jakub Jelinek <jakub@redhat.com>
* config/i386/rdseedintrin.h (_rdseed16_step, _rdseed32_step,
_rdseed64_step): Uglify argument names and/or local variable names
in inline functions.
* config/i386/rtmintrin.h (_xabort): Likewise.
* config/i386/avx512vlintrin.h (_mm256_ternarylogic_epi64,
_mm256_mask_ternarylogic_epi64, _mm256_maskz_ternarylogic_epi64,
_mm256_ternarylogic_epi32, _mm256_mask_ternarylogic_epi32,
_mm256_maskz_ternarylogic_epi32, _mm_ternarylogic_epi64,
_mm_mask_ternarylogic_epi64, _mm_maskz_ternarylogic_epi64,
_mm_ternarylogic_epi32, _mm_mask_ternarylogic_epi32,
_mm_maskz_ternarylogic_epi32): Likewise.
* config/i386/lwpintrin.h (__llwpcb, __lwpval32, __lwpval64,
__lwpins32, __lwpins64): Likewise.
* config/i386/avx2intrin.h (_mm_i32gather_pd, _mm_mask_i32gather_pd,
_mm256_i32gather_pd, _mm256_mask_i32gather_pd, _mm_i64gather_pd,
_mm_mask_i64gather_pd, _mm256_i64gather_pd, _mm256_mask_i64gather_pd,
_mm_i32gather_ps, _mm_mask_i32gather_ps, _mm256_i32gather_ps,
_mm256_mask_i32gather_ps, _mm_i64gather_ps, _mm_mask_i64gather_ps,
_mm256_i64gather_ps, _mm256_mask_i64gather_ps, _mm_i32gather_epi64,
_mm_mask_i32gather_epi64, _mm256_i32gather_epi64,
_mm256_mask_i32gather_epi64, _mm_i64gather_epi64,
_mm_mask_i64gather_epi64, _mm256_i64gather_epi64,
_mm256_mask_i64gather_epi64, _mm_i32gather_epi32,
_mm_mask_i32gather_epi32, _mm256_i32gather_epi32,
_mm256_mask_i32gather_epi32, _mm_i64gather_epi32,
_mm_mask_i64gather_epi32, _mm256_i64gather_epi32,
_mm256_mask_i64gather_epi32): Likewise.
* config/i386/pmm_malloc.h (_mm_malloc, _mm_free): Likewise.
* config/i386/ia32intrin.h (__writeeflags): Likewise.
* config/i386/pkuintrin.h (_wrpkru): Likewise.
* config/i386/avx512pfintrin.h (_mm512_mask_prefetch_i32gather_pd,
_mm512_mask_prefetch_i32gather_ps, _mm512_mask_prefetch_i64gather_pd,
_mm512_mask_prefetch_i64gather_ps, _mm512_prefetch_i32scatter_pd,
_mm512_prefetch_i32scatter_ps, _mm512_mask_prefetch_i32scatter_pd,
_mm512_mask_prefetch_i32scatter_ps, _mm512_prefetch_i64scatter_pd,
_mm512_prefetch_i64scatter_ps, _mm512_mask_prefetch_i64scatter_pd,
_mm512_mask_prefetch_i64scatter_ps): Likewise.
* config/i386/gmm_malloc.h (_mm_malloc, _mm_free): Likewise.
* config/i386/avx512fintrin.h (_mm512_ternarylogic_epi64,
_mm512_mask_ternarylogic_epi64, _mm512_maskz_ternarylogic_epi64,
_mm512_ternarylogic_epi32, _mm512_mask_ternarylogic_epi32,
_mm512_maskz_ternarylogic_epi32, _mm512_i32gather_ps,
_mm512_mask_i32gather_ps, _mm512_i32gather_pd, _mm512_i64gather_ps,
_mm512_i64gather_pd, _mm512_i32gather_epi32, _mm512_i32gather_epi64,
_mm512_i64gather_epi32, _mm512_i64gather_epi64): Likewise.
* config/i386/fxsrintrin.h (_fxsave): Remove return keyword in inlines * config/i386/fxsrintrin.h (_fxsave): Remove return keyword in inlines
returning void. returning void.
(_fxrstor, _fxsave64, _fxrstor64): Likewise. (_fxrstor, _fxsave64, _fxrstor64): Likewise.
......
...@@ -1246,422 +1246,426 @@ _mm_srlv_epi64 (__m128i __X, __m128i __Y) ...@@ -1246,422 +1246,426 @@ _mm_srlv_epi64 (__m128i __X, __m128i __Y)
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline __m128d extern __inline __m128d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i32gather_pd (double const *base, __m128i index, const int scale) _mm_i32gather_pd (double const *__base, __m128i __index, const int __scale)
{ {
__v2df zero = _mm_setzero_pd (); __v2df __zero = _mm_setzero_pd ();
__v2df mask = _mm_cmpeq_pd (zero, zero); __v2df __mask = _mm_cmpeq_pd (__zero, __zero);
return (__m128d) __builtin_ia32_gathersiv2df (_mm_undefined_pd (), return (__m128d) __builtin_ia32_gathersiv2df (_mm_undefined_pd (),
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128d extern __inline __m128d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i32gather_pd (__m128d src, double const *base, __m128i index, _mm_mask_i32gather_pd (__m128d __src, double const *__base, __m128i __index,
__m128d mask, const int scale) __m128d __mask, const int __scale)
{ {
return (__m128d) __builtin_ia32_gathersiv2df ((__v2df)src, return (__m128d) __builtin_ia32_gathersiv2df ((__v2df)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v2df)mask, (__v2df)__mask,
scale); __scale);
} }
extern __inline __m256d extern __inline __m256d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i32gather_pd (double const *base, __m128i index, const int scale) _mm256_i32gather_pd (double const *__base, __m128i __index, const int __scale)
{ {
__v4df zero = _mm256_setzero_pd (); __v4df __zero = _mm256_setzero_pd ();
__v4df mask = _mm256_cmp_pd (zero, zero, _CMP_EQ_OQ); __v4df __mask = _mm256_cmp_pd (__zero, __zero, _CMP_EQ_OQ);
return (__m256d) __builtin_ia32_gathersiv4df (_mm256_undefined_pd (), return (__m256d) __builtin_ia32_gathersiv4df (_mm256_undefined_pd (),
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256d extern __inline __m256d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i32gather_pd (__m256d src, double const *base, _mm256_mask_i32gather_pd (__m256d __src, double const *__base,
__m128i index, __m256d mask, const int scale) __m128i __index, __m256d __mask, const int __scale)
{ {
return (__m256d) __builtin_ia32_gathersiv4df ((__v4df)src, return (__m256d) __builtin_ia32_gathersiv4df ((__v4df)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v4df)mask, (__v4df)__mask,
scale); __scale);
} }
extern __inline __m128d extern __inline __m128d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i64gather_pd (double const *base, __m128i index, const int scale) _mm_i64gather_pd (double const *__base, __m128i __index, const int __scale)
{ {
__v2df src = _mm_setzero_pd (); __v2df __src = _mm_setzero_pd ();
__v2df mask = _mm_cmpeq_pd (src, src); __v2df __mask = _mm_cmpeq_pd (__src, __src);
return (__m128d) __builtin_ia32_gatherdiv2df (src, return (__m128d) __builtin_ia32_gatherdiv2df (__src,
base, __base,
(__v2di)index, (__v2di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128d extern __inline __m128d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i64gather_pd (__m128d src, double const *base, __m128i index, _mm_mask_i64gather_pd (__m128d __src, double const *__base, __m128i __index,
__m128d mask, const int scale) __m128d __mask, const int __scale)
{ {
return (__m128d) __builtin_ia32_gatherdiv2df ((__v2df)src, return (__m128d) __builtin_ia32_gatherdiv2df ((__v2df)__src,
base, __base,
(__v2di)index, (__v2di)__index,
(__v2df)mask, (__v2df)__mask,
scale); __scale);
} }
extern __inline __m256d extern __inline __m256d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i64gather_pd (double const *base, __m256i index, const int scale) _mm256_i64gather_pd (double const *__base, __m256i __index, const int __scale)
{ {
__v4df src = _mm256_setzero_pd (); __v4df __src = _mm256_setzero_pd ();
__v4df mask = _mm256_cmp_pd (src, src, _CMP_EQ_OQ); __v4df __mask = _mm256_cmp_pd (__src, __src, _CMP_EQ_OQ);
return (__m256d) __builtin_ia32_gatherdiv4df (src, return (__m256d) __builtin_ia32_gatherdiv4df (__src,
base, __base,
(__v4di)index, (__v4di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256d extern __inline __m256d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i64gather_pd (__m256d src, double const *base, _mm256_mask_i64gather_pd (__m256d __src, double const *__base,
__m256i index, __m256d mask, const int scale) __m256i __index, __m256d __mask, const int __scale)
{ {
return (__m256d) __builtin_ia32_gatherdiv4df ((__v4df)src, return (__m256d) __builtin_ia32_gatherdiv4df ((__v4df)__src,
base, __base,
(__v4di)index, (__v4di)__index,
(__v4df)mask, (__v4df)__mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i32gather_ps (float const *base, __m128i index, const int scale) _mm_i32gather_ps (float const *__base, __m128i __index, const int __scale)
{ {
__v4sf src = _mm_setzero_ps (); __v4sf __src = _mm_setzero_ps ();
__v4sf mask = _mm_cmpeq_ps (src, src); __v4sf __mask = _mm_cmpeq_ps (__src, __src);
return (__m128) __builtin_ia32_gathersiv4sf (src, return (__m128) __builtin_ia32_gathersiv4sf (__src,
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i32gather_ps (__m128 src, float const *base, __m128i index, _mm_mask_i32gather_ps (__m128 __src, float const *__base, __m128i __index,
__m128 mask, const int scale) __m128 __mask, const int __scale)
{ {
return (__m128) __builtin_ia32_gathersiv4sf ((__v4sf)src, return (__m128) __builtin_ia32_gathersiv4sf ((__v4sf)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v4sf)mask, (__v4sf)__mask,
scale); __scale);
} }
extern __inline __m256 extern __inline __m256
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i32gather_ps (float const *base, __m256i index, const int scale) _mm256_i32gather_ps (float const *__base, __m256i __index, const int __scale)
{ {
__v8sf src = _mm256_setzero_ps (); __v8sf __src = _mm256_setzero_ps ();
__v8sf mask = _mm256_cmp_ps (src, src, _CMP_EQ_OQ); __v8sf __mask = _mm256_cmp_ps (__src, __src, _CMP_EQ_OQ);
return (__m256) __builtin_ia32_gathersiv8sf (src, return (__m256) __builtin_ia32_gathersiv8sf (__src,
base, __base,
(__v8si)index, (__v8si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256 extern __inline __m256
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i32gather_ps (__m256 src, float const *base, _mm256_mask_i32gather_ps (__m256 __src, float const *__base,
__m256i index, __m256 mask, const int scale) __m256i __index, __m256 __mask, const int __scale)
{ {
return (__m256) __builtin_ia32_gathersiv8sf ((__v8sf)src, return (__m256) __builtin_ia32_gathersiv8sf ((__v8sf)__src,
base, __base,
(__v8si)index, (__v8si)__index,
(__v8sf)mask, (__v8sf)__mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i64gather_ps (float const *base, __m128i index, const int scale) _mm_i64gather_ps (float const *__base, __m128i __index, const int __scale)
{ {
__v4sf src = _mm_setzero_ps (); __v4sf __src = _mm_setzero_ps ();
__v4sf mask = _mm_cmpeq_ps (src, src); __v4sf __mask = _mm_cmpeq_ps (__src, __src);
return (__m128) __builtin_ia32_gatherdiv4sf (src, return (__m128) __builtin_ia32_gatherdiv4sf (__src,
base, __base,
(__v2di)index, (__v2di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i64gather_ps (__m128 src, float const *base, __m128i index, _mm_mask_i64gather_ps (__m128 __src, float const *__base, __m128i __index,
__m128 mask, const int scale) __m128 __mask, const int __scale)
{ {
return (__m128) __builtin_ia32_gatherdiv4sf ((__v4sf)src, return (__m128) __builtin_ia32_gatherdiv4sf ((__v4sf)__src,
base, __base,
(__v2di)index, (__v2di)__index,
(__v4sf)mask, (__v4sf)__mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i64gather_ps (float const *base, __m256i index, const int scale) _mm256_i64gather_ps (float const *__base, __m256i __index, const int __scale)
{ {
__v4sf src = _mm_setzero_ps (); __v4sf __src = _mm_setzero_ps ();
__v4sf mask = _mm_cmpeq_ps (src, src); __v4sf __mask = _mm_cmpeq_ps (__src, __src);
return (__m128) __builtin_ia32_gatherdiv4sf256 (src, return (__m128) __builtin_ia32_gatherdiv4sf256 (__src,
base, __base,
(__v4di)index, (__v4di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128 extern __inline __m128
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i64gather_ps (__m128 src, float const *base, _mm256_mask_i64gather_ps (__m128 __src, float const *__base,
__m256i index, __m128 mask, const int scale) __m256i __index, __m128 __mask, const int __scale)
{ {
return (__m128) __builtin_ia32_gatherdiv4sf256 ((__v4sf)src, return (__m128) __builtin_ia32_gatherdiv4sf256 ((__v4sf)__src,
base, __base,
(__v4di)index, (__v4di)__index,
(__v4sf)mask, (__v4sf)__mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i32gather_epi64 (long long int const *base, _mm_i32gather_epi64 (long long int const *__base,
__m128i index, const int scale) __m128i __index, const int __scale)
{ {
__v2di src = __extension__ (__v2di){ 0, 0 }; __v2di __src = __extension__ (__v2di){ 0, 0 };
__v2di mask = __extension__ (__v2di){ ~0, ~0 }; __v2di __mask = __extension__ (__v2di){ ~0, ~0 };
return (__m128i) __builtin_ia32_gathersiv2di (src, return (__m128i) __builtin_ia32_gathersiv2di (__src,
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i32gather_epi64 (__m128i src, long long int const *base, _mm_mask_i32gather_epi64 (__m128i __src, long long int const *__base,
__m128i index, __m128i mask, const int scale) __m128i __index, __m128i __mask, const int __scale)
{ {
return (__m128i) __builtin_ia32_gathersiv2di ((__v2di)src, return (__m128i) __builtin_ia32_gathersiv2di ((__v2di)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v2di)mask, (__v2di)__mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i32gather_epi64 (long long int const *base, _mm256_i32gather_epi64 (long long int const *__base,
__m128i index, const int scale) __m128i __index, const int __scale)
{ {
__v4di src = __extension__ (__v4di){ 0, 0, 0, 0 }; __v4di __src = __extension__ (__v4di){ 0, 0, 0, 0 };
__v4di mask = __extension__ (__v4di){ ~0, ~0, ~0, ~0 }; __v4di __mask = __extension__ (__v4di){ ~0, ~0, ~0, ~0 };
return (__m256i) __builtin_ia32_gathersiv4di (src, return (__m256i) __builtin_ia32_gathersiv4di (__src,
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i32gather_epi64 (__m256i src, long long int const *base, _mm256_mask_i32gather_epi64 (__m256i __src, long long int const *__base,
__m128i index, __m256i mask, const int scale) __m128i __index, __m256i __mask,
const int __scale)
{ {
return (__m256i) __builtin_ia32_gathersiv4di ((__v4di)src, return (__m256i) __builtin_ia32_gathersiv4di ((__v4di)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v4di)mask, (__v4di)__mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i64gather_epi64 (long long int const *base, _mm_i64gather_epi64 (long long int const *__base,
__m128i index, const int scale) __m128i __index, const int __scale)
{ {
__v2di src = __extension__ (__v2di){ 0, 0 }; __v2di __src = __extension__ (__v2di){ 0, 0 };
__v2di mask = __extension__ (__v2di){ ~0, ~0 }; __v2di __mask = __extension__ (__v2di){ ~0, ~0 };
return (__m128i) __builtin_ia32_gatherdiv2di (src, return (__m128i) __builtin_ia32_gatherdiv2di (__src,
base, __base,
(__v2di)index, (__v2di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i64gather_epi64 (__m128i src, long long int const *base, __m128i index, _mm_mask_i64gather_epi64 (__m128i __src, long long int const *__base,
__m128i mask, const int scale) __m128i __index, __m128i __mask, const int __scale)
{ {
return (__m128i) __builtin_ia32_gatherdiv2di ((__v2di)src, return (__m128i) __builtin_ia32_gatherdiv2di ((__v2di)__src,
base, __base,
(__v2di)index, (__v2di)__index,
(__v2di)mask, (__v2di)__mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i64gather_epi64 (long long int const *base, _mm256_i64gather_epi64 (long long int const *__base,
__m256i index, const int scale) __m256i __index, const int __scale)
{ {
__v4di src = __extension__ (__v4di){ 0, 0, 0, 0 }; __v4di __src = __extension__ (__v4di){ 0, 0, 0, 0 };
__v4di mask = __extension__ (__v4di){ ~0, ~0, ~0, ~0 }; __v4di __mask = __extension__ (__v4di){ ~0, ~0, ~0, ~0 };
return (__m256i) __builtin_ia32_gatherdiv4di (src, return (__m256i) __builtin_ia32_gatherdiv4di (__src,
base, __base,
(__v4di)index, (__v4di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i64gather_epi64 (__m256i src, long long int const *base, _mm256_mask_i64gather_epi64 (__m256i __src, long long int const *__base,
__m256i index, __m256i mask, const int scale) __m256i __index, __m256i __mask,
const int __scale)
{ {
return (__m256i) __builtin_ia32_gatherdiv4di ((__v4di)src, return (__m256i) __builtin_ia32_gatherdiv4di ((__v4di)__src,
base, __base,
(__v4di)index, (__v4di)__index,
(__v4di)mask, (__v4di)__mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i32gather_epi32 (int const *base, __m128i index, const int scale) _mm_i32gather_epi32 (int const *__base, __m128i __index, const int __scale)
{ {
__v4si src = __extension__ (__v4si){ 0, 0, 0, 0 }; __v4si __src = __extension__ (__v4si){ 0, 0, 0, 0 };
__v4si mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 }; __v4si __mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 };
return (__m128i) __builtin_ia32_gathersiv4si (src, return (__m128i) __builtin_ia32_gathersiv4si (__src,
base, __base,
(__v4si)index, (__v4si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i32gather_epi32 (__m128i src, int const *base, __m128i index, _mm_mask_i32gather_epi32 (__m128i __src, int const *__base, __m128i __index,
__m128i mask, const int scale) __m128i __mask, const int __scale)
{ {
return (__m128i) __builtin_ia32_gathersiv4si ((__v4si)src, return (__m128i) __builtin_ia32_gathersiv4si ((__v4si)__src,
base, __base,
(__v4si)index, (__v4si)__index,
(__v4si)mask, (__v4si)__mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i32gather_epi32 (int const *base, __m256i index, const int scale) _mm256_i32gather_epi32 (int const *__base, __m256i __index, const int __scale)
{ {
__v8si src = __extension__ (__v8si){ 0, 0, 0, 0, 0, 0, 0, 0 }; __v8si __src = __extension__ (__v8si){ 0, 0, 0, 0, 0, 0, 0, 0 };
__v8si mask = __extension__ (__v8si){ ~0, ~0, ~0, ~0, ~0, ~0, ~0, ~0 }; __v8si __mask = __extension__ (__v8si){ ~0, ~0, ~0, ~0, ~0, ~0, ~0, ~0 };
return (__m256i) __builtin_ia32_gathersiv8si (src, return (__m256i) __builtin_ia32_gathersiv8si (__src,
base, __base,
(__v8si)index, (__v8si)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i32gather_epi32 (__m256i src, int const *base, _mm256_mask_i32gather_epi32 (__m256i __src, int const *__base,
__m256i index, __m256i mask, const int scale) __m256i __index, __m256i __mask,
const int __scale)
{ {
return (__m256i) __builtin_ia32_gathersiv8si ((__v8si)src, return (__m256i) __builtin_ia32_gathersiv8si ((__v8si)__src,
base, __base,
(__v8si)index, (__v8si)__index,
(__v8si)mask, (__v8si)__mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i64gather_epi32 (int const *base, __m128i index, const int scale) _mm_i64gather_epi32 (int const *__base, __m128i __index, const int __scale)
{ {
__v4si src = __extension__ (__v4si){ 0, 0, 0, 0 }; __v4si __src = __extension__ (__v4si){ 0, 0, 0, 0 };
__v4si mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 }; __v4si __mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 };
return (__m128i) __builtin_ia32_gatherdiv4si (src, return (__m128i) __builtin_ia32_gatherdiv4si (__src,
base, __base,
(__v2di)index, (__v2di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_i64gather_epi32 (__m128i src, int const *base, __m128i index, _mm_mask_i64gather_epi32 (__m128i __src, int const *__base, __m128i __index,
__m128i mask, const int scale) __m128i __mask, const int __scale)
{ {
return (__m128i) __builtin_ia32_gatherdiv4si ((__v4si)src, return (__m128i) __builtin_ia32_gatherdiv4si ((__v4si)__src,
base, __base,
(__v2di)index, (__v2di)__index,
(__v4si)mask, (__v4si)__mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i64gather_epi32 (int const *base, __m256i index, const int scale) _mm256_i64gather_epi32 (int const *__base, __m256i __index, const int __scale)
{ {
__v4si src = __extension__ (__v4si){ 0, 0, 0, 0 }; __v4si __src = __extension__ (__v4si){ 0, 0, 0, 0 };
__v4si mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 }; __v4si __mask = __extension__ (__v4si){ ~0, ~0, ~0, ~0 };
return (__m128i) __builtin_ia32_gatherdiv4si256 (src, return (__m128i) __builtin_ia32_gatherdiv4si256 (__src,
base, __base,
(__v4di)index, (__v4di)__index,
mask, __mask,
scale); __scale);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_i64gather_epi32 (__m128i src, int const *base, _mm256_mask_i64gather_epi32 (__m128i __src, int const *__base,
__m256i index, __m128i mask, const int scale) __m256i __index, __m128i __mask,
const int __scale)
{ {
return (__m128i) __builtin_ia32_gatherdiv4si256 ((__v4si)src, return (__m128i) __builtin_ia32_gatherdiv4si256 ((__v4si)__src,
base, __base,
(__v4di)index, (__v4di)__index,
(__v4si)mask, (__v4si)__mask,
scale); __scale);
} }
#else /* __OPTIMIZE__ */ #else /* __OPTIMIZE__ */
#define _mm_i32gather_pd(BASE, INDEX, SCALE) \ #define _mm_i32gather_pd(BASE, INDEX, SCALE) \
......
...@@ -1438,66 +1438,68 @@ _mm_sub_round_ss (__m128 __A, __m128 __B, const int __R) ...@@ -1438,66 +1438,68 @@ _mm_sub_round_ss (__m128 __A, __m128 __B, const int __R)
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_ternarylogic_epi64 (__m512i __A, __m512i __B, __m512i __C, const int imm) _mm512_ternarylogic_epi64 (__m512i __A, __m512i __B, __m512i __C,
const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pternlogq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) __C, imm, (__v8di) __C, __imm,
(__mmask8) -1); (__mmask8) -1);
} }
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_ternarylogic_epi64 (__m512i __A, __mmask8 __U, __m512i __B, _mm512_mask_ternarylogic_epi64 (__m512i __A, __mmask8 __U, __m512i __B,
__m512i __C, const int imm) __m512i __C, const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pternlogq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) __C, imm, (__v8di) __C, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_maskz_ternarylogic_epi64 (__mmask8 __U, __m512i __A, __m512i __B, _mm512_maskz_ternarylogic_epi64 (__mmask8 __U, __m512i __A, __m512i __B,
__m512i __C, const int imm) __m512i __C, const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogq512_maskz ((__v8di) __A, return (__m512i) __builtin_ia32_pternlogq512_maskz ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) __C, (__v8di) __C,
imm, (__mmask8) __U); __imm, (__mmask8) __U);
} }
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_ternarylogic_epi32 (__m512i __A, __m512i __B, __m512i __C, const int imm) _mm512_ternarylogic_epi32 (__m512i __A, __m512i __B, __m512i __C,
const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogd512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pternlogd512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) __C, (__v16si) __C,
imm, (__mmask16) -1); __imm, (__mmask16) -1);
} }
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_ternarylogic_epi32 (__m512i __A, __mmask16 __U, __m512i __B, _mm512_mask_ternarylogic_epi32 (__m512i __A, __mmask16 __U, __m512i __B,
__m512i __C, const int imm) __m512i __C, const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogd512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pternlogd512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) __C, (__v16si) __C,
imm, (__mmask16) __U); __imm, (__mmask16) __U);
} }
extern __inline __m512i extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_maskz_ternarylogic_epi32 (__mmask16 __U, __m512i __A, __m512i __B, _mm512_maskz_ternarylogic_epi32 (__mmask16 __U, __m512i __A, __m512i __B,
__m512i __C, const int imm) __m512i __C, const int __imm)
{ {
return (__m512i) __builtin_ia32_pternlogd512_maskz ((__v16si) __A, return (__m512i) __builtin_ia32_pternlogd512_maskz ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) __C, (__v16si) __C,
imm, (__mmask16) __U); __imm, (__mmask16) __U);
} }
#else #else
#define _mm512_ternarylogic_epi64(A, B, C, I) \ #define _mm512_ternarylogic_epi64(A, B, C, I) \
...@@ -9211,21 +9213,21 @@ extern __inline __m512 ...@@ -9211,21 +9213,21 @@ extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_ps (__m512i __index, float const *__addr, int __scale) _mm512_i32gather_ps (__m512i __index, float const *__addr, int __scale)
{ {
__m512 v1_old = _mm512_undefined_ps (); __m512 __v1_old = _mm512_undefined_ps ();
__mmask16 mask = 0xFFFF; __mmask16 __mask = 0xFFFF;
return (__m512) __builtin_ia32_gathersiv16sf ((__v16sf) v1_old, return (__m512) __builtin_ia32_gathersiv16sf ((__v16sf) __v1_old,
__addr, __addr,
(__v16si) __index, (__v16si) __index,
mask, __scale); __mask, __scale);
} }
extern __inline __m512 extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_i32gather_ps (__m512 v1_old, __mmask16 __mask, _mm512_mask_i32gather_ps (__m512 __v1_old, __mmask16 __mask,
__m512i __index, float const *__addr, int __scale) __m512i __index, float const *__addr, int __scale)
{ {
return (__m512) __builtin_ia32_gathersiv16sf ((__v16sf) v1_old, return (__m512) __builtin_ia32_gathersiv16sf ((__v16sf) __v1_old,
__addr, __addr,
(__v16si) __index, (__v16si) __index,
__mask, __scale); __mask, __scale);
...@@ -9235,12 +9237,12 @@ extern __inline __m512d ...@@ -9235,12 +9237,12 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_pd (__m256i __index, double const *__addr, int __scale) _mm512_i32gather_pd (__m256i __index, double const *__addr, int __scale)
{ {
__m512d v1_old = _mm512_undefined_pd (); __m512d __v1_old = _mm512_undefined_pd ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m512d) __builtin_ia32_gathersiv8df ((__v8df) v1_old, return (__m512d) __builtin_ia32_gathersiv8df ((__v8df) __v1_old,
__addr, __addr,
(__v8si) __index, mask, (__v8si) __index, __mask,
__scale); __scale);
} }
...@@ -9259,12 +9261,12 @@ extern __inline __m256 ...@@ -9259,12 +9261,12 @@ extern __inline __m256
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_ps (__m512i __index, float const *__addr, int __scale) _mm512_i64gather_ps (__m512i __index, float const *__addr, int __scale)
{ {
__m256 v1_old = _mm256_undefined_ps (); __m256 __v1_old = _mm256_undefined_ps ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m256) __builtin_ia32_gatherdiv16sf ((__v8sf) v1_old, return (__m256) __builtin_ia32_gatherdiv16sf ((__v8sf) __v1_old,
__addr, __addr,
(__v8di) __index, mask, (__v8di) __index, __mask,
__scale); __scale);
} }
...@@ -9283,12 +9285,12 @@ extern __inline __m512d ...@@ -9283,12 +9285,12 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_pd (__m512i __index, double const *__addr, int __scale) _mm512_i64gather_pd (__m512i __index, double const *__addr, int __scale)
{ {
__m512d v1_old = _mm512_undefined_pd (); __m512d __v1_old = _mm512_undefined_pd ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m512d) __builtin_ia32_gatherdiv8df ((__v8df) v1_old, return (__m512d) __builtin_ia32_gatherdiv8df ((__v8df) __v1_old,
__addr, __addr,
(__v8di) __index, mask, (__v8di) __index, __mask,
__scale); __scale);
} }
...@@ -9307,13 +9309,13 @@ extern __inline __m512i ...@@ -9307,13 +9309,13 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_epi32 (__m512i __index, int const *__addr, int __scale) _mm512_i32gather_epi32 (__m512i __index, int const *__addr, int __scale)
{ {
__m512i v1_old = _mm512_undefined_epi32 (); __m512i __v1_old = _mm512_undefined_epi32 ();
__mmask16 mask = 0xFFFF; __mmask16 __mask = 0xFFFF;
return (__m512i) __builtin_ia32_gathersiv16si ((__v16si) v1_old, return (__m512i) __builtin_ia32_gathersiv16si ((__v16si) __v1_old,
__addr, __addr,
(__v16si) __index, (__v16si) __index,
mask, __scale); __mask, __scale);
} }
extern __inline __m512i extern __inline __m512i
...@@ -9331,12 +9333,12 @@ extern __inline __m512i ...@@ -9331,12 +9333,12 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_epi64 (__m256i __index, long long const *__addr, int __scale) _mm512_i32gather_epi64 (__m256i __index, long long const *__addr, int __scale)
{ {
__m512i v1_old = _mm512_undefined_epi32 (); __m512i __v1_old = _mm512_undefined_epi32 ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m512i) __builtin_ia32_gathersiv8di ((__v8di) v1_old, return (__m512i) __builtin_ia32_gathersiv8di ((__v8di) __v1_old,
__addr, __addr,
(__v8si) __index, mask, (__v8si) __index, __mask,
__scale); __scale);
} }
...@@ -9356,13 +9358,13 @@ extern __inline __m256i ...@@ -9356,13 +9358,13 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_epi32 (__m512i __index, int const *__addr, int __scale) _mm512_i64gather_epi32 (__m512i __index, int const *__addr, int __scale)
{ {
__m256i v1_old = _mm256_undefined_si256 (); __m256i __v1_old = _mm256_undefined_si256 ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m256i) __builtin_ia32_gatherdiv16si ((__v8si) v1_old, return (__m256i) __builtin_ia32_gatherdiv16si ((__v8si) __v1_old,
__addr, __addr,
(__v8di) __index, (__v8di) __index,
mask, __scale); __mask, __scale);
} }
extern __inline __m256i extern __inline __m256i
...@@ -9380,12 +9382,12 @@ extern __inline __m512i ...@@ -9380,12 +9382,12 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_epi64 (__m512i __index, long long const *__addr, int __scale) _mm512_i64gather_epi64 (__m512i __index, long long const *__addr, int __scale)
{ {
__m512i v1_old = _mm512_undefined_epi32 (); __m512i __v1_old = _mm512_undefined_epi32 ();
__mmask8 mask = 0xFF; __mmask8 __mask = 0xFF;
return (__m512i) __builtin_ia32_gatherdiv8di ((__v8di) v1_old, return (__m512i) __builtin_ia32_gatherdiv8di ((__v8di) __v1_old,
__addr, __addr,
(__v8di) __index, mask, (__v8di) __index, __mask,
__scale); __scale);
} }
......
...@@ -48,110 +48,110 @@ typedef unsigned short __mmask16; ...@@ -48,110 +48,110 @@ typedef unsigned short __mmask16;
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i32gather_pd (__m256i index, __mmask8 mask, _mm512_mask_prefetch_i32gather_pd (__m256i __index, __mmask8 __mask,
void *addr, int scale, int hint) void *__addr, int __scale, int __hint)
{ {
__builtin_ia32_gatherpfdpd (mask, (__v8si) index, (long long const *) addr, __builtin_ia32_gatherpfdpd (__mask, (__v8si) __index,
scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i32gather_ps (__m512i index, __mmask16 mask, _mm512_mask_prefetch_i32gather_ps (__m512i __index, __mmask16 __mask,
void *addr, int scale, int hint) void *__addr, int __scale, int __hint)
{ {
__builtin_ia32_gatherpfdps (mask, (__v16si) index, (int const *) addr, __builtin_ia32_gatherpfdps (__mask, (__v16si) __index, (int const *) __addr,
scale, hint); __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i64gather_pd (__m512i index, __mmask8 mask, _mm512_mask_prefetch_i64gather_pd (__m512i __index, __mmask8 __mask,
void *addr, int scale, int hint) void *__addr, int __scale, int __hint)
{ {
__builtin_ia32_gatherpfqpd (mask, (__v8di) index, (long long const *) addr, __builtin_ia32_gatherpfqpd (__mask, (__v8di) __index,
scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i64gather_ps (__m512i index, __mmask8 mask, _mm512_mask_prefetch_i64gather_ps (__m512i __index, __mmask8 __mask,
void *addr, int scale, int hint) void *__addr, int __scale, int __hint)
{ {
__builtin_ia32_gatherpfqps (mask, (__v8di) index, (int const *) addr, __builtin_ia32_gatherpfqps (__mask, (__v8di) __index, (int const *) __addr,
scale, hint); __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_prefetch_i32scatter_pd (void *addr, __m256i index, int scale, _mm512_prefetch_i32scatter_pd (void *__addr, __m256i __index, int __scale,
int hint) int __hint)
{ {
__builtin_ia32_scatterpfdpd ((__mmask8) 0xFF, (__v8si) index, __builtin_ia32_scatterpfdpd ((__mmask8) 0xFF, (__v8si) __index,
(long long const *)addr, scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_prefetch_i32scatter_ps (void *addr, __m512i index, int scale, _mm512_prefetch_i32scatter_ps (void *__addr, __m512i __index, int __scale,
int hint) int __hint)
{ {
__builtin_ia32_scatterpfdps ((__mmask16) 0xFFFF, (__v16si) index, (int const *) addr, __builtin_ia32_scatterpfdps ((__mmask16) 0xFFFF, (__v16si) __index,
scale, hint); (int const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i32scatter_pd (void *addr, __mmask8 mask, _mm512_mask_prefetch_i32scatter_pd (void *__addr, __mmask8 __mask,
__m256i index, int scale, int hint) __m256i __index, int __scale, int __hint)
{ {
__builtin_ia32_scatterpfdpd (mask, (__v8si) index, (long long const *) addr, __builtin_ia32_scatterpfdpd (__mask, (__v8si) __index,
scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i32scatter_ps (void *addr, __mmask16 mask, _mm512_mask_prefetch_i32scatter_ps (void *__addr, __mmask16 __mask,
__m512i index, int scale, int hint) __m512i __index, int __scale, int __hint)
{ {
__builtin_ia32_scatterpfdps (mask, (__v16si) index, (int const *) addr, __builtin_ia32_scatterpfdps (__mask, (__v16si) __index, (int const *) __addr,
scale, hint); __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_prefetch_i64scatter_pd (void *addr, __m512i index, int scale, _mm512_prefetch_i64scatter_pd (void *__addr, __m512i __index, int __scale,
int hint) int __hint)
{ {
__builtin_ia32_scatterpfqpd ((__mmask8) 0xFF, (__v8di) index, (long long const *) addr, __builtin_ia32_scatterpfqpd ((__mmask8) 0xFF, (__v8di) __index,
scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_prefetch_i64scatter_ps (void *addr, __m512i index, int scale, _mm512_prefetch_i64scatter_ps (void *__addr, __m512i __index, int __scale,
int hint) int __hint)
{ {
__builtin_ia32_scatterpfqps ((__mmask8) 0xFF, (__v8di) index, (int const *) addr, __builtin_ia32_scatterpfqps ((__mmask8) 0xFF, (__v8di) __index,
scale, hint); (int const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i64scatter_pd (void *addr, __mmask16 mask, _mm512_mask_prefetch_i64scatter_pd (void *__addr, __mmask16 __mask,
__m512i index, int scale, int hint) __m512i __index, int __scale, int __hint)
{ {
__builtin_ia32_scatterpfqpd (mask, (__v8di) index, (long long const *) addr, __builtin_ia32_scatterpfqpd (__mask, (__v8di) __index,
scale, hint); (long long const *) __addr, __scale, __hint);
} }
extern __inline void extern __inline void
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_mask_prefetch_i64scatter_ps (void *addr, __mmask16 mask, _mm512_mask_prefetch_i64scatter_ps (void *__addr, __mmask16 __mask,
__m512i index, int scale, int hint) __m512i __index, int __scale, int __hint)
{ {
__builtin_ia32_scatterpfqps (mask, (__v8di) index, (int const *) addr, __builtin_ia32_scatterpfqps (__mask, (__v8di) __index, (int const *) __addr,
scale, hint); __scale, __hint);
} }
#else #else
......
...@@ -9796,11 +9796,11 @@ _mm_maskz_srli_epi64 (__mmask8 __U, __m128i __A, const int __imm) ...@@ -9796,11 +9796,11 @@ _mm_maskz_srli_epi64 (__mmask8 __U, __m128i __A, const int __imm)
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ternarylogic_epi64 (__m256i __A, __m256i __B, __m256i __C, _mm256_ternarylogic_epi64 (__m256i __A, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogq256_mask ((__v4di) __A, return (__m256i) __builtin_ia32_pternlogq256_mask ((__v4di) __A,
(__v4di) __B, (__v4di) __B,
(__v4di) __C, imm, (__v4di) __C, __imm,
(__mmask8) -1); (__mmask8) -1);
} }
...@@ -9808,11 +9808,11 @@ extern __inline __m256i ...@@ -9808,11 +9808,11 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ternarylogic_epi64 (__m256i __A, __mmask8 __U, _mm256_mask_ternarylogic_epi64 (__m256i __A, __mmask8 __U,
__m256i __B, __m256i __C, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogq256_mask ((__v4di) __A, return (__m256i) __builtin_ia32_pternlogq256_mask ((__v4di) __A,
(__v4di) __B, (__v4di) __B,
(__v4di) __C, imm, (__v4di) __C, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
...@@ -9820,23 +9820,23 @@ extern __inline __m256i ...@@ -9820,23 +9820,23 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ternarylogic_epi64 (__mmask8 __U, __m256i __A, _mm256_maskz_ternarylogic_epi64 (__mmask8 __U, __m256i __A,
__m256i __B, __m256i __C, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogq256_maskz ((__v4di) __A, return (__m256i) __builtin_ia32_pternlogq256_maskz ((__v4di) __A,
(__v4di) __B, (__v4di) __B,
(__v4di) __C, (__v4di) __C,
imm, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m256i extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ternarylogic_epi32 (__m256i __A, __m256i __B, __m256i __C, _mm256_ternarylogic_epi32 (__m256i __A, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogd256_mask ((__v8si) __A, return (__m256i) __builtin_ia32_pternlogd256_mask ((__v8si) __A,
(__v8si) __B, (__v8si) __B,
(__v8si) __C, imm, (__v8si) __C, __imm,
(__mmask8) -1); (__mmask8) -1);
} }
...@@ -9844,11 +9844,11 @@ extern __inline __m256i ...@@ -9844,11 +9844,11 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ternarylogic_epi32 (__m256i __A, __mmask8 __U, _mm256_mask_ternarylogic_epi32 (__m256i __A, __mmask8 __U,
__m256i __B, __m256i __C, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogd256_mask ((__v8si) __A, return (__m256i) __builtin_ia32_pternlogd256_mask ((__v8si) __A,
(__v8si) __B, (__v8si) __B,
(__v8si) __C, imm, (__v8si) __C, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
...@@ -9856,80 +9856,80 @@ extern __inline __m256i ...@@ -9856,80 +9856,80 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ternarylogic_epi32 (__mmask8 __U, __m256i __A, _mm256_maskz_ternarylogic_epi32 (__mmask8 __U, __m256i __A,
__m256i __B, __m256i __C, __m256i __B, __m256i __C,
const int imm) const int __imm)
{ {
return (__m256i) __builtin_ia32_pternlogd256_maskz ((__v8si) __A, return (__m256i) __builtin_ia32_pternlogd256_maskz ((__v8si) __A,
(__v8si) __B, (__v8si) __B,
(__v8si) __C, (__v8si) __C,
imm, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ternarylogic_epi64 (__m128i __A, __m128i __B, __m128i __C, _mm_ternarylogic_epi64 (__m128i __A, __m128i __B, __m128i __C,
const int imm) const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogq128_mask ((__v2di) __A, return (__m128i) __builtin_ia32_pternlogq128_mask ((__v2di) __A,
(__v2di) __B, (__v2di) __B,
(__v2di) __C, imm, (__v2di) __C, __imm,
(__mmask8) -1); (__mmask8) -1);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ternarylogic_epi64 (__m128i __A, __mmask8 __U, _mm_mask_ternarylogic_epi64 (__m128i __A, __mmask8 __U,
__m128i __B, __m128i __C, const int imm) __m128i __B, __m128i __C, const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogq128_mask ((__v2di) __A, return (__m128i) __builtin_ia32_pternlogq128_mask ((__v2di) __A,
(__v2di) __B, (__v2di) __B,
(__v2di) __C, imm, (__v2di) __C, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ternarylogic_epi64 (__mmask8 __U, __m128i __A, _mm_maskz_ternarylogic_epi64 (__mmask8 __U, __m128i __A,
__m128i __B, __m128i __C, const int imm) __m128i __B, __m128i __C, const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogq128_maskz ((__v2di) __A, return (__m128i) __builtin_ia32_pternlogq128_maskz ((__v2di) __A,
(__v2di) __B, (__v2di) __B,
(__v2di) __C, (__v2di) __C,
imm, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ternarylogic_epi32 (__m128i __A, __m128i __B, __m128i __C, _mm_ternarylogic_epi32 (__m128i __A, __m128i __B, __m128i __C,
const int imm) const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogd128_mask ((__v4si) __A, return (__m128i) __builtin_ia32_pternlogd128_mask ((__v4si) __A,
(__v4si) __B, (__v4si) __B,
(__v4si) __C, imm, (__v4si) __C, __imm,
(__mmask8) -1); (__mmask8) -1);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ternarylogic_epi32 (__m128i __A, __mmask8 __U, _mm_mask_ternarylogic_epi32 (__m128i __A, __mmask8 __U,
__m128i __B, __m128i __C, const int imm) __m128i __B, __m128i __C, const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogd128_mask ((__v4si) __A, return (__m128i) __builtin_ia32_pternlogd128_mask ((__v4si) __A,
(__v4si) __B, (__v4si) __B,
(__v4si) __C, imm, (__v4si) __C, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
extern __inline __m128i extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ternarylogic_epi32 (__mmask8 __U, __m128i __A, _mm_maskz_ternarylogic_epi32 (__mmask8 __U, __m128i __A,
__m128i __B, __m128i __C, const int imm) __m128i __B, __m128i __C, const int __imm)
{ {
return (__m128i) __builtin_ia32_pternlogd128_maskz ((__v4si) __A, return (__m128i) __builtin_ia32_pternlogd128_maskz ((__v4si) __A,
(__v4si) __B, (__v4si) __B,
(__v4si) __C, (__v4si) __C,
imm, __imm,
(__mmask8) __U); (__mmask8) __U);
} }
......
...@@ -27,48 +27,48 @@ ...@@ -27,48 +27,48 @@
#include <stdlib.h> #include <stdlib.h>
#include <errno.h> #include <errno.h>
static __inline__ void* static __inline__ void *
_mm_malloc (size_t size, size_t align) _mm_malloc (size_t __size, size_t __align)
{ {
void * malloc_ptr; void * __malloc_ptr;
void * aligned_ptr; void * __aligned_ptr;
/* Error if align is not a power of two. */ /* Error if align is not a power of two. */
if (align & (align - 1)) if (__align & (__align - 1))
{ {
errno = EINVAL; errno = EINVAL;
return ((void*) 0); return ((void *) 0);
} }
if (size == 0) if (__size == 0)
return ((void *) 0); return ((void *) 0);
/* Assume malloc'd pointer is aligned at least to sizeof (void*). /* Assume malloc'd pointer is aligned at least to sizeof (void*).
If necessary, add another sizeof (void*) to store the value If necessary, add another sizeof (void*) to store the value
returned by malloc. Effectively this enforces a minimum alignment returned by malloc. Effectively this enforces a minimum alignment
of sizeof double. */ of sizeof double. */
if (align < 2 * sizeof (void *)) if (__align < 2 * sizeof (void *))
align = 2 * sizeof (void *); __align = 2 * sizeof (void *);
malloc_ptr = malloc (size + align); __malloc_ptr = malloc (__size + __align);
if (!malloc_ptr) if (!__malloc_ptr)
return ((void *) 0); return ((void *) 0);
/* Align We have at least sizeof (void *) space below malloc'd ptr. */ /* Align We have at least sizeof (void *) space below malloc'd ptr. */
aligned_ptr = (void *) (((size_t) malloc_ptr + align) __aligned_ptr = (void *) (((size_t) __malloc_ptr + __align)
& ~((size_t) (align) - 1)); & ~((size_t) (__align) - 1));
/* Store the original pointer just before p. */ /* Store the original pointer just before p. */
((void **) aligned_ptr) [-1] = malloc_ptr; ((void **) __aligned_ptr)[-1] = __malloc_ptr;
return aligned_ptr; return __aligned_ptr;
} }
static __inline__ void static __inline__ void
_mm_free (void * aligned_ptr) _mm_free (void *__aligned_ptr)
{ {
if (aligned_ptr) if (__aligned_ptr)
free (((void **) aligned_ptr) [-1]); free (((void **) __aligned_ptr)[-1]);
} }
#endif /* _MM_MALLOC_H_INCLUDED */ #endif /* _MM_MALLOC_H_INCLUDED */
...@@ -261,9 +261,9 @@ __readeflags (void) ...@@ -261,9 +261,9 @@ __readeflags (void)
/* Write flags register */ /* Write flags register */
extern __inline void extern __inline void
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__writeeflags (unsigned long long X) __writeeflags (unsigned long long __X)
{ {
__builtin_ia32_writeeflags_u64 (X); __builtin_ia32_writeeflags_u64 (__X);
} }
#define _bswap64(a) __bswapq(a) #define _bswap64(a) __bswapq(a)
...@@ -281,9 +281,9 @@ __readeflags (void) ...@@ -281,9 +281,9 @@ __readeflags (void)
/* Write flags register */ /* Write flags register */
extern __inline void extern __inline void
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__writeeflags (unsigned int X) __writeeflags (unsigned int __X)
{ {
__builtin_ia32_writeeflags_u32 (X); __builtin_ia32_writeeflags_u32 (__X);
} }
#endif #endif
......
...@@ -35,9 +35,9 @@ ...@@ -35,9 +35,9 @@
#endif /* __LWP__ */ #endif /* __LWP__ */
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__llwpcb (void *pcbAddress) __llwpcb (void *__pcbAddress)
{ {
__builtin_ia32_llwpcb (pcbAddress); __builtin_ia32_llwpcb (__pcbAddress);
} }
extern __inline void * __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline void * __attribute__((__gnu_inline__, __always_inline__, __artificial__))
...@@ -48,16 +48,17 @@ __slwpcb (void) ...@@ -48,16 +48,17 @@ __slwpcb (void)
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__lwpval32 (unsigned int data2, unsigned int data1, unsigned int flags) __lwpval32 (unsigned int __data2, unsigned int __data1, unsigned int __flags)
{ {
__builtin_ia32_lwpval32 (data2, data1, flags); __builtin_ia32_lwpval32 (__data2, __data1, __flags);
} }
#ifdef __x86_64__ #ifdef __x86_64__
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__lwpval64 (unsigned long long data2, unsigned int data1, unsigned int flags) __lwpval64 (unsigned long long __data2, unsigned int __data1,
unsigned int __flags)
{ {
__builtin_ia32_lwpval64 (data2, data1, flags); __builtin_ia32_lwpval64 (__data2, __data1, __flags);
} }
#endif #endif
#else #else
...@@ -74,16 +75,17 @@ __lwpval64 (unsigned long long data2, unsigned int data1, unsigned int flags) ...@@ -74,16 +75,17 @@ __lwpval64 (unsigned long long data2, unsigned int data1, unsigned int flags)
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__lwpins32 (unsigned int data2, unsigned int data1, unsigned int flags) __lwpins32 (unsigned int __data2, unsigned int __data1, unsigned int __flags)
{ {
return __builtin_ia32_lwpins32 (data2, data1, flags); return __builtin_ia32_lwpins32 (__data2, __data1, __flags);
} }
#ifdef __x86_64__ #ifdef __x86_64__
extern __inline unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__)) extern __inline unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
__lwpins64 (unsigned long long data2, unsigned int data1, unsigned int flags) __lwpins64 (unsigned long long __data2, unsigned int __data1,
unsigned int __flags)
{ {
return __builtin_ia32_lwpins64 (data2, data1, flags); return __builtin_ia32_lwpins64 (__data2, __data1, __flags);
} }
#endif #endif
#else #else
......
...@@ -43,9 +43,9 @@ _rdpkru_u32 (void) ...@@ -43,9 +43,9 @@ _rdpkru_u32 (void)
extern __inline void extern __inline void
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_wrpkru (unsigned int key) _wrpkru (unsigned int __key)
{ {
__builtin_ia32_wrpkru (key); __builtin_ia32_wrpkru (__key);
} }
#ifdef __DISABLE_PKU__ #ifdef __DISABLE_PKU__
......
...@@ -35,23 +35,23 @@ extern "C" int posix_memalign (void **, size_t, size_t) throw (); ...@@ -35,23 +35,23 @@ extern "C" int posix_memalign (void **, size_t, size_t) throw ();
#endif #endif
static __inline void * static __inline void *
_mm_malloc (size_t size, size_t alignment) _mm_malloc (size_t __size, size_t __alignment)
{ {
void *ptr; void *__ptr;
if (alignment == 1) if (__alignment == 1)
return malloc (size); return malloc (__size);
if (alignment == 2 || (sizeof (void *) == 8 && alignment == 4)) if (__alignment == 2 || (sizeof (void *) == 8 && __alignment == 4))
alignment = sizeof (void *); __alignment = sizeof (void *);
if (posix_memalign (&ptr, alignment, size) == 0) if (posix_memalign (&__ptr, __alignment, __size) == 0)
return ptr; return __ptr;
else else
return NULL; return NULL;
} }
static __inline void static __inline void
_mm_free (void * ptr) _mm_free (void *__ptr)
{ {
free (ptr); free (__ptr);
} }
#endif /* _MM_MALLOC_H_INCLUDED */ #endif /* _MM_MALLOC_H_INCLUDED */
...@@ -37,24 +37,24 @@ ...@@ -37,24 +37,24 @@
extern __inline int extern __inline int
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_rdseed16_step (unsigned short *p) _rdseed16_step (unsigned short *__p)
{ {
return __builtin_ia32_rdseed_hi_step (p); return __builtin_ia32_rdseed_hi_step (__p);
} }
extern __inline int extern __inline int
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_rdseed32_step (unsigned int *p) _rdseed32_step (unsigned int *__p)
{ {
return __builtin_ia32_rdseed_si_step (p); return __builtin_ia32_rdseed_si_step (__p);
} }
#ifdef __x86_64__ #ifdef __x86_64__
extern __inline int extern __inline int
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_rdseed64_step (unsigned long long *p) _rdseed64_step (unsigned long long *__p)
{ {
return __builtin_ia32_rdseed_di_step (p); return __builtin_ia32_rdseed_di_step (__p);
} }
#endif #endif
......
...@@ -68,9 +68,9 @@ _xend (void) ...@@ -68,9 +68,9 @@ _xend (void)
#ifdef __OPTIMIZE__ #ifdef __OPTIMIZE__
extern __inline void extern __inline void
__attribute__((__gnu_inline__, __always_inline__, __artificial__)) __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_xabort (const unsigned int imm) _xabort (const unsigned int __imm)
{ {
__builtin_ia32_xabort (imm); __builtin_ia32_xabort (__imm);
} }
#else #else
#define _xabort(N) __builtin_ia32_xabort (N) #define _xabort(N) __builtin_ia32_xabort (N)
......
Markdown is supported
0% or
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment