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 #include <movdirintrin.h>
 114
 115 #include <sgxintrin.h>
 116
 117 #include <pconfigintrin.h>
 118
 119 #include <waitpkgintrin.h>
 120
 121 #include <cldemoteintrin.h>
 122
 123 extern __inline void
 124 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 125 _wbinvd (void)
 126 {
 127   __builtin_ia32_wbinvd ();
 128 }
 129
 130 #ifndef __RDRND__
 131 #pragma GCC push_options
 132 #pragma GCC target("rdrnd")
 133 #define __DISABLE_RDRND__
 134 #endif /* __RDRND__ */
 135 extern __inline int
 136 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 137 _rdrand16_step (unsigned short *__P)
 138 {
 139   return __builtin_ia32_rdrand16_step (__P);
 140 }
 141
 142 extern __inline int
 143 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 144 _rdrand32_step (unsigned int *__P)
 145 {
 146   return __builtin_ia32_rdrand32_step (__P);
 147 }
 148 #ifdef __DISABLE_RDRND__
 149 #undef __DISABLE_RDRND__
 150 #pragma GCC pop_options
 151 #endif /* __DISABLE_RDRND__ */
 152
 153 #ifndef __RDPID__
 154 #pragma GCC push_options
 155 #pragma GCC target("rdpid")
 156 #define __DISABLE_RDPID__
 157 #endif /* __RDPID__ */
 158 extern __inline unsigned int
 159 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 160 _rdpid_u32 (void)
 161 {
 162   return __builtin_ia32_rdpid ();
 163 }
 164 #ifdef __DISABLE_RDPID__
 165 #undef __DISABLE_RDPID__
 166 #pragma GCC pop_options
 167 #endif /* __DISABLE_RDPID__ */
 168
 169 #ifdef  __x86_64__
 170
 171 #ifndef __FSGSBASE__
 172 #pragma GCC push_options
 173 #pragma GCC target("fsgsbase")
 174 #define __DISABLE_FSGSBASE__
 175 #endif /* __FSGSBASE__ */
 176 extern __inline unsigned int
 177 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 178 _readfsbase_u32 (void)
 179 {
 180   return __builtin_ia32_rdfsbase32 ();
 181 }
 182
 183 extern __inline unsigned long long
 184 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 185 _readfsbase_u64 (void)
 186 {
 187   return __builtin_ia32_rdfsbase64 ();
 188 }
 189
 190 extern __inline unsigned int
 191 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 192 _readgsbase_u32 (void)
 193 {
 194   return __builtin_ia32_rdgsbase32 ();
 195 }
 196
 197 extern __inline unsigned long long
 198 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 199 _readgsbase_u64 (void)
 200 {
 201   return __builtin_ia32_rdgsbase64 ();
 202 }
 203
 204 extern __inline void
 205 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 206 _writefsbase_u32 (unsigned int __B)
 207 {
 208   __builtin_ia32_wrfsbase32 (__B);
 209 }
 210
 211 extern __inline void
 212 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 213 _writefsbase_u64 (unsigned long long __B)
 214 {
 215   __builtin_ia32_wrfsbase64 (__B);
 216 }
 217
 218 extern __inline void
 219 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 220 _writegsbase_u32 (unsigned int __B)
 221 {
 222   __builtin_ia32_wrgsbase32 (__B);
 223 }
 224
 225 extern __inline void
 226 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 227 _writegsbase_u64 (unsigned long long __B)
 228 {
 229   __builtin_ia32_wrgsbase64 (__B);
 230 }
 231 #ifdef __DISABLE_FSGSBASE__
 232 #undef __DISABLE_FSGSBASE__
 233 #pragma GCC pop_options
 234 #endif /* __DISABLE_FSGSBASE__ */
 235
 236 #ifndef __RDRND__
 237 #pragma GCC push_options
 238 #pragma GCC target("rdrnd")
 239 #define __DISABLE_RDRND__
 240 #endif /* __RDRND__ */
 241 extern __inline int
 242 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 243 _rdrand64_step (unsigned long long *__P)
 244 {
 245   return __builtin_ia32_rdrand64_step (__P);
 246 }
 247 #ifdef __DISABLE_RDRND__
 248 #undef __DISABLE_RDRND__
 249 #pragma GCC pop_options
 250 #endif /* __DISABLE_RDRND__ */
 251
 252 #endif /* __x86_64__  */
 253
 254 #ifndef __PTWRITE__
 255 #pragma GCC push_options
 256 #pragma GCC target("ptwrite")
 257 #define __DISABLE_PTWRITE__
 258 #endif
 259
 260 #ifdef __x86_64__
 261 extern __inline void
 262 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 263 _ptwrite64 (unsigned long long __B)
 264 {
 265   __builtin_ia32_ptwrite64 (__B);
 266 }
 267 #endif /* __x86_64__ */
 268
 269 extern __inline void
 270 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 271 _ptwrite32 (unsigned __B)
 272 {
 273   __builtin_ia32_ptwrite32 (__B);
 274 }
 275 #ifdef __DISABLE_PTWRITE__
 276 #undef __DISABLE_PTWRITE__
 277 #pragma GCC pop_options
 278 #endif /* __DISABLE_PTWRITE__ */
 279
 280 #endif /* _IMMINTRIN_H_INCLUDED */