/* Copyright (C) 2024 Free Software Foundation, Inc.
This file is part of GCC.
GCC 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, or (at your option)
any later version.
GCC 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.
Under Section 7 of GPL version 3, you are granted additional
permissions described in the GCC Runtime Library Exception, version
3.1, as published by the Free Software Foundation.
You should have received a copy of the GNU General Public License and
a copy of the GCC Runtime Library Exception along with this program;
see the files COPYING3 and COPYING.RUNTIME respectively. If not, see
. */
#if !defined _IMMINTRIN_H_INCLUDED
#error "Never use directly; include instead."
#endif
#ifndef _AVX10_2SATCVTINTRIN_H_INCLUDED
#define _AVX10_2SATCVTINTRIN_H_INCLUDED
#if !defined (__AVX10_2_256__)
#pragma GCC push_options
#pragma GCC target("avx10.2")
#define __DISABLE_AVX10_2_256__
#endif /* __AVX10_2_256__ */
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtnebf16_epi16 (__m128bh __A)
{
return (__m128i) __builtin_ia32_cvtnebf162ibs128_mask ((__v8bf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtnebf16_epi16 (__m128i __W, __mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvtnebf162ibs128_mask ((__v8bf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtnebf16_epi16 (__mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvtnebf162ibs128_mask ((__v8bf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtnebf16_epi16 (__m256bh __A)
{
return
(__m256i) __builtin_ia32_cvtnebf162ibs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtnebf16_epi16 (__m256i __W, __mmask16 __U, __m256bh __A)
{
return (__m256i) __builtin_ia32_cvtnebf162ibs256_mask ((__v16bf) __A,
(__v16hi) __W,
(__mmask16) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtnebf16_epi16 (__mmask16 __U, __m256bh __A)
{
return
(__m256i) __builtin_ia32_cvtnebf162ibs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtnebf16_epu16 (__m128bh __A)
{
return
(__m128i) __builtin_ia32_cvtnebf162iubs128_mask ((__v8bf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtnebf16_epu16 (__m128i __W, __mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvtnebf162iubs128_mask ((__v8bf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtnebf16_epu16 (__mmask8 __U, __m128bh __A)
{
return
(__m128i) __builtin_ia32_cvtnebf162iubs128_mask ((__v8bf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtnebf16_epu16 (__m256bh __A)
{
return
(__m256i) __builtin_ia32_cvtnebf162iubs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtnebf16_epu16 (__m256i __W, __mmask16 __U, __m256bh __A)
{
return (__m256i) __builtin_ia32_cvtnebf162iubs256_mask ((__v16bf) __A,
(__v16hi) __W,
(__mmask16) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtnebf16_epu16 (__mmask16 __U, __m256bh __A)
{
return
(__m256i) __builtin_ia32_cvtnebf162iubs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtph_epi16 (__m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2ibs128_mask ((__v8hf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtph_epi16 (__m128i __W, __mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2ibs128_mask ((__v8hf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtph_epi16 (__mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2ibs128_mask ((__v8hf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtph_epu16 (__m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2iubs128_mask ((__v8hf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtph_epu16 (__m128i __W, __mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2iubs128_mask ((__v8hf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtph_epu16 (__mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvtph2iubs128_mask ((__v8hf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtps_epi32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2ibs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtps_epi32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2ibs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtps_epi32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2ibs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvtps_epu32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2iubs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvtps_epu32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2iubs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvtps_epu32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvtps2iubs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttnebf16_epi16 (__m128bh __A)
{
return
(__m128i) __builtin_ia32_cvttnebf162ibs128_mask ((__v8bf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttnebf16_epi16 (__m128i __W, __mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvttnebf162ibs128_mask ((__v8bf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttnebf16_epi16 (__mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvttnebf162ibs128_mask ((__v8bf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttnebf16_epu16 (__m128bh __A)
{
return
(__m128i) __builtin_ia32_cvttnebf162iubs128_mask ((__v8bf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttnebf16_epu16 (__m128i __W, __mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvttnebf162iubs128_mask ((__v8bf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttnebf16_epu16 (__mmask8 __U, __m128bh __A)
{
return (__m128i) __builtin_ia32_cvttnebf162iubs128_mask ((__v8bf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvttnebf16_epi16 (__m256bh __A)
{
return (__m256i)
__builtin_ia32_cvttnebf162ibs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvttnebf16_epi16 (__m256i __W, __mmask16 __U, __m256bh __A)
{
return (__m256i) __builtin_ia32_cvttnebf162ibs256_mask ((__v16bf) __A,
(__v16hi) __W,
(__mmask16) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvttnebf16_epi16 (__mmask16 __U, __m256bh __A)
{
return (__m256i)
__builtin_ia32_cvttnebf162ibs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvttnebf16_epu16 (__m256bh __A)
{
return (__m256i)
__builtin_ia32_cvttnebf162iubs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvttnebf16_epu16 (__m256i __W, __mmask16 __U, __m256bh __A)
{
return (__m256i) __builtin_ia32_cvttnebf162iubs256_mask ((__v16bf) __A,
(__v16hi) __W,
(__mmask16) __U);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvttnebf16_epu16 (__mmask16 __U, __m256bh __A)
{
return (__m256i)
__builtin_ia32_cvttnebf162iubs256_mask ((__v16bf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttph_epi16 (__m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2ibs128_mask ((__v8hf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttph_epi16 (__m128i __W, __mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2ibs128_mask ((__v8hf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttph_epi16 (__mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2ibs128_mask ((__v8hf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttph_epu16 (__m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2iubs128_mask ((__v8hf) __A,
(__v8hi)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttph_epu16 (__m128i __W, __mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2iubs128_mask ((__v8hf) __A,
(__v8hi) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttph_epu16 (__mmask8 __U, __m128h __A)
{
return (__m128i) __builtin_ia32_cvttph2iubs128_mask ((__v8hf) __A,
(__v8hi)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttps_epi32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2ibs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttps_epi32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2ibs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttps_epi32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2ibs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_ipcvttps_epu32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2iubs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_ipcvttps_epu32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2iubs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_ipcvttps_epu32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2iubs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttspd_epi32 (__m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2dqs128_mask ((__v2df) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttspd_epi32 (__m128i __W, __mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2dqs128_mask ((__v2df) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttspd_epi32 (__mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2dqs128_mask ((__v2df) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttspd_epi64 (__m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2qqs128_mask ((__v2df) __A,
(__v2di)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttspd_epi64 (__m128i __W, __mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2qqs128_mask ((__v2df) __A,
(__v2di) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttspd_epi64 (__mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2qqs128_mask ((__v2df) __A,
(__v2di)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttspd_epu32 (__m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2udqs128_mask ((__v2df) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttspd_epu32 (__m128i __W, __mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2udqs128_mask ((__v2df) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttspd_epu32 (__mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2udqs128_mask ((__v2df) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttspd_epu64 (__m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2uqqs128_mask ((__v2df) __A,
(__v2di)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttspd_epu64 (__m128i __W, __mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2uqqs128_mask ((__v2df) __A,
(__v2di) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttspd_epu64 (__mmask8 __U, __m128d __A)
{
return (__m128i) __builtin_ia32_cvttpd2uqqs128_mask ((__v2df) __A,
(__v2di)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttsps_epi32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2dqs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttsps_epi32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2dqs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttsps_epi32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2dqs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttsps_epi64 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2qqs128_mask ((__v4sf) __A,
(__v2di)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttsps_epi64 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2qqs128_mask ((__v4sf) __A,
(__v2di) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttsps_epi64 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2qqs128_mask ((__v4sf) __A,
(__v2di)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttsps_epu32 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2udqs128_mask ((__v4sf) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttsps_epu32 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2udqs128_mask ((__v4sf) __A,
(__v4si) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttsps_epu32 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2udqs128_mask ((__v4sf) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvttsps_epu64 (__m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2uqqs128_mask ((__v4sf) __A,
(__v2di)
_mm_undefined_si128 (),
(__mmask8) -1);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_cvttsps_epu64 (__m128i __W, __mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2uqqs128_mask ((__v4sf) __A,
(__v2di) __W,
(__mmask8) __U);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_cvttsps_epu64 (__mmask8 __U, __m128 __A)
{
return (__m128i) __builtin_ia32_cvttps2uqqs128_mask ((__v4sf) __A,
(__v2di)
_mm_setzero_si128 (),
(__mmask8) __U);
}
#ifdef __OPTIMIZE__
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvt_roundph_epi16 (__m256h __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvt_roundph_epi16 (__m256i __W, __mmask16 __U, __m256h __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) __A,
(__v16hi) __W,
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvt_roundph_epi16 (__mmask16 __U, __m256h __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvt_roundph_epu16 (__m256h __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvt_roundph_epu16 (__m256i __W, __mmask16 __U, __m256h __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) __A,
(__v16hi) __W,
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvt_roundph_epu16 (__mmask16 __U, __m256h __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvt_roundps_epi32 (__m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvt_roundps_epi32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvt_roundps_epi32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvt_roundps_epu32 (__m256 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvt_roundps_epu32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvt_roundps_epu32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtt_roundph_epi16 (__m256h __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtt_roundph_epi16 (__m256i __W, __mmask16 __U, __m256h __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) __A,
(__v16hi) __W,
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtt_roundph_epi16 (__mmask16 __U, __m256h __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtt_roundph_epu16 (__m256h __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_undefined_si256 (),
(__mmask16) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtt_roundph_epu16 (__m256i __W, __mmask16 __U, __m256h __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) __A,
(__v16hi) __W,
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtt_roundph_epu16 (__mmask16 __U, __m256h __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) __A,
(__v16hi)
_mm256_setzero_si256 (),
(__mmask16) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtt_roundps_epi32 (__m256 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtt_roundps_epi32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtt_roundps_epi32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_ipcvtt_roundps_epu32 (__m256 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_ipcvtt_roundps_epu32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_ipcvtt_roundps_epu32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundpd_epi32 (__m256d __A, const int __R)
{
return
(__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundpd_epi32 (__m128i __W, __mmask8 __U, __m256d __A,
const int __R)
{
return (__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) __A,
(__v4si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundpd_epi32 (__mmask8 __U, __m256d __A, const int __R)
{
return
(__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundpd_epi64 (__m256d __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) __A,
(__v4di)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundpd_epi64 (__m256i __W, __mmask8 __U, __m256d __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) __A,
(__v4di) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundpd_epi64 (__mmask8 __U, __m256d __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) __A,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundpd_epu32 (__m256d __A, const int __R)
{
return
(__m128i) __builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) __A,
(__v4si)
_mm_undefined_si128 (),
(__mmask8) -1,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundpd_epu32 (__m128i __W, __mmask8 __U, __m256d __A,
const int __R)
{
return (__m128i) __builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) __A,
(__v4si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundpd_epu32 (__mmask8 __U, __m256d __A, const int __R)
{
return
(__m128i) __builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) __A,
(__v4si)
_mm_setzero_si128 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundpd_epu64 (__m256d __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) __A,
(__v4di)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundpd_epu64 (__m256i __W, __mmask8 __U, __m256d __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) __A,
(__v4di) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundpd_epu64 (__mmask8 __U, __m256d __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) __A,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundps_epi32 (__m256 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundps_epi32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundps_epi32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundps_epi64 (__m128 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) __A,
(__v4di)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundps_epi64 (__m256i __W, __mmask8 __U, __m128 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) __A,
(__v4di) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundps_epi64 (__mmask8 __U, __m128 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) __A,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundps_epu32 (__m256 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundps_epu32 (__m256i __W, __mmask8 __U, __m256 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) __A,
(__v8si) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundps_epu32 (__mmask8 __U, __m256 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) __A,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_cvtts_roundps_epu64 (__m128 __A, const int __R)
{
return (__m256i)
__builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) __A,
(__v4di)
_mm256_undefined_si256 (),
(__mmask8) -1,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_cvtts_roundps_epu64 (__m256i __W, __mmask8 __U, __m128 __A,
const int __R)
{
return (__m256i) __builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) __A,
(__v4di) __W,
(__mmask8) __U,
__R);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_cvtts_roundps_epu64 (__mmask8 __U, __m128 __A, const int __R)
{
return
(__m256i) __builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) __A,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8) __U,
__R);
}
extern __inline int
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundsd_epi32 (__m128d __A, const int __R)
{
return (int) __builtin_ia32_cvttsd2sis32_round ((__v2df) __A,
__R);
}
extern __inline unsigned int
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundsd_epu32 (__m128d __A, const int __R)
{
return (unsigned int) __builtin_ia32_cvttsd2usis32_round ((__v2df) __A,
__R);
}
extern __inline int
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundss_epi32 (__m128 __A, const int __R)
{
return (int) __builtin_ia32_cvttss2sis32_round ((__v4sf) __A,
__R);
}
extern __inline unsigned int
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundss_epu32 (__m128 __A, const int __R)
{
return (unsigned int) __builtin_ia32_cvttss2usis32_round ((__v4sf) __A,
__R);
}
#else
#define _mm256_ipcvt_roundph_epi16(A, R) \
((__m256i) \
__builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvt_roundph_epi16(W, U, A, R) \
((__m256i) __builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvt_roundph_epi16(U, A, R) \
((__m256i) \
__builtin_ia32_cvtph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvt_roundph_epu16(A, R) \
((__m256i) \
__builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvt_roundph_epu16(W, U, A, R) \
((__m256i) __builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvt_roundph_epu16(U, A, R) \
((__m256i) \
__builtin_ia32_cvtph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvt_roundps_epi32(A, R) \
((__m256i) \
__builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_ipcvt_roundps_epi32(W, U, A, R) \
((__m256i) __builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_ipcvt_roundps_epi32(U, A, R) \
((__m256i) \
__builtin_ia32_cvtps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_ipcvt_roundps_epu32(A, R) \
((__m256i) \
__builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_ipcvt_roundps_epu32(W, U, A, R) \
((__m256i) __builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_ipcvt_roundps_epu32(U, A, R) \
((__m256i) \
__builtin_ia32_cvtps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_ipcvttne_roundbf16_epi16(A, R) \
((__m256i) \
__builtin_ia32_cvttnebf162ibs256_mask_round ((__v16bf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvttne_roundbf16_epi16(W, U, A, R) \
((__m256i) __builtin_ia32_cvttnebf162ibs256_mask_round ((__v16bf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvttne_roundbf16_epi16(U, A, R) \
((__m256i) \
__builtin_ia32_cvttnebf162ibs256_mask_round ((__v16bf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvttne_roundbf16_epu16(A, R) \
((__m256i) \
__builtin_ia32_cvttnebf162iubs256_mask_round ((__v16bf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvttne_roundbf16_epu16(W, U, A, R) \
((__m256i) __builtin_ia32_cvttnebf162iubs256_mask_round ((__v16bf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvttne_roundbf16_epu16(U, A, R) \
((__m256i) \
__builtin_ia32_cvttnebf162iubs256_mask_round ((__v16bf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvtt_roundph_epi16(A, R) \
((__m256i) \
__builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvtt_roundph_epi16(W, U, A, R) \
((__m256i) __builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvtt_roundph_epi16(U, A, R) \
((__m256i) \
__builtin_ia32_cvttph2ibs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvtt_roundph_epu16(A, R) \
((__m256i) \
__builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_undefined_si256 ()), \
(__mmask16) (-1), \
(R)))
#define _mm256_mask_ipcvtt_roundph_epu16(W, U, A, R) \
((__m256i) __builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) (W), \
(__mmask16) (U), \
(R)))
#define _mm256_maskz_ipcvtt_roundph_epu16(U, A, R) \
((__m256i) \
__builtin_ia32_cvttph2iubs256_mask_round ((__v16hf) (A), \
(__v16hi) \
(_mm256_setzero_si256 ()), \
(__mmask16) (U), \
(R)))
#define _mm256_ipcvtt_roundps_epi32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_ipcvtt_roundps_epi32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_ipcvtt_roundps_epi32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2ibs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_ipcvtt_roundps_epu32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_ipcvtt_roundps_epu32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_ipcvtt_roundps_epu32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2iubs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epi32(A, R) \
((__m128i) \
__builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_undefined_si128 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epi32(W, U, A, R) \
((__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epi32(U, A, R) \
((__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_setzero_si128 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epi64(A, R) \
((__m256i) \
__builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epi64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epi64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epu32(A, R) \
((__m128i) \
__builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_undefined_si128 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epu32(W, U, A, R) \
((__m128i) __builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epu32(U, A, R) \
((__m128i) \
__builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) (_mm_setzero_si128 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epu64(A, R) \
((__m256i) \
__builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epu64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epu64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epi32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epi32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epi32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epi64(A, R) \
((__m256i) \
__builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epi64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epi64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epu32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epu32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epu32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epu64(A, R) \
((__m256i) \
__builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epu64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epu64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm_cvtts_roundsd_epi32(A, R) \
((int) __builtin_ia32_cvttsd2sis32_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundsd_epu32(A, R) \
((unsigned int) __builtin_ia32_cvttsd2usis32_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundss_epi32(A, R) \
((int) __builtin_ia32_cvttss2sis32_round ((__v4sf) (A), \
(R)))
#define _mm_cvtts_roundss_epu32(A, R) \
((unsigned int) __builtin_ia32_cvttss2usis32_round ((__v4sf) (A), \
(R)))
#define _mm256_cvtts_roundpd_epi32(A, R) \
((__m128i) \
__builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_undefined_si128 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epi32(W, U, A, R) \
((__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epi32(U, A, R) \
((__m128i) __builtin_ia32_cvttpd2dqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_setzero_si128 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epi64(A, R) \
((__m256i) \
__builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epi64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epi64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttpd2qqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epu32(A, R) \
((__m128i) \
__builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) \
(_mm_undefined_si128 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epu32(W, U, A, R) \
((__m128i) __builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epu32(U, A, R) \
((__m128i) \
__builtin_ia32_cvttpd2udqs256_mask_round ((__v4df) (A), \
(__v4si) (_mm_setzero_si128 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundpd_epu64(A, R) \
((__m256i) \
__builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundpd_epu64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundpd_epu64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttpd2uqqs256_mask_round ((__v4df) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epi32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epi32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epi32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2dqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epi64(A, R) \
((__m256i) \
__builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epi64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epi64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2qqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epu32(A, R) \
((__m256i) \
__builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epu32(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epu32(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2udqs256_mask_round ((__v8sf) (A), \
(__v8si) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm256_cvtts_roundps_epu64(A, R) \
((__m256i) \
__builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_undefined_si256 ()), \
(__mmask8) (-1), \
(R)))
#define _mm256_mask_cvtts_roundps_epu64(W, U, A, R) \
((__m256i) __builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) (W), \
(__mmask8) (U), \
(R)))
#define _mm256_maskz_cvtts_roundps_epu64(U, A, R) \
((__m256i) \
__builtin_ia32_cvttps2uqqs256_mask_round ((__v4sf) (A), \
(__v4di) \
(_mm256_setzero_si256 ()), \
(__mmask8) (U), \
(R)))
#define _mm_cvtts_roundsd_epi32(A, R) \
((int) __builtin_ia32_cvttsd2sis32_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundsd_epu32(A, R) \
((unsigned int) __builtin_ia32_cvttsd2usis32_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundss_epi32(A, R) \
((int) __builtin_ia32_cvttss2sis32_round ((__v4sf) (A), \
(R)))
#define _mm_cvtts_roundss_epu32(A, R) \
((unsigned int) __builtin_ia32_cvttss2usis32_round ((__v4sf) (A), \
(R)))
#endif
#ifdef __x86_64__
#ifdef __OPTIMIZE__
extern __inline long long
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundsd_epi64 (__m128d __A, const int __R)
{
return (long long) __builtin_ia32_cvttsd2sis64_round ((__v2df) __A,
__R);
}
extern __inline unsigned long long
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundsd_epu64 (__m128d __A, const int __R)
{
return (unsigned long long) __builtin_ia32_cvttsd2usis64_round ((__v2df) __A,
__R);
}
extern __inline long long
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundss_epi64 (__m128 __A, const int __R)
{
return (long long) __builtin_ia32_cvttss2sis64_round ((__v4sf) __A,
__R);
}
extern __inline unsigned long long
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_cvtts_roundss_epu64 (__m128 __A, const int __R)
{
return (unsigned long long) __builtin_ia32_cvttss2usis64_round ((__v4sf) __A,
__R);
}
#else
#define _mm_cvtts_roundsd_epi64(A, R) \
((long long) __builtin_ia32_cvttsd2sis64_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundsd_epu64(A, R) \
((unsigned long long) __builtin_ia32_cvttsd2usis64_round ((__v2df) (A), \
(R)))
#define _mm_cvtts_roundss_epi64(A, R) \
((long long) __builtin_ia32_cvttss2sis64_round ((__v4sf) (A), \
(R)))
#define _mm_cvtts_roundss_epu64(A, R) \
((unsigned long long) __builtin_ia32_cvttss2usis64_round ((__v4sf) (A), \
(R)))
#endif
#endif /* __x86_64__ */
#ifdef __DISABLE_AVX10_2_256__
#undef __DISABLE_AVX10_2_256__
#pragma GCC pop_options
#endif /* __DISABLE_AVX10_2_256__ */
#endif /* _AVX10_2SATCVTINTRIN_H_INCLUDED */