diff options
author | Florian Weimer <fweimer@redhat.com> | 2016-03-07 16:00:25 +0100 |
---|---|---|
committer | Florian Weimer <fweimer@redhat.com> | 2016-03-07 16:00:25 +0100 |
commit | 3c0f7407eedb524c9114bb675cd55b903c71daaa (patch) | |
tree | 0c5c22fd03aeece465c74675d6f277820db2f092 /sysdeps/x86_64/tst-audit10-aux.c | |
parent | 900056024b75eae8b550d7fee1dec9e71f28344e (diff) | |
download | glibc-3c0f7407eedb524c9114bb675cd55b903c71daaa.tar.gz glibc-3c0f7407eedb524c9114bb675cd55b903c71daaa.tar.xz glibc-3c0f7407eedb524c9114bb675cd55b903c71daaa.zip |
tst-audit4, tst-audit10: Compile AVX/AVX-512 code separately [BZ #19269]
This ensures that GCC will not use unsupported instructions before the run-time check to ensure support.
Diffstat (limited to 'sysdeps/x86_64/tst-audit10-aux.c')
-rw-r--r-- | sysdeps/x86_64/tst-audit10-aux.c | 41 |
1 files changed, 41 insertions, 0 deletions
diff --git a/sysdeps/x86_64/tst-audit10-aux.c b/sysdeps/x86_64/tst-audit10-aux.c new file mode 100644 index 0000000000..4398b8fd6f --- /dev/null +++ b/sysdeps/x86_64/tst-audit10-aux.c @@ -0,0 +1,41 @@ +/* Test case for preserved AVX512 registers in dynamic linker, -mavx512f part. + Copyright (C) 2012-2016 Free Software Foundation, Inc. + This file is part of the GNU C Library. + + The GNU C Library is free software; you can redistribute it and/or + modify it under the terms of the GNU Lesser General Public + License as published by the Free Software Foundation; either + version 2.1 of the License, or (at your option) any later version. + + The GNU C Library is distributed in the hope that it will be useful, + but WITHOUT ANY WARRANTY; without even the implied warranty of + MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the GNU + Lesser General Public License for more details. + + You should have received a copy of the GNU Lesser General Public + License along with the GNU C Library; if not, see + <http://www.gnu.org/licenses/>. */ + +#include <immintrin.h> +#include <stdlib.h> +#include <string.h> + +extern __m512i audit_test (__m512i, __m512i, __m512i, __m512i, + __m512i, __m512i, __m512i, __m512i); + +int +tst_audit10_aux (void) +{ +#ifdef __AVX512F__ + __m512i zmm = _mm512_setzero_si512 (); + __m512i ret = audit_test (zmm, zmm, zmm, zmm, zmm, zmm, zmm, zmm); + + zmm = _mm512_set1_epi64 (0x12349876); + + if (memcmp (&zmm, &ret, sizeof (ret))) + abort (); + return 0; +#else /* __AVX512F__ */ + return 77; +#endif /* __AVX512F__ */ +} |