This is the mail archive of the
glibc-cvs@sourceware.org
mailing list for the glibc project.
GNU C Library master sources branch hjl/pr19590 created. glibc-2.22-723-g0ba41c4
- From: hjl at sourceware dot org
- To: glibc-cvs at sourceware dot org
- Date: 16 Feb 2016 18:52:18 -0000
- Subject: GNU C Library master sources branch hjl/pr19590 created. glibc-2.22-723-g0ba41c4
This is an automated email from the git hooks/post-receive script. It was
generated because a ref change was pushed to the repository containing
the project "GNU C Library master sources".
The branch, hjl/pr19590 has been created
at 0ba41c40474348422f138744f162d33f7069668a (commit)
- Log -----------------------------------------------------------------
http://sourceware.org/git/gitweb.cgi?p=glibc.git;a=commitdiff;h=0ba41c40474348422f138744f162d33f7069668a
commit 0ba41c40474348422f138744f162d33f7069668a
Author: H.J. Lu <hjl.tools@gmail.com>
Date: Tue Feb 16 10:49:01 2016 -0800
Rewrite test-libmvec-alias
diff --git a/sysdeps/x86_64/fpu/Makefile b/sysdeps/x86_64/fpu/Makefile
index 1db3532..d689ff3 100644
--- a/sysdeps/x86_64/fpu/Makefile
+++ b/sysdeps/x86_64/fpu/Makefile
@@ -29,7 +29,9 @@ endif
ifeq ($(subdir),math)
ifeq ($(build-mathvec),yes)
libmvec-tests += double-vlen2 double-vlen4 double-vlen4-avx2 \
- float-vlen4 float-vlen8 float-vlen8-avx2 libmvec-alias
+ float-vlen4 float-vlen8 float-vlen8-avx2
+
+tests += test-libmvec-alias
modules-names += test-libmvec-alias-mod
test-libmvec-alias-mod.so-no-z-defs = yes
@@ -38,13 +40,7 @@ $(objpfx)test-libmvec-alias-mod.so: $(objpfx)../mathvec/libmvec_nonshared.a \
$(libmvec)
ifeq (yes,$(config-cflags-avx512))
-libmvec-tests += double-vlen8 float-vlen16 libmvec-alias-avx512
-modules-names += test-libmvec-alias-avx512-mod
-test-libmvec-alias-avx512-mod.so-no-z-defs = yes
-
-$(objpfx)test-libmvec-alias-avx512: $(objpfx)test-libmvec-alias-avx512-mod.so
-$(objpfx)test-libmvec-alias-avx512-mod.so: \
- $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec)
+libmvec-tests += double-vlen8 float-vlen16
endif
double-vlen4-arch-ext-cflags = -mavx
diff --git a/sysdeps/x86_64/fpu/svml_finite_alias.S b/sysdeps/x86_64/fpu/svml_finite_alias.S
index 8314cf4..2dcfc37 100644
--- a/sysdeps/x86_64/fpu/svml_finite_alias.S
+++ b/sysdeps/x86_64/fpu/svml_finite_alias.S
@@ -23,7 +23,7 @@
#define ALIAS_IMPL(alias, target) \
ENTRY (alias); \
- jmp target@PLT; \
+ jmp *target@GOTPCREL(%rip); \
END (alias)
.text
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-mod.c b/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-mod.c
deleted file mode 100644
index 64218f8..0000000
--- a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-mod.c
+++ /dev/null
@@ -1,46 +0,0 @@
-/* Part of test to build shared library to ensure link against
- *_finite aliases from libmvec.
- Copyright (C) 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 "test-double-vlen8.h"
-#define VEC_TYPE __m512d
-
-VECTOR_WRAPPER (WRAPPER_NAME (log), _ZGVeN8v___log_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (exp), _ZGVeN8v___exp_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (pow), _ZGVeN8vv___pow_finite)
-
-#undef FUNC
-#undef FLOAT
-#undef BUILD_COMPLEX
-#undef TEST_MSG
-#undef CHOOSE
-#undef FUNC_TEST
-#undef VEC_TYPE
-#undef VECTOR_WRAPPER
-#undef VECTOR_WRAPPER_ff
-#undef VEC_SUFF
-#undef VEC_LEN
-
-#include "test-float-vlen16.h"
-#define VEC_TYPE __m512
-
-VECTOR_WRAPPER (WRAPPER_NAME (logf), _ZGVeN16v___logf_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (expf), _ZGVeN16v___expf_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (powf), _ZGVeN16vv___powf_finite)
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-wrappers.c b/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-wrappers.c
deleted file mode 100644
index 9d841c9..0000000
--- a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512-wrappers.c
+++ /dev/null
@@ -1 +0,0 @@
-/* Dummy file. */
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512.c b/sysdeps/x86_64/fpu/test-libmvec-alias-avx512.c
deleted file mode 100644
index 8d11234..0000000
--- a/sysdeps/x86_64/fpu/test-libmvec-alias-avx512.c
+++ /dev/null
@@ -1,43 +0,0 @@
-/* Part of test to ensure link against *_finite aliases from libmvec.
- Copyright (C) 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 <init-arch.h>
-
-extern double log_vlen8 (double);
-extern double exp_vlen8 (double);
-extern double pow_vlen8 (double, double);
-
-extern float logf_vlen16 (float);
-extern float expf_vlen16 (float);
-extern float powf_vlen16 (float, float);
-
-int main(void)
-{
- if (!HAS_ARCH_FEATURE (AVX512F_Usable)) return 0;
-
- if (log_vlen8(1.0) != 0.0
- || logf_vlen16(1.0) != 0.0) abort();
-
- if (exp_vlen8(0.0) != 1.0
- || expf_vlen16(0.0) != 1.0) abort();
-
- if (pow_vlen8(1.0, 1.0) != 1.0
- || powf_vlen16(1.0, 1.0) != 1.0) abort();
-
- return 0;
-}
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias-mod.c b/sysdeps/x86_64/fpu/test-libmvec-alias-mod.c
deleted file mode 100644
index 37c2d75..0000000
--- a/sysdeps/x86_64/fpu/test-libmvec-alias-mod.c
+++ /dev/null
@@ -1,86 +0,0 @@
-/* Part of test to build shared library to ensure link against
- *_finite aliases from libmvec.
- Copyright (C) 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 "test-double-vlen2.h"
-#define VEC_TYPE __m128d
-
-VECTOR_WRAPPER (WRAPPER_NAME (log), _ZGVbN2v___log_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (exp), _ZGVbN2v___exp_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (pow), _ZGVbN2vv___pow_finite)
-
-#undef VEC_TYPE
-#undef VECTOR_WRAPPER
-#undef VECTOR_WRAPPER_ff
-#undef VEC_SUFF
-#undef VEC_LEN
-
-#include "test-double-vlen4.h"
-#define VEC_TYPE __m256d
-
-VECTOR_WRAPPER (WRAPPER_NAME (log), _ZGVcN4v___log_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (exp), _ZGVcN4v___exp_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (pow), _ZGVcN4vv___pow_finite)
-
-#undef VEC_SUFF
-#define VEC_SUFF _vlen4_avx2
-
-VECTOR_WRAPPER (WRAPPER_NAME (log), _ZGVdN4v___log_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (exp), _ZGVdN4v___exp_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (pow), _ZGVdN4vv___pow_finite)
-
-#undef FUNC
-#undef FLOAT
-#undef BUILD_COMPLEX
-#undef TEST_MSG
-#undef CHOOSE
-#undef FUNC_TEST
-#undef VEC_TYPE
-#undef VECTOR_WRAPPER
-#undef VECTOR_WRAPPER_ff
-#undef VEC_SUFF
-#undef VEC_LEN
-
-#include "test-float-vlen4.h"
-#define VEC_TYPE __m128
-
-VECTOR_WRAPPER (WRAPPER_NAME (logf), _ZGVbN4v___logf_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (expf), _ZGVbN4v___expf_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (powf), _ZGVbN4vv___powf_finite)
-
-#undef VEC_TYPE
-#undef VECTOR_WRAPPER
-#undef VECTOR_WRAPPER_ff
-#undef VEC_SUFF
-#undef VEC_LEN
-
-#include "test-float-vlen8.h"
-#define VEC_TYPE __m256
-
-VECTOR_WRAPPER (WRAPPER_NAME (logf), _ZGVcN8v___logf_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (expf), _ZGVcN8v___expf_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (powf), _ZGVcN8vv___powf_finite)
-
-#undef VEC_SUFF
-#define VEC_SUFF _vlen8_avx2
-
-VECTOR_WRAPPER (WRAPPER_NAME (logf), _ZGVdN8v___logf_finite)
-VECTOR_WRAPPER (WRAPPER_NAME (expf), _ZGVdN8v___expf_finite)
-VECTOR_WRAPPER_ff (WRAPPER_NAME (powf), _ZGVdN8vv___powf_finite)
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias-wrappers.c b/sysdeps/x86_64/fpu/test-libmvec-alias-wrappers.c
deleted file mode 100644
index 9d841c9..0000000
--- a/sysdeps/x86_64/fpu/test-libmvec-alias-wrappers.c
+++ /dev/null
@@ -1 +0,0 @@
-/* Dummy file. */
diff --git a/sysdeps/x86_64/fpu/test-libmvec-alias.c b/sysdeps/x86_64/fpu/test-libmvec-alias.c
index 429b19e..b0aedef 100644
--- a/sysdeps/x86_64/fpu/test-libmvec-alias.c
+++ b/sysdeps/x86_64/fpu/test-libmvec-alias.c
@@ -16,66 +16,10 @@
License along with the GNU C Library; if not, see
<http://www.gnu.org/licenses/>. */
-#include <init-arch.h>
+extern int test (void);
-extern double log_vlen2 (double);
-extern double exp_vlen2 (double);
-extern double pow_vlen2 (double, double);
-
-extern double log_vlen4 (double);
-extern double exp_vlen4 (double);
-extern double pow_vlen4 (double, double);
-
-extern double log_vlen4_avx2 (double);
-extern double exp_vlen4_avx2 (double);
-extern double pow_vlen4_avx2 (double, double);
-
-extern float logf_vlen4 (float);
-extern float expf_vlen4 (float);
-extern float powf_vlen4 (float, float);
-
-extern float logf_vlen8 (float);
-extern float expf_vlen8 (float);
-extern float powf_vlen8 (float, float);
-
-extern float logf_vlen8_avx2 (float);
-extern float expf_vlen8_avx2 (float);
-extern float powf_vlen8_avx2 (float, float);
-
-int main(void)
+int
+main (void)
{
- if (log_vlen2(1.0) != 0.0
- || logf_vlen4(1.0) != 0.0) abort();
-
- if (exp_vlen2(0.0) != 1.0
- || expf_vlen4(0.0) != 1.0) abort();
-
- if (pow_vlen2(1.0, 1.0) != 1.0
- || powf_vlen4(1.0, 1.0) != 1.0) abort();
-
- if (HAS_ARCH_FEATURE (AVX_Usable))
- {
- if (log_vlen4(1.0) != 0.0
- || logf_vlen8(1.0) != 0.0) abort();
-
- if (exp_vlen4(0.0) != 1.0
- || expf_vlen8(0.0) != 1.0) abort();
-
- if (pow_vlen4(1.0, 1.0) != 1.0
- || powf_vlen8(1.0, 1.0) != 1.0) abort();
- }
-
- if (HAS_ARCH_FEATURE (AVX2_Usable))
- {
- if (log_vlen4_avx2(1.0) != 0.0
- || logf_vlen8_avx2(1.0) != 0.0) abort();
-
- if (exp_vlen4_avx2(0.0) != 1.0
- || expf_vlen8_avx2(0.0) != 1.0) abort();
-
- if (pow_vlen4_avx2(1.0, 1.0) != 1.0
- || powf_vlen8_avx2(1.0, 1.0) != 1.0) abort();
- }
-
- return 0;
+ return test ();
}
-----------------------------------------------------------------------
hooks/post-receive
--
GNU C Library master sources