gcc/config/i386/immintrin.h

   1 /* Copyright (C) 2008-2018 Free Software Foundation, Inc.
   2
   3    This file is part of GCC.
   4
   5    GCC is free software; you can redistribute it and/or modify
   6    it under the terms of the GNU General Public License as published by
   7    the Free Software Foundation; either version 3, or (at your option)
   8    any later version.
   9
  10    GCC is distributed in the hope that it will be useful,
  11    but WITHOUT ANY WARRANTY; without even the implied warranty of
  12    MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
  13    GNU General Public License for more details.
  14
  15    Under Section 7 of GPL version 3, you are granted additional
  16    permissions described in the GCC Runtime Library Exception, version
  17    3.1, as published by the Free Software Foundation.
  18
  19    You should have received a copy of the GNU General Public License and
  20    a copy of the GCC Runtime Library Exception along with this program;
  21    see the files COPYING3 and COPYING.RUNTIME respectively.  If not, see
  22    <http://www.gnu.org/licenses/>.  */
  23
  24 #ifndef _IMMINTRIN_H_INCLUDED
  25 #define _IMMINTRIN_H_INCLUDED
  26
  27 #include <mmintrin.h>
  28
  29 #include <xmmintrin.h>
  30
  31 #include <emmintrin.h>
  32
  33 #include <pmmintrin.h>
  34
  35 #include <tmmintrin.h>
  36
  37 #include <smmintrin.h>
  38
  39 #include <wmmintrin.h>
  40
  41 #include <avxintrin.h>
  42
  43 #include <avx2intrin.h>
  44
  45 #include <avx512fintrin.h>
  46
  47 #include <avx512erintrin.h>
  48
  49 #include <avx512pfintrin.h>
  50
  51 #include <avx512cdintrin.h>
  52
  53 #include <avx512vlintrin.h>
  54
  55 #include <avx512bwintrin.h>
  56
  57 #include <avx512dqintrin.h>
  58
  59 #include <avx512vlbwintrin.h>
  60
  61 #include <avx512vldqintrin.h>
  62
  63 #include <avx512ifmaintrin.h>
  64
  65 #include <avx512ifmavlintrin.h>
  66
  67 #include <avx512vbmiintrin.h>
  68
  69 #include <avx512vbmivlintrin.h>
  70
  71 #include <avx5124fmapsintrin.h>
  72
  73 #include <avx5124vnniwintrin.h>
  74
  75 #include <avx512vpopcntdqintrin.h>
  76
  77 #include <avx512vbmi2intrin.h>
  78
  79 #include <avx512vbmi2vlintrin.h>
  80
  81 #include <avx512vnniintrin.h>
  82
  83 #include <avx512vnnivlintrin.h>
  84
  85 #include <avx512vpopcntdqvlintrin.h>
  86
  87 #include <avx512bitalgintrin.h>
  88
  89 #include <shaintrin.h>
  90
  91 #include <lzcntintrin.h>
  92
  93 #include <bmiintrin.h>
  94
  95 #include <bmi2intrin.h>
  96
  97 #include <fmaintrin.h>
  98
  99 #include <f16cintrin.h>
 100
 101 #include <rtmintrin.h>
 102
 103 #include <xtestintrin.h>
 104
 105 #include <cetintrin.h>
 106
 107 #include <gfniintrin.h>
 108
 109 #include <vaesintrin.h>
 110
 111 #include <vpclmulqdqintrin.h>
 112
 113 extern __inline void
 114 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 115 _wbinvd (void)
 116 {
 117   __builtin_ia32_wbinvd ();
 118 }
 119
 120 #ifndef __RDRND__
 121 #pragma GCC push_options
 122 #pragma GCC target("rdrnd")
 123 #define __DISABLE_RDRND__
 124 #endif /* __RDRND__ */
 125 extern __inline int
 126 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 127 _rdrand16_step (unsigned short *__P)
 128 {
 129   return __builtin_ia32_rdrand16_step (__P);
 130 }
 131
 132 extern __inline int
 133 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 134 _rdrand32_step (unsigned int *__P)
 135 {
 136   return __builtin_ia32_rdrand32_step (__P);
 137 }
 138 #ifdef __DISABLE_RDRND__
 139 #undef __DISABLE_RDRND__
 140 #pragma GCC pop_options
 141 #endif /* __DISABLE_RDRND__ */
 142
 143 #ifndef __RDPID__
 144 #pragma GCC push_options
 145 #pragma GCC target("rdpid")
 146 #define __DISABLE_RDPID__
 147 #endif /* __RDPID__ */
 148 extern __inline unsigned int
 149 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 150 _rdpid_u32 (void)
 151 {
 152   return __builtin_ia32_rdpid ();
 153 }
 154 #ifdef __DISABLE_RDPID__
 155 #undef __DISABLE_RDPID__
 156 #pragma GCC pop_options
 157 #endif /* __DISABLE_RDPID__ */
 158
 159 #ifdef  __x86_64__
 160
 161 #ifndef __FSGSBASE__
 162 #pragma GCC push_options
 163 #pragma GCC target("fsgsbase")
 164 #define __DISABLE_FSGSBASE__
 165 #endif /* __FSGSBASE__ */
 166 extern __inline unsigned int
 167 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 168 _readfsbase_u32 (void)
 169 {
 170   return __builtin_ia32_rdfsbase32 ();
 171 }
 172
 173 extern __inline unsigned long long
 174 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 175 _readfsbase_u64 (void)
 176 {
 177   return __builtin_ia32_rdfsbase64 ();
 178 }
 179
 180 extern __inline unsigned int
 181 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 182 _readgsbase_u32 (void)
 183 {
 184   return __builtin_ia32_rdgsbase32 ();
 185 }
 186
 187 extern __inline unsigned long long
 188 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 189 _readgsbase_u64 (void)
 190 {
 191   return __builtin_ia32_rdgsbase64 ();
 192 }
 193
 194 extern __inline void
 195 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 196 _writefsbase_u32 (unsigned int __B)
 197 {
 198   __builtin_ia32_wrfsbase32 (__B);
 199 }
 200
 201 extern __inline void
 202 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 203 _writefsbase_u64 (unsigned long long __B)
 204 {
 205   __builtin_ia32_wrfsbase64 (__B);
 206 }
 207
 208 extern __inline void
 209 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 210 _writegsbase_u32 (unsigned int __B)
 211 {
 212   __builtin_ia32_wrgsbase32 (__B);
 213 }
 214
 215 extern __inline void
 216 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 217 _writegsbase_u64 (unsigned long long __B)
 218 {
 219   __builtin_ia32_wrgsbase64 (__B);
 220 }
 221 #ifdef __DISABLE_FSGSBASE__
 222 #undef __DISABLE_FSGSBASE__
 223 #pragma GCC pop_options
 224 #endif /* __DISABLE_FSGSBASE__ */
 225
 226 #ifndef __RDRND__
 227 #pragma GCC push_options
 228 #pragma GCC target("rdrnd")
 229 #define __DISABLE_RDRND__
 230 #endif /* __RDRND__ */
 231 extern __inline int
 232 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 233 _rdrand64_step (unsigned long long *__P)
 234 {
 235   return __builtin_ia32_rdrand64_step (__P);
 236 }
 237 #ifdef __DISABLE_RDRND__
 238 #undef __DISABLE_RDRND__
 239 #pragma GCC pop_options
 240 #endif /* __DISABLE_RDRND__ */
 241
 242 #endif /* __x86_64__  */
 243
 244 #endif /* _IMMINTRIN_H_INCLUDED */