diff options
| author | H.J. Lu <hongjiu.lu@intel.com> | 2009-07-10 12:04:14 -0700 |
|---|---|---|
| committer | Ulrich Drepper <drepper@redhat.com> | 2009-07-10 12:04:14 -0700 |
| commit | b0ecde3a63fd3e987137aa9eb76da3b556b14559 (patch) | |
| tree | 9ec97c379f41fcb36164d03ee5b852e1b3f1e59f /elf/tst-audit4.c | |
| parent | 786b74f41a076ac67b5d4fe59ab26e55745095df (diff) | |
| download | glibc-b0ecde3a63fd3e987137aa9eb76da3b556b14559.tar glibc-b0ecde3a63fd3e987137aa9eb76da3b556b14559.tar.gz glibc-b0ecde3a63fd3e987137aa9eb76da3b556b14559.tar.bz2 glibc-b0ecde3a63fd3e987137aa9eb76da3b556b14559.zip | |
Add AVX support to ld.so auditing for x86-64.
Diffstat (limited to 'elf/tst-audit4.c')
| -rw-r--r-- | elf/tst-audit4.c | 35 |
1 files changed, 35 insertions, 0 deletions
diff --git a/elf/tst-audit4.c b/elf/tst-audit4.c new file mode 100644 index 0000000000..b17d4a61a7 --- /dev/null +++ b/elf/tst-audit4.c @@ -0,0 +1,35 @@ +/* Test case for x86-64 preserved registers in dynamic linker. */ + +#ifdef __AVX__ +#include <stdlib.h> +#include <string.h> +#include <cpuid.h> +#include <immintrin.h> + +extern __m256i audit_test (__m256i, __m256i, __m256i, __m256i, + __m256i, __m256i, __m256i, __m256i); +int +main (void) +{ + unsigned int eax, ebx, ecx, edx; + + /* Run AVX test only if AVX is supported. */ + if (__get_cpuid (1, &eax, &ebx, &ecx, &edx) + && (ecx & bit_AVX)) + { + __m256i ymm = _mm256_setzero_si256 (); + __m256i ret = audit_test (ymm, ymm, ymm, ymm, ymm, ymm, ymm, ymm); + + ymm = _mm256_set1_epi32 (0x12349876); + if (memcmp (&ymm, &ret, sizeof (ret))) + abort (); + } + return 0; +} +#else +int +main (void) +{ + return 0; +} +#endif |