diff options
| author | Jakub Jelinek <jakub@redhat.com> | 2017-01-19 16:41:15 +0100 |
|---|---|---|
| committer | Jakub Jelinek <jakub@gcc.gnu.org> | 2017-01-19 16:41:15 +0100 |
| commit | 9db0a8c2bfe8e9602109d3fc3de0dc5e575b8c5c (patch) | |
| tree | 4bae35124712f9ca92f86fa84595ae73858cd929 | |
| parent | 0655c6d5561026bf5b3749d69cc3f30ea09ff66e (diff) | |
| download | gcc-9db0a8c2bfe8e9602109d3fc3de0dc5e575b8c5c.zip gcc-9db0a8c2bfe8e9602109d3fc3de0dc5e575b8c5c.tar.gz gcc-9db0a8c2bfe8e9602109d3fc3de0dc5e575b8c5c.tar.bz2 | |
re PR target/79127 (Error: invalid register for .seh_savexmm in matmul_i4.c)
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.
From-SVN: r244636
| -rw-r--r-- | libgfortran/ChangeLog | 8 | ||||
| -rw-r--r-- | libgfortran/acinclude.m4 | 9 | ||||
| -rwxr-xr-x | libgfortran/configure | 9 |
3 files changed, 24 insertions, 2 deletions
diff --git a/libgfortran/ChangeLog b/libgfortran/ChangeLog index 3335177..6d252be 100644 --- a/libgfortran/ChangeLog +++ b/libgfortran/ChangeLog @@ -1,3 +1,11 @@ +2017-01-19 Jakub Jelinek <jakub@redhat.com> + + 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 <jakub@redhat.com> PR other/79046 diff --git a/libgfortran/acinclude.m4 b/libgfortran/acinclude.m4 index 9a7f461..34e1407 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 f975e2a..20b5e68 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 () |