From d6c831fb02edf685d688511de4d6c8084e490d66 Mon Sep 17 00:00:00 2001 From: jakub Date: Thu, 19 Jan 2017 15:41:15 +0000 Subject: [PATCH] PR target/79127 * acinclude.m4 (LIBGFOR_CHECK_AVX512F): Ensure the test clobbers some zmm16+ registers to verify they are handled by unwind info properly if needed. * configure: Regenerated. git-svn-id: svn+ssh://gcc.gnu.org/svn/gcc/trunk@244636 138bc75d-0d04-0410-961f-82ee72b054a4 --- libgfortran/ChangeLog | 8 ++++++++ libgfortran/acinclude.m4 | 9 ++++++++- libgfortran/configure | 9 ++++++++- 3 files changed, 24 insertions(+), 2 deletions(-) diff --git a/libgfortran/ChangeLog b/libgfortran/ChangeLog index 3335177eebe6..6d252be9186c 100644 --- a/libgfortran/ChangeLog +++ b/libgfortran/ChangeLog @@ -1,3 +1,11 @@ +2017-01-19 Jakub Jelinek + + PR target/79127 + * acinclude.m4 (LIBGFOR_CHECK_AVX512F): Ensure the test clobbers + some zmm16+ registers to verify they are handled by unwind info + properly if needed. + * configure: Regenerated. + 2017-01-17 Jakub Jelinek PR other/79046 diff --git a/libgfortran/acinclude.m4 b/libgfortran/acinclude.m4 index 9a7f461af3c4..34e14071aebd 100644 --- a/libgfortran/acinclude.m4 +++ b/libgfortran/acinclude.m4 @@ -437,7 +437,14 @@ AC_DEFUN([LIBGFOR_CHECK_AVX512F], [ typedef double __m512d __attribute__ ((__vector_size__ (64))); __m512d _mm512_add (__m512d a) { - return __builtin_ia32_addpd512_mask (a, a, a, 1, 4); + __m512d b = __builtin_ia32_addpd512_mask (a, a, a, 1, 4); + /* For -m64/-mx32 also verify that code will work even if + the target uses call saved zmm16+ and needs to emit + unwind info for them (e.g. on mingw). See PR79127. */ +#ifdef __x86_64__ + asm volatile ("" : : : "zmm16", "zmm17", "zmm18", "zmm19"); +#endif + return b; }]], [[]])], AC_DEFINE(HAVE_AVX512F, 1, [Define if AVX512f instructions can be compiled.]), diff --git a/libgfortran/configure b/libgfortran/configure index f975e2abc50f..20b5e6817126 100755 --- a/libgfortran/configure +++ b/libgfortran/configure @@ -26300,7 +26300,14 @@ rm -f core conftest.err conftest.$ac_objext conftest.$ac_ext typedef double __m512d __attribute__ ((__vector_size__ (64))); __m512d _mm512_add (__m512d a) { - return __builtin_ia32_addpd512_mask (a, a, a, 1, 4); + __m512d b = __builtin_ia32_addpd512_mask (a, a, a, 1, 4); + /* For -m64/-mx32 also verify that code will work even if + the target uses call saved zmm16+ and needs to emit + unwind info for them (e.g. on mingw). See PR79127. */ +#ifdef __x86_64__ + asm volatile ("" : : : "zmm16", "zmm17", "zmm18", "zmm19"); +#endif + return b; } int main () -- 2.39.5