gcc/config/i386/immintrin.h

   1 /* Copyright (C) 2008-2019 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 <fxsrintrin.h>
  42
  43 #include <xsaveintrin.h>
  44
  45 #include <xsaveoptintrin.h>
  46
  47 #include <xsavesintrin.h>
  48
  49 #include <xsavecintrin.h>
  50
  51 #include <avxintrin.h>
  52
  53 #include <avx2intrin.h>
  54
  55 #include <avx512fintrin.h>
  56
  57 #include <avx512erintrin.h>
  58
  59 #include <avx512pfintrin.h>
  60
  61 #include <avx512cdintrin.h>
  62
  63 #include <avx512vlintrin.h>
  64
  65 #include <avx512bwintrin.h>
  66
  67 #include <avx512dqintrin.h>
  68
  69 #include <avx512vlbwintrin.h>
  70
  71 #include <avx512vldqintrin.h>
  72
  73 #include <avx512ifmaintrin.h>
  74
  75 #include <avx512ifmavlintrin.h>
  76
  77 #include <avx512vbmiintrin.h>
  78
  79 #include <avx512vbmivlintrin.h>
  80
  81 #include <avx5124fmapsintrin.h>
  82
  83 #include <avx5124vnniwintrin.h>
  84
  85 #include <avx512vpopcntdqintrin.h>
  86
  87 #include <avx512vbmi2intrin.h>
  88
  89 #include <avx512vbmi2vlintrin.h>
  90
  91 #include <avx512vnniintrin.h>
  92
  93 #include <avx512vnnivlintrin.h>
  94
  95 #include <avx512vpopcntdqvlintrin.h>
  96
  97 #include <avx512bitalgintrin.h>
  98
  99 #include <shaintrin.h>
 100
 101 #include <lzcntintrin.h>
 102
 103 #include <bmiintrin.h>
 104
 105 #include <bmi2intrin.h>
 106
 107 #include <fmaintrin.h>
 108
 109 #include <f16cintrin.h>
 110
 111 #include <rtmintrin.h>
 112
 113 #include <xtestintrin.h>
 114
 115 #include <cetintrin.h>
 116
 117 #include <gfniintrin.h>
 118
 119 #include <vaesintrin.h>
 120
 121 #include <vpclmulqdqintrin.h>
 122
 123 #include <movdirintrin.h>
 124
 125 #include <sgxintrin.h>
 126
 127 #include <pconfigintrin.h>
 128
 129 #include <waitpkgintrin.h>
 130
 131 #include <cldemoteintrin.h>
 132
 133 #include <avx512bf16vlintrin.h>
 134
 135 #include <avx512bf16intrin.h>
 136
 137 #include <enqcmdintrin.h>
 138
 139 #include <rdseedintrin.h>
 140
 141 #include <prfchwintrin.h>
 142
 143 #include <adxintrin.h>
 144
 145 #include <clwbintrin.h>
 146
 147 #include <clflushoptintrin.h>
 148
 149 #include <wbnoinvdintrin.h>
 150
 151 #include <pkuintrin.h>
 152
 153 extern __inline void
 154 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 155 _wbinvd (void)
 156 {
 157   __builtin_ia32_wbinvd ();
 158 }
 159
 160 #ifndef __RDRND__
 161 #pragma GCC push_options
 162 #pragma GCC target("rdrnd")
 163 #define __DISABLE_RDRND__
 164 #endif /* __RDRND__ */
 165 extern __inline int
 166 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 167 _rdrand16_step (unsigned short *__P)
 168 {
 169   return __builtin_ia32_rdrand16_step (__P);
 170 }
 171
 172 extern __inline int
 173 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 174 _rdrand32_step (unsigned int *__P)
 175 {
 176   return __builtin_ia32_rdrand32_step (__P);
 177 }
 178 #ifdef __DISABLE_RDRND__
 179 #undef __DISABLE_RDRND__
 180 #pragma GCC pop_options
 181 #endif /* __DISABLE_RDRND__ */
 182
 183 #ifndef __RDPID__
 184 #pragma GCC push_options
 185 #pragma GCC target("rdpid")
 186 #define __DISABLE_RDPID__
 187 #endif /* __RDPID__ */
 188 extern __inline unsigned int
 189 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 190 _rdpid_u32 (void)
 191 {
 192   return __builtin_ia32_rdpid ();
 193 }
 194 #ifdef __DISABLE_RDPID__
 195 #undef __DISABLE_RDPID__
 196 #pragma GCC pop_options
 197 #endif /* __DISABLE_RDPID__ */
 198
 199 #ifdef  __x86_64__
 200
 201 #ifndef __FSGSBASE__
 202 #pragma GCC push_options
 203 #pragma GCC target("fsgsbase")
 204 #define __DISABLE_FSGSBASE__
 205 #endif /* __FSGSBASE__ */
 206 extern __inline unsigned int
 207 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 208 _readfsbase_u32 (void)
 209 {
 210   return __builtin_ia32_rdfsbase32 ();
 211 }
 212
 213 extern __inline unsigned long long
 214 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 215 _readfsbase_u64 (void)
 216 {
 217   return __builtin_ia32_rdfsbase64 ();
 218 }
 219
 220 extern __inline unsigned int
 221 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 222 _readgsbase_u32 (void)
 223 {
 224   return __builtin_ia32_rdgsbase32 ();
 225 }
 226
 227 extern __inline unsigned long long
 228 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 229 _readgsbase_u64 (void)
 230 {
 231   return __builtin_ia32_rdgsbase64 ();
 232 }
 233
 234 extern __inline void
 235 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 236 _writefsbase_u32 (unsigned int __B)
 237 {
 238   __builtin_ia32_wrfsbase32 (__B);
 239 }
 240
 241 extern __inline void
 242 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 243 _writefsbase_u64 (unsigned long long __B)
 244 {
 245   __builtin_ia32_wrfsbase64 (__B);
 246 }
 247
 248 extern __inline void
 249 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 250 _writegsbase_u32 (unsigned int __B)
 251 {
 252   __builtin_ia32_wrgsbase32 (__B);
 253 }
 254
 255 extern __inline void
 256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 257 _writegsbase_u64 (unsigned long long __B)
 258 {
 259   __builtin_ia32_wrgsbase64 (__B);
 260 }
 261 #ifdef __DISABLE_FSGSBASE__
 262 #undef __DISABLE_FSGSBASE__
 263 #pragma GCC pop_options
 264 #endif /* __DISABLE_FSGSBASE__ */
 265
 266 #ifndef __RDRND__
 267 #pragma GCC push_options
 268 #pragma GCC target("rdrnd")
 269 #define __DISABLE_RDRND__
 270 #endif /* __RDRND__ */
 271 extern __inline int
 272 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 273 _rdrand64_step (unsigned long long *__P)
 274 {
 275   return __builtin_ia32_rdrand64_step (__P);
 276 }
 277 #ifdef __DISABLE_RDRND__
 278 #undef __DISABLE_RDRND__
 279 #pragma GCC pop_options
 280 #endif /* __DISABLE_RDRND__ */
 281
 282 #endif /* __x86_64__  */
 283
 284 #ifndef __PTWRITE__
 285 #pragma GCC push_options
 286 #pragma GCC target("ptwrite")
 287 #define __DISABLE_PTWRITE__
 288 #endif
 289
 290 #ifdef __x86_64__
 291 extern __inline void
 292 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 293 _ptwrite64 (unsigned long long __B)
 294 {
 295   __builtin_ia32_ptwrite64 (__B);
 296 }
 297 #endif /* __x86_64__ */
 298
 299 extern __inline void
 300 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 301 _ptwrite32 (unsigned __B)
 302 {
 303   __builtin_ia32_ptwrite32 (__B);
 304 }
 305 #ifdef __DISABLE_PTWRITE__
 306 #undef __DISABLE_PTWRITE__
 307 #pragma GCC pop_options
 308 #endif /* __DISABLE_PTWRITE__ */
 309
 310 #endif /* _IMMINTRIN_H_INCLUDED */