24 #ifndef _X86INTRIN_H_INCLUDED
25 # error "Never use <ia32intrin.h> directly; include <x86intrin.h> instead."
33 return __builtin_ctz (__X);
38 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
41 return __builtin_ia32_bsrsi (__X);
46 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
49 return __builtin_bswap32 (__X);
54 extern __inline
unsigned int
55 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
56 __crc32b (
unsigned int __C,
unsigned char __V)
58 return __builtin_ia32_crc32qi (__C, __V);
61 extern __inline
unsigned int
62 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
63 __crc32w (
unsigned int __C,
unsigned short __V)
65 return __builtin_ia32_crc32hi (__C, __V);
68 extern __inline
unsigned int
69 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
70 __crc32d (
unsigned int __C,
unsigned int __V)
72 return __builtin_ia32_crc32si (__C, __V);
78 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
79 __popcntd (
unsigned int __X)
81 return __builtin_popcount (__X);
85 extern __inline
unsigned long long
86 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
89 return __builtin_ia32_rdpmc (__S);
93 extern __inline
unsigned long long
94 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
97 return __builtin_ia32_rdtsc ();
101 extern __inline
unsigned long long
102 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
103 __rdtscp (
unsigned int *
__A)
105 return __builtin_ia32_rdtscp (__A);
109 extern __inline
unsigned char
110 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
111 __rolb (
unsigned char __X,
int __C)
117 extern __inline
unsigned short
118 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
119 __rolw (
unsigned short __X,
int __C)
121 return __builtin_ia32_rolhi (__X, __C);
125 extern __inline
unsigned int
126 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
127 __rold (
unsigned int __X,
int __C)
129 return (__X << __C) | (__X >> (32 -
__C));
133 extern __inline
unsigned char
134 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
135 __rorb (
unsigned char __X,
int __C)
137 return __builtin_ia32_rorqi (__X, __C);
141 extern __inline
unsigned short
142 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
143 __rorw (
unsigned short __X,
int __C)
145 return __builtin_ia32_rorhi (__X, __C);
149 extern __inline
unsigned int
150 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
151 __rord (
unsigned int __X,
int __C)
153 return (__X >> __C) | (__X << (32 -
__C));
158 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
161 __builtin_ia32_pause ();
167 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
168 __bsfq (
long long __X)
170 return __builtin_ctzll (__X);
175 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
176 __bsrq (
long long __X)
178 return __builtin_ia32_bsrdi (__X);
182 extern __inline
long long
183 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
184 __bswapq (
long long __X)
186 return __builtin_bswap64 (__X);
191 extern __inline
unsigned long long
192 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
193 __crc32q (
unsigned long long __C,
unsigned long long __V)
195 return __builtin_ia32_crc32di (__C, __V);
200 extern __inline
long long
201 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
202 __popcntq (
unsigned long long __X)
204 return __builtin_popcountll (__X);
208 extern __inline
unsigned long long
209 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
210 __rolq (
unsigned long long __X,
int __C)
212 return (__X << __C) | (__X >> (64 -
__C));
216 extern __inline
unsigned long long
217 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
218 __rorq (
unsigned long long __X,
int __C)
220 return (__X >> __C) | (__X << (64 -
__C));
223 #define _bswap64(a) __bswapq(a)
224 #define _popcnt64(a) __popcntq(a)
225 #define _lrotl(a,b) __rolq((a), (b))
226 #define _lrotr(a,b) __rorq((a), (b))
228 #define _lrotl(a,b) __rold((a), (b))
229 #define _lrotr(a,b) __rord((a), (b))
232 #define _bit_scan_forward(a) __bsfd(a)
233 #define _bit_scan_reverse(a) __bsrd(a)
234 #define _bswap(a) __bswapd(a)
235 #define _popcnt32(a) __popcntd(a)
236 #define _rdpmc(a) __rdpmc(a)
237 #define _rdtsc() __rdtsc()
238 #define _rdtscp(a) __rdtscp(a)
239 #define _rotwl(a,b) __rolw((a), (b))
240 #define _rotwr(a,b) __rorw((a), (b))
241 #define _rotl(a,b) __rold((a), (b))
242 #define _rotr(a,b) __rord((a), (b))
__inline int __m128d __V
Definition: avxintrin.h:1061
__inline void __m256d __A
Definition: avxintrin.h:828
__inline unsigned char int __C return __builtin_ia32_rolqi(__X, __C)
__inline unsigned char unsigned int __X
Definition: adxintrin.h:33
__inline unsigned short int __C
Definition: ia32intrin.h:120
__inline int __attribute__((__gnu_inline__, __always_inline__, __artificial__)) __bsfd(int __X)
Definition: ia32intrin.h:30