x86/cpu: implement support for xgetbv through intrinsics
authorRonald S. Bultje <rsbultje@gmail.com>
Mon, 9 Jul 2012 00:21:26 +0000 (02:21 +0200)
committerMartin Storsjö <martin@martin.st>
Tue, 10 Jul 2012 11:33:17 +0000 (14:33 +0300)
Signed-off-by: Martin Storsjö <martin@martin.st>
configure
libavutil/x86/cpu.c

index a1506c9..76ad4c7 100755 (executable)
--- a/configure
+++ b/configure
@@ -1169,6 +1169,7 @@ HAVE_LIST="
     windows_h
     winsock2_h
     xform_asm
+    xgetbv
     xmm_clobbers
     yasm
 "
@@ -2742,6 +2743,7 @@ elif enabled sparc; then
 
 elif enabled x86; then
 
+    check_code ld immintrin.h "__xgetbv(0)" && enable xgetbv
     check_code ld intrin.h "__rdtsc()" && enable rdtsc
 
     check_code ld mmintrin.h "_mm_empty()" && enable mm_empty
index 5d77b0c..dfdc123 100644 (file)
         : "=a" (eax), "=S" (ebx), "=c" (ecx), "=d" (edx)        \
         : "0" (index))
 
+#if HAVE_INLINE_ASM
 #define xgetbv(index, eax, edx)                                 \
     __asm__ (".byte 0x0f, 0x01, 0xd0" : "=a"(eax), "=d"(edx) : "c" (index))
+#elif HAVE_XGETBV
+#include <immintrin.h>
+
+#define xgetbv(index, eax, edx)                 \
+    do {                                        \
+        uint64_t res = __xgetbv(index);         \
+        eax = res;                              \
+        edx = res >> 32;                        \
+    } while (0)
+#endif /* HAVE_XGETBV */
 
 #define get_eflags(x)                           \
     __asm__ volatile ("pushfl     \n"           \