11 #if defined(_M_IX86) || defined(_M_X64)
12 //#include <immintrin.h>
13 //#include <ammintrin.h>
14 #endif /* _M_IX86 || _M_X64 */
17 //#include <mm3dnow.h>
21 //#include <arm_neon.h>
25 #if defined(__cplusplus)
29 void* _AddressOfReturnAddress(void);
30 unsigned char _BitScanForward(unsigned long * _Index
, unsigned long _Mask
);
31 unsigned char _BitScanReverse(unsigned long * _Index
, unsigned long _Mask
);
32 long _InterlockedAnd(_Interlocked_operand_
long volatile * _Value
, long _Mask
);
33 short _InterlockedAnd16(_Interlocked_operand_
short volatile * _Value
, short _Mask
);
34 char _InterlockedAnd8(_Interlocked_operand_
char volatile * _Value
, char _Mask
);
35 long __cdecl
_InterlockedCompareExchange(_Interlocked_operand_
long volatile * _Destination
, long _Exchange
, long _Comparand
);
36 short _InterlockedCompareExchange16(_Interlocked_operand_
short volatile * _Destination
, short _Exchange
, short _Comparand
);
37 __int64
_InterlockedCompareExchange64(_Interlocked_operand_ __int64
volatile * _Destination
, __int64 _Exchange
, __int64 _Comparand
);
38 char _InterlockedCompareExchange8(_Interlocked_operand_
char volatile * _Destination
, char _Exchange
, char _Comparand
);
39 void * _InterlockedCompareExchangePointer(_Interlocked_operand_
void * volatile * _Destination
, void * _Exchange
, void * _Comparand
);
40 long __cdecl
_InterlockedDecrement(_Interlocked_operand_
long volatile * _Addend
);
41 short _InterlockedDecrement16(_Interlocked_operand_
short volatile * _Addend
);
42 long __cdecl
_InterlockedExchange(_Interlocked_operand_
long volatile * _Target
, long _Value
);
43 short _InterlockedExchange16(_Interlocked_operand_
short volatile * _Target
, short _Value
);
44 char _InterlockedExchange8(_Interlocked_operand_
char volatile * _Target
, char _Value
);
45 long __cdecl
_InterlockedExchangeAdd(_Interlocked_operand_
long volatile * _Addend
, long _Value
);
46 short _InterlockedExchangeAdd16(_Interlocked_operand_
short volatile * _Addend
, short _Value
);
47 char _InterlockedExchangeAdd8(_Interlocked_operand_
char volatile * _Addend
, char _Value
);
48 void * _InterlockedExchangePointer(_Interlocked_operand_
void * volatile * _Target
, void * _Value
);
49 long __cdecl
_InterlockedIncrement(_Interlocked_operand_
long volatile * _Addend
);
50 short _InterlockedIncrement16(_Interlocked_operand_
short volatile * _Addend
);
51 long _InterlockedOr(_Interlocked_operand_
long volatile * _Value
, long _Mask
);
52 short _InterlockedOr16(_Interlocked_operand_
short volatile * _Value
, short _Mask
);
53 char _InterlockedOr8(_Interlocked_operand_
char volatile * _Value
, char _Mask
);
54 long _InterlockedXor(_Interlocked_operand_
long volatile * _Value
, long _Mask
);
55 short _InterlockedXor16(_Interlocked_operand_
short volatile * _Value
, short _Mask
);
56 char _InterlockedXor8(_Interlocked_operand_
char volatile * _Value
, char _Mask
);
57 void _ReadBarrier(void);
58 void _ReadWriteBarrier(void);
59 void * _ReturnAddress(void);
60 void _WriteBarrier(void);
61 void __code_seg(const char *);
62 void __cdecl
__debugbreak(void);
63 __declspec(noreturn
) void __fastfail(unsigned int);
65 __int64 __cdecl
_abs64(__int64
);
66 unsigned char _bittest(long const *, long);
67 unsigned char _bittestandcomplement(long *, long);
68 unsigned char _bittestandreset(long *, long);
69 unsigned char _bittestandset(long *, long);
70 _Check_return_
unsigned __int64 __cdecl
_byteswap_uint64(_In_
unsigned __int64
);
71 _Check_return_
unsigned long __cdecl
_byteswap_ulong(_In_
unsigned long);
72 _Check_return_
unsigned short __cdecl
_byteswap_ushort(_In_
unsigned short);
73 void __cdecl
_disable(void);
74 void __cdecl
_enable(void);
75 unsigned char _interlockedbittestandreset(long volatile *, long);
76 unsigned char _interlockedbittestandset(long volatile *, long);
77 _Check_return_
unsigned long __cdecl
_lrotl(_In_
unsigned long, _In_
int);
78 _Check_return_
unsigned long __cdecl
_lrotr(_In_
unsigned long, _In_
int);
79 _Check_return_
unsigned int __cdecl
_rotl(_In_
unsigned int _Value
, _In_
int _Shift
);
80 _Check_return_
unsigned short __cdecl
_rotl16(_In_
unsigned short _Value
, _In_
unsigned char _Shift
);
81 _Check_return_
unsigned __int64 __cdecl
_rotl64(_In_
unsigned __int64 _Value
, _In_
int _Shift
);
82 _Check_return_
unsigned char __cdecl
_rotl8(_In_
unsigned char _Value
, _In_
unsigned char _Shift
);
83 _Check_return_
unsigned int __cdecl
_rotr(_In_
unsigned int _Value
, _In_
int _Shift
);
84 _Check_return_
unsigned short __cdecl
_rotr16(_In_
unsigned short _Value
, _In_
unsigned char _Shift
);
85 _Check_return_
unsigned __int64 __cdecl
_rotr64(_In_
unsigned __int64 _Value
, _In_
int _Shift
);
86 _Check_return_
unsigned char __cdecl
_rotr8(_In_
unsigned char _Value
, _In_
unsigned char _Shift
);
88 #if defined(_M_IX86) || defined(_M_X64)
90 void __cpuid(int[4], int);
91 void __cpuidex(int[4], int, int);
92 __int64
__emul(int, int);
93 unsigned __int64
__emulu(unsigned int, unsigned int);
94 unsigned int __getcallerseflags(void);
96 unsigned char __inbyte(unsigned short);
97 void __inbytestring(unsigned short, unsigned char *, unsigned long);
98 unsigned long __indword(unsigned short);
99 void __indwordstring(unsigned short, unsigned long *, unsigned long);
101 void __invlpg(void *);
102 unsigned short __inword(unsigned short);
103 void __inwordstring(unsigned short, unsigned short *, unsigned long);
105 unsigned __int64
__ll_lshift(unsigned __int64
, int);
106 __int64
__ll_rshift(__int64
, int);
107 unsigned int __lzcnt(unsigned int);
108 unsigned short __lzcnt16(unsigned short);
109 void __movsb(unsigned char *, unsigned char const *, size_t);
110 void __movsd(unsigned long *, unsigned long const *, size_t);
111 void __movsw(unsigned short *, unsigned short const *, size_t);
112 void __nvreg_restore_fence(void);
113 void __nvreg_save_fence(void);
114 void __outbyte(unsigned short, unsigned char);
115 void __outbytestring(unsigned short, unsigned char *, unsigned long);
116 void __outdword(unsigned short, unsigned long);
117 void __outdwordstring(unsigned short, unsigned long *, unsigned long);
118 void __outword(unsigned short, unsigned short);
119 void __outwordstring(unsigned short, unsigned short *, unsigned long);
120 unsigned int __popcnt(unsigned int);
121 unsigned short __popcnt16(unsigned short);
122 unsigned __int64
__rdtsc(void);
123 unsigned __int64
__rdtscp(unsigned int *);
124 unsigned __int64
__readmsr(unsigned long);
125 unsigned __int64
__readpmc(unsigned long);
126 unsigned long __segmentlimit(unsigned long);
129 void __stosb(unsigned char *, unsigned char, size_t);
130 void __stosd(unsigned long *, unsigned long, size_t);
131 void __stosw(unsigned short *, unsigned short, size_t);
132 void __svm_clgi(void);
133 void __svm_invlpga(void *, int);
134 void __svm_skinit(int);
135 void __svm_stgi(void);
136 void __svm_vmload(size_t);
137 void __svm_vmrun(size_t);
138 void __svm_vmsave(size_t);
140 unsigned __int64
__ull_rshift(unsigned __int64
, int);
141 void __vmx_off(void);
142 void __vmx_vmptrst(unsigned __int64
*);
144 void __writemsr(unsigned long, unsigned __int64
);
145 int __cdecl
_inp(unsigned short);
146 unsigned long __cdecl
_inpd(unsigned short);
147 unsigned short __cdecl
_inpw(unsigned short);
148 void _m_prefetch(void *);
149 void _m_prefetchw(volatile const void *);
151 void _mm_mfence(void);
152 void _mm_lfence(void);
153 void _mm_sfence(void);
154 void _mm_pause(void);
157 __m128i
_mm_abs_epi16(__m128i
);
158 __m128i
_mm_abs_epi32(__m128i
);
159 __m128i
_mm_abs_epi8(__m128i
);
160 __m64
_mm_abs_pi16(__m64
);
161 __m64
_mm_abs_pi32(__m64
);
162 __m64
_mm_abs_pi8(__m64
);
163 __m128i
_mm_add_epi16(__m128i
, __m128i
);
164 __m128i
_mm_add_epi32(__m128i
, __m128i
);
165 __m128i
_mm_add_epi64(__m128i
, __m128i
);
166 __m128i
_mm_add_epi8(__m128i
, __m128i
);
167 __m128d
_mm_add_pd(__m128d
, __m128d
);
168 __m128
_mm_add_ps(__m128
, __m128
);
169 __m128d
_mm_add_sd(__m128d
, __m128d
);
170 __m128
_mm_add_ss(__m128
, __m128
);
171 __m128i
_mm_adds_epi16(__m128i
, __m128i
);
172 __m128i
_mm_adds_epi8(__m128i
, __m128i
);
173 __m128i
_mm_adds_epu16(__m128i
, __m128i
);
174 __m128i
_mm_adds_epu8(__m128i
, __m128i
);
175 __m128d
_mm_addsub_pd(__m128d
, __m128d
);
176 __m128
_mm_addsub_ps(__m128
, __m128
);
177 __m128i
_mm_alignr_epi8(__m128i
, __m128i
, int);
178 __m64
_mm_alignr_pi8(__m64
, __m64
, int);
179 __m128d
_mm_and_pd(__m128d
, __m128d
);
180 __m128
_mm_and_ps(__m128
, __m128
);
181 __m128i
_mm_and_si128(__m128i
, __m128i
);
182 __m128d
_mm_andnot_pd(__m128d
, __m128d
);
183 __m128
_mm_andnot_ps(__m128
, __m128
);
184 __m128i
_mm_andnot_si128(__m128i
, __m128i
);
185 __m128i
_mm_avg_epu16(__m128i
, __m128i
);
186 __m128i
_mm_avg_epu8(__m128i
, __m128i
);
187 __m128i
_mm_blend_epi16(__m128i
, __m128i
, int);
188 __m128d
_mm_blend_pd(__m128d
, __m128d
, int);
189 __m128
_mm_blend_ps(__m128
, __m128
, int);
190 __m128i
_mm_blendv_epi8(__m128i
, __m128i
, __m128i
);
191 __m128d
_mm_blendv_pd(__m128d
, __m128d
, __m128d
);
192 __m128
_mm_blendv_ps(__m128
, __m128
, __m128
);
193 void _mm_clflush(void const *);
194 __m128i
_mm_cmpeq_epi16(__m128i
, __m128i
);
195 __m128i
_mm_cmpeq_epi32(__m128i
, __m128i
);
196 __m128i
_mm_cmpeq_epi64(__m128i
, __m128i
);
197 __m128i
_mm_cmpeq_epi8(__m128i
, __m128i
);
198 __m128d
_mm_cmpeq_pd(__m128d
, __m128d
);
199 __m128
_mm_cmpeq_ps(__m128
, __m128
);
200 __m128d
_mm_cmpeq_sd(__m128d
, __m128d
);
201 __m128
_mm_cmpeq_ss(__m128
, __m128
);
202 int _mm_cmpestra(__m128i
, int, __m128i
, int, int);
203 int _mm_cmpestrc(__m128i
, int, __m128i
, int, int);
204 int _mm_cmpestri(__m128i
, int, __m128i
, int, int);
205 __m128i
_mm_cmpestrm(__m128i
, int, __m128i
, int, int);
206 int _mm_cmpestro(__m128i
, int, __m128i
, int, int);
207 int _mm_cmpestrs(__m128i
, int, __m128i
, int, int);
208 int _mm_cmpestrz(__m128i
, int, __m128i
, int, int);
209 __m128d
_mm_cmpge_pd(__m128d
, __m128d
);
210 __m128
_mm_cmpge_ps(__m128
, __m128
);
211 __m128d
_mm_cmpge_sd(__m128d
, __m128d
);
212 __m128
_mm_cmpge_ss(__m128
, __m128
);
213 __m128i
_mm_cmpgt_epi16(__m128i
, __m128i
);
214 __m128i
_mm_cmpgt_epi32(__m128i
, __m128i
);
215 __m128i
_mm_cmpgt_epi64(__m128i
, __m128i
);
216 __m128i
_mm_cmpgt_epi8(__m128i
, __m128i
);
217 __m128d
_mm_cmpgt_pd(__m128d
, __m128d
);
218 __m128
_mm_cmpgt_ps(__m128
, __m128
);
219 __m128d
_mm_cmpgt_sd(__m128d
, __m128d
);
220 __m128
_mm_cmpgt_ss(__m128
, __m128
);
221 int _mm_cmpistra(__m128i
, __m128i
, int);
222 int _mm_cmpistrc(__m128i
, __m128i
, int);
223 int _mm_cmpistri(__m128i
, __m128i
, int);
224 __m128i
_mm_cmpistrm(__m128i
, __m128i
, int);
225 int _mm_cmpistro(__m128i
, __m128i
, int);
226 int _mm_cmpistrs(__m128i
, __m128i
, int);
227 int _mm_cmpistrz(__m128i
, __m128i
, int);
228 __m128d
_mm_cmple_pd(__m128d
, __m128d
);
229 __m128
_mm_cmple_ps(__m128
, __m128
);
230 __m128d
_mm_cmple_sd(__m128d
, __m128d
);
231 __m128
_mm_cmple_ss(__m128
, __m128
);
232 __m128i
_mm_cmplt_epi16(__m128i
, __m128i
);
233 __m128i
_mm_cmplt_epi32(__m128i
, __m128i
);
234 __m128i
_mm_cmplt_epi8(__m128i
, __m128i
);
235 __m128d
_mm_cmplt_pd(__m128d
, __m128d
);
236 __m128
_mm_cmplt_ps(__m128
, __m128
);
237 __m128d
_mm_cmplt_sd(__m128d
, __m128d
);
238 __m128
_mm_cmplt_ss(__m128
, __m128
);
239 __m128d
_mm_cmpneq_pd(__m128d
, __m128d
);
240 __m128
_mm_cmpneq_ps(__m128
, __m128
);
241 __m128d
_mm_cmpneq_sd(__m128d
, __m128d
);
242 __m128
_mm_cmpneq_ss(__m128
, __m128
);
243 __m128d
_mm_cmpnge_pd(__m128d
, __m128d
);
244 __m128
_mm_cmpnge_ps(__m128
, __m128
);
245 __m128d
_mm_cmpnge_sd(__m128d
, __m128d
);
246 __m128
_mm_cmpnge_ss(__m128
, __m128
);
247 __m128d
_mm_cmpngt_pd(__m128d
, __m128d
);
248 __m128
_mm_cmpngt_ps(__m128
, __m128
);
249 __m128d
_mm_cmpngt_sd(__m128d
, __m128d
);
250 __m128
_mm_cmpngt_ss(__m128
, __m128
);
251 __m128d
_mm_cmpnle_pd(__m128d
, __m128d
);
252 __m128
_mm_cmpnle_ps(__m128
, __m128
);
253 __m128d
_mm_cmpnle_sd(__m128d
, __m128d
);
254 __m128
_mm_cmpnle_ss(__m128
, __m128
);
255 __m128d
_mm_cmpnlt_pd(__m128d
, __m128d
);
256 __m128
_mm_cmpnlt_ps(__m128
, __m128
);
257 __m128d
_mm_cmpnlt_sd(__m128d
, __m128d
);
258 __m128
_mm_cmpnlt_ss(__m128
, __m128
);
259 __m128d
_mm_cmpord_pd(__m128d
, __m128d
);
260 __m128
_mm_cmpord_ps(__m128
, __m128
);
261 __m128d
_mm_cmpord_sd(__m128d
, __m128d
);
262 __m128
_mm_cmpord_ss(__m128
, __m128
);
263 __m128d
_mm_cmpunord_pd(__m128d
, __m128d
);
264 __m128
_mm_cmpunord_ps(__m128
, __m128
);
265 __m128d
_mm_cmpunord_sd(__m128d
, __m128d
);
266 __m128
_mm_cmpunord_ss(__m128
, __m128
);
267 int _mm_comieq_sd(__m128d
, __m128d
);
268 int _mm_comieq_ss(__m128
, __m128
);
269 int _mm_comige_sd(__m128d
, __m128d
);
270 int _mm_comige_ss(__m128
, __m128
);
271 int _mm_comigt_sd(__m128d
, __m128d
);
272 int _mm_comigt_ss(__m128
, __m128
);
273 int _mm_comile_sd(__m128d
, __m128d
);
274 int _mm_comile_ss(__m128
, __m128
);
275 int _mm_comilt_sd(__m128d
, __m128d
);
276 int _mm_comilt_ss(__m128
, __m128
);
277 int _mm_comineq_sd(__m128d
, __m128d
);
278 int _mm_comineq_ss(__m128
, __m128
);
279 unsigned int _mm_crc32_u16(unsigned int, unsigned short);
280 unsigned int _mm_crc32_u32(unsigned int, unsigned int);
281 unsigned int _mm_crc32_u8(unsigned int, unsigned char);
282 __m128
_mm_cvt_si2ss(__m128
, int);
283 int _mm_cvt_ss2si(__m128
);
284 __m128i
_mm_cvtepi16_epi32(__m128i
);
285 __m128i
_mm_cvtepi16_epi64(__m128i
);
286 __m128i
_mm_cvtepi32_epi64(__m128i
);
287 __m128d
_mm_cvtepi32_pd(__m128i
);
288 __m128
_mm_cvtepi32_ps(__m128i
);
289 __m128i
_mm_cvtepi8_epi16(__m128i
);
290 __m128i
_mm_cvtepi8_epi32(__m128i
);
291 __m128i
_mm_cvtepi8_epi64(__m128i
);
292 __m128i
_mm_cvtepu16_epi32(__m128i
);
293 __m128i
_mm_cvtepu16_epi64(__m128i
);
294 __m128i
_mm_cvtepu32_epi64(__m128i
);
295 __m128i
_mm_cvtepu8_epi16(__m128i
);
296 __m128i
_mm_cvtepu8_epi32(__m128i
);
297 __m128i
_mm_cvtepu8_epi64(__m128i
);
298 __m128i
_mm_cvtpd_epi32(__m128d
);
299 __m128
_mm_cvtpd_ps(__m128d
);
300 __m128i
_mm_cvtps_epi32(__m128
);
301 __m128d
_mm_cvtps_pd(__m128
);
302 int _mm_cvtsd_si32(__m128d
);
303 __m128
_mm_cvtsd_ss(__m128
, __m128d
);
304 int _mm_cvtsi128_si32(__m128i
);
305 __m128d
_mm_cvtsi32_sd(__m128d
, int);
306 __m128i
_mm_cvtsi32_si128(int);
307 __m128d
_mm_cvtss_sd(__m128d
, __m128
);
308 int _mm_cvtt_ss2si(__m128
);
309 __m128i
_mm_cvttpd_epi32(__m128d
);
310 __m128i
_mm_cvttps_epi32(__m128
);
311 int _mm_cvttsd_si32(__m128d
);
312 __m128d
_mm_div_pd(__m128d
, __m128d
);
313 __m128
_mm_div_ps(__m128
, __m128
);
314 __m128d
_mm_div_sd(__m128d
, __m128d
);
315 __m128
_mm_div_ss(__m128
, __m128
);
316 __m128d
_mm_dp_pd(__m128d
, __m128d
, int);
317 __m128
_mm_dp_ps(__m128
, __m128
, int);
318 int _mm_extract_epi16(__m128i
, int);
319 int _mm_extract_epi32(__m128i
, int);
320 int _mm_extract_epi8(__m128i
, int);
321 int _mm_extract_ps(__m128
, int);
322 __m128i
_mm_extract_si64(__m128i
, __m128i
);
323 __m128i
_mm_extracti_si64(__m128i
, int, int);
324 unsigned int _mm_getcsr(void);
325 __m128i
_mm_hadd_epi16(__m128i
, __m128i
);
326 __m128i
_mm_hadd_epi32(__m128i
, __m128i
);
327 __m128d
_mm_hadd_pd(__m128d
, __m128d
);
328 __m64
_mm_hadd_pi16(__m64
, __m64
);
329 __m64
_mm_hadd_pi32(__m64
, __m64
);
330 __m128
_mm_hadd_ps(__m128
, __m128
);
331 __m128i
_mm_hadds_epi16(__m128i
, __m128i
);
332 __m64
_mm_hadds_pi16(__m64
, __m64
);
333 __m128i
_mm_hsub_epi16(__m128i
, __m128i
);
334 __m128i
_mm_hsub_epi32(__m128i
, __m128i
);
335 __m128d
_mm_hsub_pd(__m128d
, __m128d
);
336 __m64
_mm_hsub_pi16(__m64
, __m64
);
337 __m64
_mm_hsub_pi32(__m64
, __m64
);
338 __m128
_mm_hsub_ps(__m128
, __m128
);
339 __m128i
_mm_hsubs_epi16(__m128i
, __m128i
);
340 __m64
_mm_hsubs_pi16(__m64
, __m64
);
341 __m128i
_mm_insert_epi16(__m128i
, int, int);
342 __m128i
_mm_insert_epi32(__m128i
, int, int);
343 __m128i
_mm_insert_epi8(__m128i
, int, int);
344 __m128
_mm_insert_ps(__m128
, __m128
, int);
345 __m128i
_mm_insert_si64(__m128i
, __m128i
);
346 __m128i
_mm_inserti_si64(__m128i
, __m128i
, int, int);
347 __m128i
_mm_lddqu_si128(__m128i
const *);
348 __m128d
_mm_load1_pd(double const *);
349 __m128d
_mm_load_pd(double const *);
350 __m128
_mm_load_ps(float const *);
351 __m128
_mm_load_ps1(float const *);
352 __m128d
_mm_load_sd(double const *);
353 __m128i
_mm_load_si128(__m128i
const *);
354 __m128
_mm_load_ss(float const *);
355 __m128d
_mm_loaddup_pd(double const *);
356 __m128d
_mm_loadh_pd(__m128d
, double const *);
357 __m128
_mm_loadh_pi(__m128
, __m64
const *);
358 __m128i
_mm_loadl_epi64(__m128i
const *);
359 __m128d
_mm_loadl_pd(__m128d
, double const *);
360 __m128
_mm_loadl_pi(__m128
, __m64
const *);
361 __m128d
_mm_loadr_pd(double const *);
362 __m128
_mm_loadr_ps(float const *);
363 __m128d
_mm_loadu_pd(double const *);
364 __m128
_mm_loadu_ps(float const *);
365 __m128i
_mm_loadu_si128(__m128i
const *);
366 __m128i
_mm_madd_epi16(__m128i
, __m128i
);
367 __m128i
_mm_maddubs_epi16(__m128i
, __m128i
);
368 __m64
_mm_maddubs_pi16(__m64
, __m64
);
369 void _mm_maskmoveu_si128(__m128i
, __m128i
, _Out_writes_bytes_(16) char *);
370 __m128i
_mm_max_epi16(__m128i
, __m128i
);
371 __m128i
_mm_max_epi32(__m128i
, __m128i
);
372 __m128i
_mm_max_epi8(__m128i
, __m128i
);
373 __m128i
_mm_max_epu16(__m128i
, __m128i
);
374 __m128i
_mm_max_epu32(__m128i
, __m128i
);
375 __m128i
_mm_max_epu8(__m128i
, __m128i
);
376 __m128d
_mm_max_pd(__m128d
, __m128d
);
377 __m128
_mm_max_ps(__m128
, __m128
);
378 __m128d
_mm_max_sd(__m128d
, __m128d
);
379 __m128
_mm_max_ss(__m128
, __m128
);
380 __m128i
_mm_min_epi16(__m128i
, __m128i
);
381 __m128i
_mm_min_epi32(__m128i
, __m128i
);
382 __m128i
_mm_min_epi8(__m128i
, __m128i
);
383 __m128i
_mm_min_epu16(__m128i
, __m128i
);
384 __m128i
_mm_min_epu32(__m128i
, __m128i
);
385 __m128i
_mm_min_epu8(__m128i
, __m128i
);
386 __m128d
_mm_min_pd(__m128d
, __m128d
);
387 __m128
_mm_min_ps(__m128
, __m128
);
388 __m128d
_mm_min_sd(__m128d
, __m128d
);
389 __m128
_mm_min_ss(__m128
, __m128
);
390 __m128i
_mm_minpos_epu16(__m128i
);
391 void _mm_monitor(void const *, unsigned int, unsigned int);
392 __m128i
_mm_move_epi64(__m128i
);
393 __m128d
_mm_move_sd(__m128d
, __m128d
);
394 __m128
_mm_move_ss(__m128
, __m128
);
395 __m128d
_mm_movedup_pd(__m128d
);
396 __m128
_mm_movehdup_ps(__m128
);
397 __m128
_mm_movehl_ps(__m128
, __m128
);
398 __m128
_mm_moveldup_ps(__m128
);
399 __m128
_mm_movelh_ps(__m128
, __m128
);
400 int _mm_movemask_epi8(__m128i
);
401 int _mm_movemask_pd(__m128d
);
402 int _mm_movemask_ps(__m128
);
403 __m64
_mm_movepi64_pi64(__m128i
);
404 __m128i
_mm_movpi64_epi64(__m64
);
405 __m128i
_mm_mpsadbw_epu8(__m128i
, __m128i
, int);
406 __m128i
_mm_mul_epi32(__m128i
, __m128i
);
407 __m128i
_mm_mul_epu32(__m128i
, __m128i
);
408 __m128d
_mm_mul_pd(__m128d
, __m128d
);
409 __m128
_mm_mul_ps(__m128
, __m128
);
410 __m128d
_mm_mul_sd(__m128d
, __m128d
);
411 __m128
_mm_mul_ss(__m128
, __m128
);
412 __m128i
_mm_mulhi_epi16(__m128i
, __m128i
);
413 __m128i
_mm_mulhi_epu16(__m128i
, __m128i
);
414 __m128i
_mm_mulhrs_epi16(__m128i
, __m128i
);
415 __m64
_mm_mulhrs_pi16(__m64
, __m64
);
416 __m128i
_mm_mullo_epi16(__m128i
, __m128i
);
417 __m128i
_mm_mullo_epi32(__m128i
, __m128i
);
418 void _mm_mwait(unsigned int, unsigned int);
419 __m128d
_mm_or_pd(__m128d
, __m128d
);
420 __m128
_mm_or_ps(__m128
, __m128
);
421 __m128i
_mm_or_si128(__m128i
, __m128i
);
422 __m128i
_mm_packs_epi16(__m128i
, __m128i
);
423 __m128i
_mm_packs_epi32(__m128i
, __m128i
);
424 __m128i
_mm_packus_epi16(__m128i
, __m128i
);
425 __m128i
_mm_packus_epi32(__m128i
, __m128i
);
426 int _mm_popcnt_u32(unsigned int);
427 void _mm_prefetch(_In_
char const *, _In_
int);
428 __m128
_mm_rcp_ps(__m128
);
429 __m128
_mm_rcp_ss(__m128
);
430 __m128d
_mm_round_pd(__m128d
, int);
431 __m128
_mm_round_ps(__m128
, int);
432 __m128d
_mm_round_sd(__m128d
, __m128d
, int);
433 __m128
_mm_round_ss(__m128
, __m128
, int);
434 __m128
_mm_rsqrt_ps(__m128
);
435 __m128
_mm_rsqrt_ss(__m128
);
436 __m128i
_mm_sad_epu8(__m128i
, __m128i
);
437 __m128i
_mm_set1_epi16(short);
438 __m128i
_mm_set1_epi32(int);
439 __m128i
_mm_set1_epi8(char);
440 __m128d
_mm_set1_pd(double);
441 __m128i
_mm_set_epi16(short, short, short, short, short, short, short, short);
442 __m128i
_mm_set_epi32(int, int, int, int);
443 __m128i
_mm_set_epi8(char, char, char, char, char, char, char, char, char, char, char, char, char, char, char, char);
444 __m128d
_mm_set_pd(double, double);
445 __m128
_mm_set_ps(float, float, float, float);
446 __m128
_mm_set_ps1(float);
447 __m128d
_mm_set_sd(double);
448 __m128
_mm_set_ss(float);
449 void _mm_setcsr(unsigned int);
450 __m128i
_mm_setl_epi64(__m128i
);
451 __m128i
_mm_setr_epi16(short, short, short, short, short, short, short, short);
452 __m128i
_mm_setr_epi32(int, int, int, int);
453 __m128i
_mm_setr_epi8(char, char, char, char, char, char, char, char, char, char, char, char, char, char, char, char);
454 __m128d
_mm_setr_pd(double, double);
455 __m128
_mm_setr_ps(float, float, float, float);
456 __m128d
_mm_setzero_pd(void);
457 __m128
_mm_setzero_ps(void);
458 __m128i
_mm_setzero_si128(void);
459 __m128i
_mm_shuffle_epi32(__m128i
, int);
460 __m128i
_mm_shuffle_epi8(__m128i
, __m128i
);
461 __m128d
_mm_shuffle_pd(__m128d
, __m128d
, int);
462 __m64
_mm_shuffle_pi8(__m64
, __m64
);
463 __m128
_mm_shuffle_ps(__m128
, __m128
, unsigned int);
464 __m128i
_mm_shufflehi_epi16(__m128i
, int);
465 __m128i
_mm_shufflelo_epi16(__m128i
, int);
466 __m128i
_mm_sign_epi16(__m128i
, __m128i
);
467 __m128i
_mm_sign_epi32(__m128i
, __m128i
);
468 __m128i
_mm_sign_epi8(__m128i
, __m128i
);
469 __m64
_mm_sign_pi16(__m64
, __m64
);
470 __m64
_mm_sign_pi32(__m64
, __m64
);
471 __m64
_mm_sign_pi8(__m64
, __m64
);
472 __m128i
_mm_sll_epi16(__m128i
, __m128i
);
473 __m128i
_mm_sll_epi32(__m128i
, __m128i
);
474 __m128i
_mm_sll_epi64(__m128i
, __m128i
);
475 __m128i
_mm_slli_epi16(__m128i
, int);
476 __m128i
_mm_slli_epi32(__m128i
, int);
477 __m128i
_mm_slli_epi64(__m128i
, int);
478 __m128i
_mm_slli_si128(__m128i
, int);
479 __m128d
_mm_sqrt_pd(__m128d
);
480 __m128
_mm_sqrt_ps(__m128
);
481 __m128d
_mm_sqrt_sd(__m128d
, __m128d
);
482 __m128
_mm_sqrt_ss(__m128
);
483 __m128i
_mm_sra_epi16(__m128i
, __m128i
);
484 __m128i
_mm_sra_epi32(__m128i
, __m128i
);
485 __m128i
_mm_srai_epi16(__m128i
, int);
486 __m128i
_mm_srai_epi32(__m128i
, int);
487 __m128i
_mm_srl_epi16(__m128i
, __m128i
);
488 __m128i
_mm_srl_epi32(__m128i
, __m128i
);
489 __m128i
_mm_srl_epi64(__m128i
, __m128i
);
490 __m128i
_mm_srli_epi16(__m128i
, int);
491 __m128i
_mm_srli_epi32(__m128i
, int);
492 __m128i
_mm_srli_epi64(__m128i
, int);
493 __m128i
_mm_srli_si128(__m128i
, int);
494 void _mm_store1_pd(double *, __m128d
);
495 void _mm_store_pd(double *, __m128d
);
496 void _mm_store_ps(float *, __m128
);
497 void _mm_store_ps1(float *, __m128
);
498 void _mm_store_sd(double *, __m128d
);
499 void _mm_store_si128(__m128i
*, __m128i
);
500 void _mm_store_ss(float *, __m128
);
501 void _mm_storeh_pd(double *, __m128d
);
502 void _mm_storeh_pi(__m64
*, __m128
);
503 void _mm_storel_epi64(__m128i
*, __m128i
);
504 void _mm_storel_pd(double *, __m128d
);
505 void _mm_storel_pi(__m64
*, __m128
);
506 void _mm_storer_pd(double *, __m128d
);
507 void _mm_storer_ps(float *, __m128
);
508 void _mm_storeu_pd(double *, __m128d
);
509 void _mm_storeu_ps(float *, __m128
);
510 void _mm_storeu_si128(__m128i
*, __m128i
);
511 __m128i
_mm_stream_load_si128(__m128i
*);
512 void _mm_stream_pd(double *, __m128d
);
513 void _mm_stream_ps(float *, __m128
);
514 void _mm_stream_sd(double *, __m128d
);
515 void _mm_stream_si128(__m128i
*, __m128i
);
516 void _mm_stream_si32(int *, int);
517 void _mm_stream_ss(float *, __m128
);
518 __m128i
_mm_sub_epi16(__m128i
, __m128i
);
519 __m128i
_mm_sub_epi32(__m128i
, __m128i
);
520 __m128i
_mm_sub_epi64(__m128i
, __m128i
);
521 __m128i
_mm_sub_epi8(__m128i
, __m128i
);
522 __m128d
_mm_sub_pd(__m128d
, __m128d
);
523 __m128
_mm_sub_ps(__m128
, __m128
);
524 __m128d
_mm_sub_sd(__m128d
, __m128d
);
525 __m128
_mm_sub_ss(__m128
, __m128
);
526 __m128i
_mm_subs_epi16(__m128i
, __m128i
);
527 __m128i
_mm_subs_epi8(__m128i
, __m128i
);
528 __m128i
_mm_subs_epu16(__m128i
, __m128i
);
529 __m128i
_mm_subs_epu8(__m128i
, __m128i
);
530 int _mm_testc_si128(__m128i
, __m128i
);
531 int _mm_testnzc_si128(__m128i
, __m128i
);
532 int _mm_testz_si128(__m128i
, __m128i
);
533 int _mm_ucomieq_sd(__m128d
, __m128d
);
534 int _mm_ucomieq_ss(__m128
, __m128
);
535 int _mm_ucomige_sd(__m128d
, __m128d
);
536 int _mm_ucomige_ss(__m128
, __m128
);
537 int _mm_ucomigt_sd(__m128d
, __m128d
);
538 int _mm_ucomigt_ss(__m128
, __m128
);
539 int _mm_ucomile_sd(__m128d
, __m128d
);
540 int _mm_ucomile_ss(__m128
, __m128
);
541 int _mm_ucomilt_sd(__m128d
, __m128d
);
542 int _mm_ucomilt_ss(__m128
, __m128
);
543 int _mm_ucomineq_sd(__m128d
, __m128d
);
544 int _mm_ucomineq_ss(__m128
, __m128
);
545 __m128i
_mm_unpackhi_epi16(__m128i
, __m128i
);
546 __m128i
_mm_unpackhi_epi32(__m128i
, __m128i
);
547 __m128i
_mm_unpackhi_epi64(__m128i
, __m128i
);
548 __m128i
_mm_unpackhi_epi8(__m128i
, __m128i
);
549 __m128d
_mm_unpackhi_pd(__m128d
, __m128d
);
550 __m128
_mm_unpackhi_ps(__m128
, __m128
);
551 __m128i
_mm_unpacklo_epi16(__m128i
, __m128i
);
552 __m128i
_mm_unpacklo_epi32(__m128i
, __m128i
);
553 __m128i
_mm_unpacklo_epi64(__m128i
, __m128i
);
554 __m128i
_mm_unpacklo_epi8(__m128i
, __m128i
);
555 __m128d
_mm_unpacklo_pd(__m128d
, __m128d
);
556 __m128
_mm_unpacklo_ps(__m128
, __m128
);
557 __m128d
_mm_xor_pd(__m128d
, __m128d
);
558 __m128
_mm_xor_ps(__m128
, __m128
);
559 __m128i
_mm_xor_si128(__m128i
, __m128i
);
562 int __cdecl
_outp(unsigned short, int);
563 unsigned long __cdecl
_outpd(unsigned short, unsigned long);
564 unsigned short __cdecl
_outpw(unsigned short, unsigned short);
565 int __cdecl
inp(unsigned short);
566 unsigned long __cdecl
inpd(unsigned short);
567 unsigned short __cdecl
inpw(unsigned short);
568 int __cdecl
outp(unsigned short, int);
569 unsigned long __cdecl
outpd(unsigned short, unsigned long);
570 unsigned short __cdecl
outpw(unsigned short, unsigned short);
572 #endif /* _M_IX86 || _M_X64 */
576 long _InterlockedAddLargeStatistic(_Interlocked_operand_ __int64
volatile * _Addend
, long _Value
);
577 void __addfsbyte(unsigned long, unsigned char);
578 void __addfsdword(unsigned long, unsigned long);
579 void __addfsword(unsigned long, unsigned short);
580 void __incfsbyte(unsigned long);
581 void __incfsdword(unsigned long);
582 void __incfsword(unsigned long);
583 unsigned long __readcr0(void);
584 unsigned long __readcr2(void);
585 unsigned long __readcr3(void);
586 unsigned long __readcr4(void);
587 unsigned long __readcr8(void);
588 unsigned int __readdr(unsigned int);
589 unsigned int __readeflags(void);
590 unsigned char __readfsbyte(unsigned long);
591 unsigned long __readfsdword(unsigned long);
592 unsigned short __readfsword(unsigned long);
593 void __writecr0(unsigned int);
594 void __writecr3(unsigned int);
595 void __writecr4(unsigned int);
596 void __writecr8(unsigned int);
597 void __writedr(unsigned int, unsigned int);
598 void __writeeflags(unsigned int);
599 void __writefsbyte(unsigned long, unsigned char);
600 void __writefsdword(unsigned long, unsigned long);
601 void __writefsword(unsigned long, unsigned short);
606 __m64
_m_from_float(float);
607 __m64
_m_from_int(int);
608 void _m_maskmovq(__m64
, __m64
, _Out_writes_bytes_(8) char *);
609 __m64
_m_packssdw(__m64
, __m64
);
610 __m64
_m_packsswb(__m64
, __m64
);
611 __m64
_m_packuswb(__m64
, __m64
);
612 __m64
_m_paddb(__m64
, __m64
);
613 __m64
_m_paddd(__m64
, __m64
);
614 __m64
_m_paddsb(__m64
, __m64
);
615 __m64
_m_paddsw(__m64
, __m64
);
616 __m64
_m_paddusb(__m64
, __m64
);
617 __m64
_m_paddusw(__m64
, __m64
);
618 __m64
_m_paddw(__m64
, __m64
);
619 __m64
_m_pand(__m64
, __m64
);
620 __m64
_m_pandn(__m64
, __m64
);
621 __m64
_m_pavgb(__m64
, __m64
);
622 __m64
_m_pavgusb(__m64
, __m64
);
623 __m64
_m_pavgw(__m64
, __m64
);
624 __m64
_m_pcmpeqb(__m64
, __m64
);
625 __m64
_m_pcmpeqd(__m64
, __m64
);
626 __m64
_m_pcmpeqw(__m64
, __m64
);
627 __m64
_m_pcmpgtb(__m64
, __m64
);
628 __m64
_m_pcmpgtd(__m64
, __m64
);
629 __m64
_m_pcmpgtw(__m64
, __m64
);
630 int _m_pextrw(__m64
, int);
631 __m64
_m_pf2id(__m64
);
632 __m64
_m_pf2iw(__m64
);
633 __m64
_m_pfacc(__m64
, __m64
);
634 __m64
_m_pfadd(__m64
, __m64
);
635 __m64
_m_pfcmpeq(__m64
, __m64
);
636 __m64
_m_pfcmpge(__m64
, __m64
);
637 __m64
_m_pfcmpgt(__m64
, __m64
);
638 __m64
_m_pfmax(__m64
, __m64
);
639 __m64
_m_pfmin(__m64
, __m64
);
640 __m64
_m_pfmul(__m64
, __m64
);
641 __m64
_m_pfnacc(__m64
, __m64
);
642 __m64
_m_pfpnacc(__m64
, __m64
);
643 __m64
_m_pfrcp(__m64
);
644 __m64
_m_pfrcpit1(__m64
, __m64
);
645 __m64
_m_pfrcpit2(__m64
, __m64
);
646 __m64
_m_pfrsqit1(__m64
, __m64
);
647 __m64
_m_pfrsqrt(__m64
);
648 __m64
_m_pfsub(__m64
, __m64
);
649 __m64
_m_pfsubr(__m64
, __m64
);
650 __m64
_m_pi2fd(__m64
);
651 __m64
_m_pi2fw(__m64
);
652 __m64
_m_pinsrw(__m64
, int, int);
653 __m64
_m_pmaddwd(__m64
, __m64
);
654 __m64
_m_pmaxsw(__m64
, __m64
);
655 __m64
_m_pmaxub(__m64
, __m64
);
656 __m64
_m_pminsw(__m64
, __m64
);
657 __m64
_m_pminub(__m64
, __m64
);
658 int _m_pmovmskb(__m64
);
659 __m64
_m_pmulhrw(__m64
, __m64
);
660 __m64
_m_pmulhuw(__m64
, __m64
);
661 __m64
_m_pmulhw(__m64
, __m64
);
662 __m64
_m_pmullw(__m64
, __m64
);
663 __m64
_m_por(__m64
, __m64
);
664 __m64
_m_psadbw(__m64
, __m64
);
665 __m64
_m_pshufw(__m64
, int);
666 __m64
_m_pslld(__m64
, __m64
);
667 __m64
_m_pslldi(__m64
, int);
668 __m64
_m_psllq(__m64
, __m64
);
669 __m64
_m_psllqi(__m64
, int);
670 __m64
_m_psllw(__m64
, __m64
);
671 __m64
_m_psllwi(__m64
, int);
672 __m64
_m_psrad(__m64
, __m64
);
673 __m64
_m_psradi(__m64
, int);
674 __m64
_m_psraw(__m64
, __m64
);
675 __m64
_m_psrawi(__m64
, int);
676 __m64
_m_psrld(__m64
, __m64
);
677 __m64
_m_psrldi(__m64
, int);
678 __m64
_m_psrlq(__m64
, __m64
);
679 __m64
_m_psrlqi(__m64
, int);
680 __m64
_m_psrlw(__m64
, __m64
);
681 __m64
_m_psrlwi(__m64
, int);
682 __m64
_m_psubb(__m64
, __m64
);
683 __m64
_m_psubd(__m64
, __m64
);
684 __m64
_m_psubsb(__m64
, __m64
);
685 __m64
_m_psubsw(__m64
, __m64
);
686 __m64
_m_psubusb(__m64
, __m64
);
687 __m64
_m_psubusw(__m64
, __m64
);
688 __m64
_m_psubw(__m64
, __m64
);
689 __m64
_m_pswapd(__m64
);
690 __m64
_m_punpckhbw(__m64
, __m64
);
691 __m64
_m_punpckhdq(__m64
, __m64
);
692 __m64
_m_punpckhwd(__m64
, __m64
);
693 __m64
_m_punpcklbw(__m64
, __m64
);
694 __m64
_m_punpckldq(__m64
, __m64
);
695 __m64
_m_punpcklwd(__m64
, __m64
);
696 __m64
_m_pxor(__m64
, __m64
);
697 float _m_to_float(__m64
);
698 int _m_to_int(__m64
);
699 __m64
_mm_add_si64(__m64
, __m64
);
700 __m128
_mm_cvt_pi2ps(__m128
, __m64
);
701 __m64
_mm_cvt_ps2pi(__m128
);
702 __m64
_mm_cvtpd_pi32(__m128d
);
703 __m128d
_mm_cvtpi32_pd(__m64
);
704 __m64
_mm_cvtt_ps2pi(__m128
);
705 __m64
_mm_cvttpd_pi32(__m128d
);
706 __m64
_mm_mul_su32(__m64
, __m64
);
707 __m128i
_mm_set1_epi64(__m64
);
708 __m64
_mm_set1_pi16(short);
709 __m64
_mm_set1_pi32(int);
710 __m64
_mm_set1_pi8(char);
711 __m128i
_mm_set_epi64(__m64
, __m64
);
712 __m64
_mm_set_pi16(short, short, short, short);
713 __m64
_mm_set_pi32(int, int);
714 __m64
_mm_set_pi8(char, char, char, char, char, char, char, char);
715 __m128i
_mm_setr_epi64(__m64
, __m64
);
716 __m64
_mm_setr_pi16(short, short, short, short);
717 __m64
_mm_setr_pi32(int, int);
718 __m64
_mm_setr_pi8(char, char, char, char, char, char, char, char);
719 __m64
_mm_setzero_si64(void);
720 void _mm_stream_pi(__m64
*, __m64
);
721 __m64
_mm_sub_si64(__m64
, __m64
);
728 unsigned char _BitScanForward64(unsigned long * _Index
, unsigned __int64 _Mask
);
729 unsigned char _BitScanReverse64(unsigned long * _Index
, unsigned __int64 _Mask
);
730 short _InterlockedAnd16_np(short volatile * _Value
, short _Mask
);
731 __int64
_InterlockedAnd64_np(__int64
volatile * _Value
, __int64 _Mask
);
732 char _InterlockedAnd8_np(char volatile * _Value
, char _Mask
);
733 long _InterlockedAnd_np(long volatile * _Value
, long _Mask
);
734 unsigned char _InterlockedCompareExchange128(_Interlocked_operand_ __int64
volatile * _Destination
, __int64 _ExchangeHigh
, __int64 _ExchangeLow
, __int64
* _ComparandResult
);
735 unsigned char _InterlockedCompareExchange128_np(__int64
volatile * _Destination
, __int64 _ExchangeHigh
, __int64 _ExchangeLow
, __int64
* _ComparandResult
);
736 short _InterlockedCompareExchange16_np(short volatile * _Destination
, short _Exchange
, short _Comparand
);
737 __int64
_InterlockedCompareExchange64_np(__int64
volatile * _Destination
, __int64 _Exchange
, __int64 _Comparand
);
738 void * _InterlockedCompareExchangePointer_np(void * volatile * _Destination
, void * _Exchange
, void * _Comparand
);
739 long _InterlockedCompareExchange_np(long volatile * _Destination
, long _Exchange
, long _Comparand
);
740 short _InterlockedOr16_np(short volatile * _Value
, short _Mask
);
741 __int64
_InterlockedOr64_np(__int64
volatile * _Value
, __int64 _Mask
);
742 char _InterlockedOr8_np(char volatile * _Value
, char _Mask
);
743 long _InterlockedOr_np(long volatile * _Value
, long _Mask
);
744 short _InterlockedXor16_np(short volatile * _Value
, short _Mask
);
745 __int64
_InterlockedXor64_np(__int64
volatile * _Value
, __int64 _Mask
);
746 char _InterlockedXor8_np(char volatile * _Value
, char _Mask
);
747 long _InterlockedXor_np(long volatile * _Value
, long _Mask
);
748 void __addgsbyte(unsigned long, unsigned char);
749 void __addgsdword(unsigned long, unsigned long);
750 void __addgsqword(unsigned long, unsigned __int64
);
751 void __addgsword(unsigned long, unsigned short);
752 void __faststorefence(void);
753 void __incgsbyte(unsigned long);
754 void __incgsdword(unsigned long);
755 void __incgsqword(unsigned long);
756 void __incgsword(unsigned long);
757 unsigned __int64
__lzcnt64(unsigned __int64
);
758 void __movsq(unsigned long long *, unsigned long long const *, size_t);
759 __int64
__mulh(__int64
, __int64
);
760 __int64
_mul128(__int64 _Multiplier
, __int64 _Multiplicand
, __int64
* _HighProduct
);
761 unsigned __int64
_umul128(unsigned __int64 _Multiplier
, unsigned __int64 _Multiplicand
, unsigned __int64
* _HighProduct
);
762 unsigned __int64
__popcnt64(unsigned __int64
);
763 unsigned __int64
__readcr0(void);
764 unsigned __int64
__readcr2(void);
765 unsigned __int64
__readcr3(void);
766 unsigned __int64
__readcr4(void);
767 unsigned __int64
__readcr8(void);
768 unsigned __int64
__readdr(unsigned int);
769 unsigned __int64
__readeflags(void);
770 unsigned char __readgsbyte(unsigned long);
771 unsigned long __readgsdword(unsigned long);
772 unsigned __int64
__readgsqword(unsigned long);
773 unsigned short __readgsword(unsigned long);
774 unsigned __int64
__shiftleft128(unsigned __int64 _LowPart
, unsigned __int64 _HighPart
, unsigned char _Shift
);
775 unsigned __int64
__shiftright128(unsigned __int64 _LowPart
, unsigned __int64 _HighPart
, unsigned char _Shift
);
776 void __stosq(unsigned __int64
*, unsigned __int64
, size_t);
777 unsigned __int64
__umulh(unsigned __int64
, unsigned __int64
);
778 unsigned char __vmx_on(unsigned __int64
*);
779 unsigned char __vmx_vmclear(unsigned __int64
*);
780 unsigned char __vmx_vmlaunch(void);
781 unsigned char __vmx_vmptrld(unsigned __int64
*);
782 unsigned char __vmx_vmread(size_t, size_t *);
783 unsigned char __vmx_vmresume(void);
784 unsigned char __vmx_vmwrite(size_t, size_t);
785 void __writecr0(unsigned __int64
);
786 void __writecr3(unsigned __int64
);
787 void __writecr4(unsigned __int64
);
788 void __writecr8(unsigned __int64
);
789 void __writedr(unsigned int, unsigned __int64
);
790 void __writeeflags(unsigned __int64
);
791 void __writegsbyte(unsigned long, unsigned char);
792 void __writegsdword(unsigned long, unsigned long);
793 void __writegsqword(unsigned long, unsigned __int64
);
794 void __writegsword(unsigned long, unsigned short);
795 unsigned char _bittest64(__int64
const *, __int64
);
796 unsigned char _bittestandcomplement64(__int64
*, __int64
);
797 unsigned char _bittestandreset64(__int64
*, __int64
);
798 unsigned char _bittestandset64(__int64
*, __int64
);
799 unsigned char _interlockedbittestandreset64(__int64
volatile *, __int64
);
800 unsigned char _interlockedbittestandset64(__int64
volatile *, __int64
);
801 unsigned __int64
_mm_crc32_u64(unsigned __int64
, unsigned __int64
);
803 __int64
_mm_cvtsd_si64(__m128d
);
804 __int64
_mm_cvtsd_si64x(__m128d
);
805 __int64
_mm_cvtsi128_si64(__m128i
);
806 __int64
_mm_cvtsi128_si64x(__m128i
);
807 __m128d
_mm_cvtsi64_sd(__m128d
, __int64
);
808 __m128i
_mm_cvtsi64_si128(__int64
);
809 __m128
_mm_cvtsi64_ss(__m128
, __int64
);
810 __m128d
_mm_cvtsi64x_sd(__m128d
, __int64
);
811 __m128i
_mm_cvtsi64x_si128(__int64
);
812 __m128
_mm_cvtsi64x_ss(__m128
, __int64
);
813 __int64
_mm_cvtss_si64(__m128
);
814 __int64
_mm_cvtss_si64x(__m128
);
815 __int64
_mm_cvttsd_si64(__m128d
);
816 __int64
_mm_cvttsd_si64x(__m128d
);
817 __int64
_mm_cvttss_si64(__m128
);
818 __int64
_mm_cvttss_si64x(__m128
);
819 __int64
_mm_extract_epi64(__m128i
, int);
820 __m128i
_mm_insert_epi64(__m128i
, __int64
, int);
821 __int64
_mm_popcnt_u64(unsigned __int64
);
822 __m128i
_mm_set1_epi64x(__int64
);
823 __m128i
_mm_set_epi64x(__int64
, __int64
);
824 void _mm_stream_si64x(__int64
*, __int64
);
828 #if defined(_M_ARM) || defined(_M_X64)
830 __int64
_InterlockedAnd64(_Interlocked_operand_ __int64
volatile * _Value
, __int64 _Mask
);
831 __int64
_InterlockedDecrement64(_Interlocked_operand_ __int64
volatile * _Addend
);
832 __int64
_InterlockedExchange64(_Interlocked_operand_ __int64
volatile * _Target
, __int64 _Value
);
833 __int64
_InterlockedExchangeAdd64(_Interlocked_operand_ __int64
volatile * _Addend
, __int64 _Value
);
834 __int64
_InterlockedIncrement64(_Interlocked_operand_ __int64
volatile * _Addend
);
835 __int64
_InterlockedOr64(_Interlocked_operand_ __int64
volatile * _Value
, __int64 _Mask
);
836 __int64
_InterlockedXor64(_Interlocked_operand_ __int64
volatile * _Value
, __int64 _Mask
);
838 #endif /* _M_ARM || _M_X64 */
842 int _AddSatInt(int, int);
843 double _CopyDoubleFromInt64(__int64
);
844 float _CopyFloatFromInt32(__int32
);
845 __int32
_CopyInt32FromFloat(float);
846 __int64
_CopyInt64FromDouble(double);
847 unsigned int _CountLeadingOnes(unsigned long);
848 unsigned int _CountLeadingOnes64(unsigned __int64
);
849 unsigned int _CountLeadingSigns(long);
850 unsigned int _CountLeadingSigns64(__int64
);
851 unsigned int _CountLeadingZeros(unsigned long);
852 unsigned int _CountLeadingZeros64(unsigned __int64
);
853 unsigned int _CountOneBits(unsigned long);
854 unsigned int _CountOneBits64(unsigned __int64
);
855 int _DAddSatInt(int, int);
856 int _DSubSatInt(int, int);
857 long _InterlockedAdd(_Interlocked_operand_
long volatile * _Addend
, long _Value
);
858 __int64
_InterlockedAdd64(_Interlocked_operand_ __int64
volatile * _Addend
, __int64 _Value
);
859 __int64
_InterlockedAdd64_acq(__int64
volatile * _Addend
, __int64 _Value
);
860 __int64
_InterlockedAdd64_nf(__int64
volatile * _Addend
, __int64 _Value
);
861 __int64
_InterlockedAdd64_rel(__int64
volatile * _Addend
, __int64 _Value
);
862 long _InterlockedAdd_acq(long volatile * _Addend
, long _Value
);
863 long _InterlockedAdd_nf(long volatile * _Addend
, long _Value
);
864 long _InterlockedAdd_rel(long volatile * _Addend
, long _Value
);
865 short _InterlockedAnd16_acq(short volatile * _Value
, short _Mask
);
866 short _InterlockedAnd16_nf(short volatile * _Value
, short _Mask
);
867 short _InterlockedAnd16_rel(short volatile * _Value
, short _Mask
);
868 __int64
_InterlockedAnd64_acq(__int64
volatile * _Value
, __int64 _Mask
);
869 __int64
_InterlockedAnd64_nf(__int64
volatile * _Value
, __int64 _Mask
);
870 __int64
_InterlockedAnd64_rel(__int64
volatile * _Value
, __int64 _Mask
);
871 char _InterlockedAnd8_acq(char volatile * _Value
, char _Mask
);
872 char _InterlockedAnd8_nf(char volatile * _Value
, char _Mask
);
873 char _InterlockedAnd8_rel(char volatile * _Value
, char _Mask
);
874 long _InterlockedAnd_acq(long volatile * _Value
, long _Mask
);
875 long _InterlockedAnd_nf(long volatile * _Value
, long _Mask
);
876 long _InterlockedAnd_rel(long volatile * _Value
, long _Mask
);
877 short _InterlockedCompareExchange16_acq(short volatile * _Destination
, short _Exchange
, short _Comparand
);
878 short _InterlockedCompareExchange16_nf(short volatile * _Destination
, short _Exchange
, short _Comparand
);
879 short _InterlockedCompareExchange16_rel(short volatile * _Destination
, short _Exchange
, short _Comparand
);
880 __int64
_InterlockedCompareExchange64_acq(__int64
volatile * _Destination
, __int64 _Exchange
, __int64 _Comparand
);
881 __int64
_InterlockedCompareExchange64_nf(__int64
volatile * _Destination
, __int64 _Exchange
, __int64 _Comparand
);
882 __int64
_InterlockedCompareExchange64_rel(__int64
volatile * _Destination
, __int64 _Exchange
, __int64 _Comparand
);
883 char _InterlockedCompareExchange8_acq(char volatile * _Destination
, char _Exchange
, char _Comparand
);
884 char _InterlockedCompareExchange8_nf(char volatile * _Destination
, char _Exchange
, char _Comparand
);
885 char _InterlockedCompareExchange8_rel(char volatile * _Destination
, char _Exchange
, char _Comparand
);
886 void * _InterlockedCompareExchangePointer_acq(void * volatile * _Destination
, void * _Exchange
, void * _Comparand
);
887 void * _InterlockedCompareExchangePointer_nf(void * volatile * _Destination
, void * _Exchange
, void * _Comparand
);
888 void * _InterlockedCompareExchangePointer_rel(void * volatile * _Destination
, void * _Exchange
, void * _Comparand
);
889 long _InterlockedCompareExchange_acq(long volatile * _Destination
, long _Exchange
, long _Comparand
);
890 long _InterlockedCompareExchange_nf(long volatile * _Destination
, long _Exchange
, long _Comparand
);
891 long _InterlockedCompareExchange_rel(long volatile * _Destination
, long _Exchange
, long _Comparand
);
892 short _InterlockedDecrement16_acq(short volatile * _Addend
);
893 short _InterlockedDecrement16_nf(short volatile * _Addend
);
894 short _InterlockedDecrement16_rel(short volatile * _Addend
);
895 __int64
_InterlockedDecrement64_acq(__int64
volatile * _Addend
);
896 __int64
_InterlockedDecrement64_nf(__int64
volatile * _Addend
);
897 __int64
_InterlockedDecrement64_rel(__int64
volatile * _Addend
);
898 long _InterlockedDecrement_acq(long volatile * _Addend
);
899 long _InterlockedDecrement_nf(long volatile * _Addend
);
900 long _InterlockedDecrement_rel(long volatile * _Addend
);
901 short _InterlockedExchange16_acq(short volatile * _Target
, short _Value
);
902 short _InterlockedExchange16_nf(short volatile * _Target
, short _Value
);
903 __int64
_InterlockedExchange64_acq(__int64
volatile * _Target
, __int64 _Value
);
904 __int64
_InterlockedExchange64_nf(__int64
volatile * _Target
, __int64 _Value
);
905 char _InterlockedExchange8_acq(char volatile * _Target
, char _Value
);
906 char _InterlockedExchange8_nf(char volatile * _Target
, char _Value
);
907 short _InterlockedExchangeAdd16_acq(short volatile * _Addend
, short _Value
);
908 short _InterlockedExchangeAdd16_nf(short volatile * _Addend
, short _Value
);
909 short _InterlockedExchangeAdd16_rel(short volatile * _Addend
, short _Value
);
910 __int64
_InterlockedExchangeAdd64_acq(__int64
volatile * _Addend
, __int64 _Value
);
911 __int64
_InterlockedExchangeAdd64_nf(__int64
volatile * _Addend
, __int64 _Value
);
912 __int64
_InterlockedExchangeAdd64_rel(__int64
volatile * _Addend
, __int64 _Value
);
913 char _InterlockedExchangeAdd8_acq(char volatile * _Addend
, char _Value
);
914 char _InterlockedExchangeAdd8_nf(char volatile * _Addend
, char _Value
);
915 char _InterlockedExchangeAdd8_rel(char volatile * _Addend
, char _Value
);
916 long _InterlockedExchangeAdd_acq(long volatile * _Addend
, long _Value
);
917 long _InterlockedExchangeAdd_nf(long volatile * _Addend
, long _Value
);
918 long _InterlockedExchangeAdd_rel(long volatile * _Addend
, long _Value
);
919 void * _InterlockedExchangePointer_acq(void * volatile * _Target
, void * _Value
);
920 void * _InterlockedExchangePointer_nf(void * volatile * _Target
, void * _Value
);
921 long _InterlockedExchange_acq(long volatile * _Target
, long _Value
);
922 long _InterlockedExchange_nf(long volatile * _Target
, long _Value
);
923 short _InterlockedIncrement16_acq(short volatile * _Addend
);
924 short _InterlockedIncrement16_nf(short volatile * _Addend
);
925 short _InterlockedIncrement16_rel(short volatile * _Addend
);
926 __int64
_InterlockedIncrement64_acq(__int64
volatile * _Addend
);
927 __int64
_InterlockedIncrement64_nf(__int64
volatile * _Addend
);
928 __int64
_InterlockedIncrement64_rel(__int64
volatile * _Addend
);
929 long _InterlockedIncrement_acq(long volatile * _Addend
);
930 long _InterlockedIncrement_nf(long volatile * _Addend
);
931 long _InterlockedIncrement_rel(long volatile * _Addend
);
932 short _InterlockedOr16_acq(short volatile * _Value
, short _Mask
);
933 short _InterlockedOr16_nf(short volatile * _Value
, short _Mask
);
934 short _InterlockedOr16_rel(short volatile * _Value
, short _Mask
);
935 __int64
_InterlockedOr64_acq(__int64
volatile * _Value
, __int64 _Mask
);
936 __int64
_InterlockedOr64_nf(__int64
volatile * _Value
, __int64 _Mask
);
937 __int64
_InterlockedOr64_rel(__int64
volatile * _Value
, __int64 _Mask
);
938 char _InterlockedOr8_acq(char volatile * _Value
, char _Mask
);
939 char _InterlockedOr8_nf(char volatile * _Value
, char _Mask
);
940 char _InterlockedOr8_rel(char volatile * _Value
, char _Mask
);
941 long _InterlockedOr_acq(long volatile * _Value
, long _Mask
);
942 long _InterlockedOr_nf(long volatile * _Value
, long _Mask
);
943 long _InterlockedOr_rel(long volatile * _Value
, long _Mask
);
944 short _InterlockedXor16_acq(short volatile * _Value
, short _Mask
);
945 short _InterlockedXor16_nf(short volatile * _Value
, short _Mask
);
946 short _InterlockedXor16_rel(short volatile * _Value
, short _Mask
);
947 __int64
_InterlockedXor64_acq(__int64
volatile * _Value
, __int64 _Mask
);
948 __int64
_InterlockedXor64_nf(__int64
volatile * _Value
, __int64 _Mask
);
949 __int64
_InterlockedXor64_rel(_Interlocked_operand_ __int64
volatile * _Value
, __int64 _Mask
);
950 char _InterlockedXor8_acq(char volatile * _Value
, char _Mask
);
951 char _InterlockedXor8_nf(char volatile * _Value
, char _Mask
);
952 char _InterlockedXor8_rel(char volatile * _Value
, char _Mask
);
953 long _InterlockedXor_acq(long volatile * _Value
, long _Mask
);
954 long _InterlockedXor_nf(long volatile * _Value
, long _Mask
);
955 long _InterlockedXor_rel(long volatile * _Value
, long _Mask
);
956 #if _MSC_FULL_VER >= 170040825
957 unsigned int _MoveFromCoprocessor(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
958 unsigned int _MoveFromCoprocessor2(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
960 int _MoveFromCoprocessor(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
961 int _MoveFromCoprocessor2(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
963 unsigned __int64
_MoveFromCoprocessor64(unsigned int, unsigned int, unsigned int);
964 void _MoveToCoprocessor(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
965 void _MoveToCoprocessor2(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int);
966 void _MoveToCoprocessor64(unsigned __int64
, unsigned int, unsigned int, unsigned int);
967 long _MulHigh(long, long);
968 unsigned long _MulUnsignedHigh(unsigned long, unsigned long);
969 int _ReadStatusReg(int);
970 int _SubSatInt(int, int);
971 void _WriteStatusReg(int, int, int);
972 void __emit(unsigned __int32
);
973 __int64
__ldrexd(__int64
volatile *);
974 void __cdecl
__prefetch(const void *);
975 unsigned __int64
__rdpmccntr64(void);
977 void __static_assert(int, const char *);
978 unsigned int __swi(unsigned int, ...);
979 unsigned int __hvc(unsigned int, ...);
980 int __trap(int, ...);
981 __int16
__iso_volatile_load16(const volatile __int16
*);
982 __int32
__iso_volatile_load32(const volatile __int32
*);
983 __int64
__iso_volatile_load64(const volatile __int64
*);
984 __int8
__iso_volatile_load8(const volatile __int8
*);
985 void __iso_volatile_store16(volatile __int16
*, __int16
);
986 void __iso_volatile_store32(volatile __int32
*, __int32
);
987 void __iso_volatile_store64(volatile __int64
*, __int64
);
988 void __iso_volatile_store8(volatile __int8
*, __int8
);
992 unsigned char _interlockedbittestandreset_acq(long volatile *, long);
993 unsigned char _interlockedbittestandreset_nf(long volatile *, long);
994 unsigned char _interlockedbittestandreset_rel(long volatile *, long);
995 unsigned char _interlockedbittestandset_acq(long volatile *, long);
996 unsigned char _interlockedbittestandset_nf(long volatile *, long);
997 unsigned char _interlockedbittestandset_rel(long volatile *, long);
998 int _isunordered(double, double);
999 int _isunorderedf(float, float);
1003 #if defined(_M_CEE_PURE)
1005 long _InterlockedCompareExchange(_Interlocked_operand_
long volatile * _Destination
, long _Exchange
, long _Comparand
);
1006 long _InterlockedDecrement(_Interlocked_operand_
long volatile * _Addend
);
1007 long _InterlockedIncrement(_Interlocked_operand_
long volatile * _Addend
);
1009 #endif /* _M_CEE_PURE */
1011 #if defined(__cplusplus)
1013 #endif /* __cplusplus */
1015 #if (defined(__GNUC__) || defined(__clang__)) && defined(_WIN32) // We can't use __MINGW32__ here
1016 # include "mingw32/intrin.h"
1017 #elif defined(_MSC_VER)
1018 # include "msc/intrin.h"
1020 # error Please implement intrinsics for your target compiler