contrib/llvm/tools/clang/lib/Headers/avx512ifmaintrin.h

   1 /*===------------- avx512ifmaintrin.h - IFMA intrinsics ------------------===
   2  *
   3  *
   4  * Permission is hereby granted, free of charge, to any person obtaining a copy
   5  * of this software and associated documentation files (the "Software"), to deal
   6  * in the Software without restriction, including without limitation the rights
   7  * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
   8  * copies of the Software, and to permit persons to whom the Software is
   9  * furnished to do so, subject to the following conditions:
  10  *
  11  * The above copyright notice and this permission notice shall be included in
  12  * all copies or substantial portions of the Software.
  13  *
  14  * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
  15  * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
  16  * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
  17  * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
  18  * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
  19  * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
  20  * THE SOFTWARE.
  21  *
  22  *===-----------------------------------------------------------------------===
  23  */
  24 #ifndef __IMMINTRIN_H
  25 #error "Never use <avx512ifmaintrin.h> directly; include <immintrin.h> instead."
  26 #endif
  27
  28 #ifndef __IFMAINTRIN_H
  29 #define __IFMAINTRIN_H
  30
  31 /* Define the default attributes for the functions in this file. */
  32 #define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512ifma")))
  33
  34 static __inline__ __m512i __DEFAULT_FN_ATTRS
  35 _mm512_madd52hi_epu64 (__m512i __X, __m512i __Y, __m512i __Z)
  36 {
  37   return (__m512i) __builtin_ia32_vpmadd52huq512_mask ((__v8di) __X,
  38                    (__v8di) __Y,
  39                    (__v8di) __Z,
  40                    (__mmask8) -1);
  41 }
  42
  43 static __inline__ __m512i __DEFAULT_FN_ATTRS
  44 _mm512_mask_madd52hi_epu64 (__m512i __W, __mmask8 __M, __m512i __X,
  45           __m512i __Y)
  46 {
  47   return (__m512i) __builtin_ia32_vpmadd52huq512_mask ((__v8di) __W,
  48                    (__v8di) __X,
  49                    (__v8di) __Y,
  50                    (__mmask8) __M);
  51 }
  52
  53 static __inline__ __m512i __DEFAULT_FN_ATTRS
  54 _mm512_maskz_madd52hi_epu64 (__mmask8 __M, __m512i __X, __m512i __Y, __m512i __Z)
  55 {
  56   return (__m512i) __builtin_ia32_vpmadd52huq512_maskz ((__v8di) __X,
  57               (__v8di) __Y,
  58               (__v8di) __Z,
  59               (__mmask8) __M);
  60 }
  61
  62 static __inline__ __m512i __DEFAULT_FN_ATTRS
  63 _mm512_madd52lo_epu64 (__m512i __X, __m512i __Y, __m512i __Z)
  64 {
  65   return (__m512i) __builtin_ia32_vpmadd52luq512_mask ((__v8di) __X,
  66                    (__v8di) __Y,
  67                    (__v8di) __Z,
  68                    (__mmask8) -1);
  69 }
  70
  71 static __inline__ __m512i __DEFAULT_FN_ATTRS
  72 _mm512_mask_madd52lo_epu64 (__m512i __W, __mmask8 __M, __m512i __X,
  73           __m512i __Y)
  74 {
  75   return (__m512i) __builtin_ia32_vpmadd52luq512_mask ((__v8di) __W,
  76                    (__v8di) __X,
  77                    (__v8di) __Y,
  78                    (__mmask8) __M);
  79 }
  80
  81 static __inline__ __m512i __DEFAULT_FN_ATTRS
  82 _mm512_maskz_madd52lo_epu64 (__mmask8 __M, __m512i __X, __m512i __Y, __m512i __Z)
  83 {
  84   return (__m512i) __builtin_ia32_vpmadd52luq512_maskz ((__v8di) __X,
  85               (__v8di) __Y,
  86               (__v8di) __Z,
  87               (__mmask8) __M);
  88 }
  89
  90 #undef __DEFAULT_FN_ATTRS
  91
  92 #endif