[reactos] 04/10: [VCRUNTIME] Add immintrin.h

[Timo Kreuzer]

https://git.reactos.org/?p=reactos.git;a=commitdiff;h=f4936069993e67e2ee9fc…

commit f4936069993e67e2ee9fc09b3ecfa3e7ebff5608
Author:     Timo Kreuzer <timo.kreuzer(a)reactos.org>
AuthorDate: Fri Oct 11 16:35:51 2024 +0300
Commit:     Timo Kreuzer <timo.kreuzer(a)reactos.org>
CommitDate: Sat Nov 16 20:01:49 2024 +0200

    [VCRUNTIME] Add immintrin.h
---
 sdk/include/vcruntime/immintrin.h | 171 ++++++++++++++++++++++++++++++++++++++
 sdk/include/vcruntime/intrin.h    |   2 +-
 2 files changed, 172 insertions(+), 1 deletion(-)

diff --git a/sdk/include/vcruntime/immintrin.h b/sdk/include/vcruntime/immintrin.h
new file mode 100644
index 00000000000..a819cfee33d
--- /dev/null
+++ b/sdk/include/vcruntime/immintrin.h
@@ -0,0 +1,171 @@
+/*
+ * PROJECT:     ReactOS SDK
+ * LICENSE:     MIT (https://spdx.org/licenses/MIT)
+ * PURPOSE:     Intrinsics for the SSE2 instruction set
+ * COPYRIGHT:   Copyright 2024 Timo Kreuzer (timo.kreuzer(a)reactos.org)
+ */
+
+#pragma once
+
+#define _INCLUDED_IMM
+
+//#include <wmmintrin.h>
+#include <emmintrin.h>
+
+#if defined(_MSC_VER) && !defined(__clang__)
+
+typedef union _DECLSPEC_INTRIN_TYPE  _CRT_ALIGN(32) __m256i
+{
+    __int8              m256i_i8[32];
+    __int16             m256i_i16[16];
+    __int32             m256i_i32[8];
+    __int64             m256i_i64[4];
+    unsigned __int8     m256i_u8[32];
+    unsigned __int16    m256i_u16[16];
+    unsigned __int32    m256i_u32[8];
+    unsigned __int64    m256i_u64[4];
+} __m256i;
+
+#else /* _MSC_VER */
+
+typedef char __v32qi __attribute__ ((__vector_size__ (32)));
+typedef short __v16hi __attribute__ ((__vector_size__ (32)));
+typedef long long __v4di __attribute__ ((__vector_size__ (32)));
+
+typedef long long __m256i __attribute__((__vector_size__(32), __may_alias__));
+
+#endif /* _MSC_VER */
+
+#ifdef __cplusplus
+extern "C" {
+#endif
+
+extern __m256i __cdecl _mm256_cmpeq_epi8(__m256i, __m256i);
+extern __m256i __cdecl _mm256_cmpeq_epi16(__m256i, __m256i);
+extern int __cdecl _mm256_movemask_epi8(__m256i);
+extern __m256i __cdecl _mm256_setzero_si256(void);
+extern void __cdecl _mm256_zeroupper(void);
+
+extern int __cdecl _rdrand16_step(unsigned short *random_val);
+extern int __cdecl _rdrand32_step(unsigned int *random_val);
+#if defined(_M_X64)
+extern int __cdecl _rdrand64_step(unsigned __int64 *random_val);
+#endif
+
+extern int __cdecl _rdseed16_step(unsigned short *random_val);
+extern int __cdecl _rdseed32_step(unsigned int *random_val);
+#if defined(_M_X64)
+extern int __cdecl _rdseed64_step(unsigned __int64 *random_val);
+#endif
+
+
+#if defined(_MSC_VER) && !defined(__clang__)
+
+#pragma intrinsic(_mm256_cmpeq_epi8)
+#pragma intrinsic(_mm256_cmpeq_epi16)
+#pragma intrinsic(_mm256_movemask_epi8)
+#pragma intrinsic(_mm256_setzero_si256)
+#pragma intrinsic(_mm256_zeroupper)
+
+#pragma intrinsic(_rdrand16_step)
+#pragma intrinsic(_rdrand32_step)
+#if defined(_M_X64)
+#pragma intrinsic(_rdrand64_step)
+#endif
+#pragma intrinsic(_rdseed16_step)
+#pragma intrinsic(_rdseed32_step)
+#if defined(_M_X64)
+#pragma intrinsic(_rdseed64_step)
+#endif
+
+#else /* _MSC_VER */
+
+#ifdef __clang__
+#define __ATTRIBUTE_SSE2__
__attribute__((__target__("sse2"),__min_vector_width__(128)))
+#define __ATTRIBUTE_AVX__
__attribute__((__target__("avx"),__min_vector_width__(256)))
+#define __ATTRIBUTE_AVX2__
__attribute__((__target__("avx2"),__min_vector_width__(256)))
+#else
+#define __ATTRIBUTE_SSE2__ __attribute__((__target__("sse2")))
+#define __ATTRIBUTE_AVX__ __attribute__((__target__("avx")))
+#define __ATTRIBUTE_AVX2__ __attribute__((__target__("avx2")))
+#endif
+#define __INTRIN_INLINE_SSE2 __INTRIN_INLINE __ATTRIBUTE_SSE2__
+#define __INTRIN_INLINE_AVX __INTRIN_INLINE __ATTRIBUTE_AVX__
+#define __INTRIN_INLINE_AVX2 __INTRIN_INLINE __ATTRIBUTE_AVX2__
+
+__INTRIN_INLINE_AVX __m256i __cdecl _mm256_cmpeq_epi8(__m256i __A, __m256i __B)
+{
+    return (__m256i)((__v32qi)__A == (__v32qi)__B);
+}
+
+__INTRIN_INLINE_AVX __m256i __cdecl _mm256_cmpeq_epi16(__m256i __A, __m256i __B)
+{
+    return (__m256i)((__v16hi)__A == (__v16hi)__B);
+}
+
+__INTRIN_INLINE_AVX2 int __cdecl _mm256_movemask_epi8(__m256i __A)
+{
+    return __builtin_ia32_pmovmskb256((__v32qi)__A);
+}
+
+__INTRIN_INLINE_AVX __m256i __cdecl _mm256_setzero_si256(void)
+{
+    return __extension__ (__m256i)(__v4di){ 0, 0, 0, 0 };
+}
+
+__INTRIN_INLINE void __cdecl _mm256_zeroupper(void)
+{
+    __asm__ __volatile__("vzeroupper");
+}
+
+__INTRIN_INLINE int _rdrand16_step(unsigned short* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdrand %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+
+__INTRIN_INLINE int _rdrand32_step(unsigned int* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdrand %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+
+#if defined(__x86_64__)
+__INTRIN_INLINE int _rdrand64_step(unsigned __int64* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdrand %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+#endif // __x86_64__
+
+__INTRIN_INLINE int _rdseed16_step(unsigned short* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdseed %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+
+__INTRIN_INLINE int _rdseed32_step(unsigned int* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdseed %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+
+#if defined(__x86_64__)
+__INTRIN_INLINE int _rdseed64_step(unsigned __int64* random_val)
+{
+    unsigned char ok;
+    __asm__ __volatile__("rdseed %0; setc %1" : "=r"(*random_val),
"=qm"(ok));
+    return (int)ok;
+}
+#endif // __x86_64__
+
+#endif /* _MSC_VER */
+
+#ifdef __cplusplus
+} // extern "C"
+#endif
diff --git a/sdk/include/vcruntime/intrin.h b/sdk/include/vcruntime/intrin.h
index 513c2667786..fda1dc4c8e9 100644
--- a/sdk/include/vcruntime/intrin.h
+++ b/sdk/include/vcruntime/intrin.h
@@ -9,7 +9,7 @@
 #include <stddef.h>
 
 #if defined(_M_IX86) || defined(_M_X64)
-//#include <immintrin.h>
+#include <immintrin.h>
 //#include <ammintrin.h>
 #include <xmmintrin.h> // native headers: immintrin.h -> wmmintrin.h ->
nmmintrin.h -> smmintrin.h -> tmmintrin.h -> pmmintrin.h -> emmintrin.h
 #endif /* _M_IX86 || _M_X64 */