Message ID | VI1PR0801MB2127879AB40C189C4483AD1F83E20@VI1PR0801MB2127.eurprd08.prod.outlook.com |
---|---|
State | New |
Headers | show |
Series | [1/4] Remove math-finite.h | expand |
On 26/06/2019 11:00, Wilco Dijkstra wrote: > Remove _finite tests and references from x86_64. Rather than calling > __exp_finite, use exp directly (since it's the same entry point). > > x86_64 builds and passes testsuite. > > ChangeLog: > > 2019-06-26 Wilco Dijkstra <wdijkstr@arm.com> > > * sysdeps/x86_64/fpu/Makefile: Remove all finite tests. > * sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S: Use exp. > * sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S: Use exp. > * sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S: Use exp. > * sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S: Use log. > * sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S: Use log. > * sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S: Use log. > * sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S: Use pow. > * sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S: Use pow. > * sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S: Use pow. > * sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S: Use expf. > * sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S: Use expf. > * sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S: Use expf. > * sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S: Use logf. > * sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S: Use logf. > * sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S: Use logf. > * sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S: Use powf. > * sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S: Use powf. > * sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S: Use powf. > * sysdeps/x86_64/fpu/svml_d_exp2_core.S: Use exp. > * sysdeps/x86_64/fpu/svml_d_log2_core.S: Use log. > * sysdeps/x86_64/fpu/svml_d_pow2_core.S: Use pow. > * sysdeps/x86_64/fpu/svml_finite_alias.S: Remove. > * sysdeps/x86_64/fpu/svml_s_expf4_core.S: Use expf. > * sysdeps/x86_64/fpu/svml_s_logf4_core.S: Use logf. > * sysdeps/x86_64/fpu/svml_s_powf4_core.S: Use powf. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c: Remove. > * sysdeps/x86_64/fpu/test-double-libmvec-alias.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c: Remove. > * sysdeps/x86_64/fpu/test-float-libmvec-alias.c: Remove. > * sysdeps/x86_64/fpu/test-libmvec-alias-mod.c: Remove. LGTM. Reviewed-by: Adhemerval Zanella <adhemerval.zanella@linaro.org> > > -- > > diff --git a/sysdeps/x86_64/fpu/Makefile b/sysdeps/x86_64/fpu/Makefile > index 2b7d69bb5044e9917300d1d6759d28b8ba5a66b0..0f03d300730a6442c1bdc777108be001fc55a157 100644 > --- a/sysdeps/x86_64/fpu/Makefile > +++ b/sysdeps/x86_64/fpu/Makefile > @@ -20,9 +20,9 @@ libmvec-support += svml_d_cos2_core svml_d_cos4_core_avx \ > svml_d_pow_data svml_s_powf4_core svml_s_powf8_core_avx \ > svml_s_powf8_core svml_s_powf16_core svml_s_powf_data \ > svml_s_sincosf4_core svml_s_sincosf8_core_avx \ > - svml_s_sincosf8_core svml_s_sincosf16_core svml_finite_alias > + svml_s_sincosf8_core svml_s_sincosf16_core > > -libmvec-static-only-routines = svml_finite_alias > +libmvec-static-only-routines = > endif > > # Variables for libmvec tests. Ok. > @@ -30,93 +30,15 @@ ifeq ($(subdir),math) > ifeq ($(build-mathvec),yes) > libmvec-tests += double-vlen2 double-vlen4 double-vlen4-avx2 \ > float-vlen4 float-vlen8 float-vlen8-avx2 > -tests += test-double-libmvec-alias test-double-libmvec-alias-avx \ > - test-double-libmvec-alias-avx2 test-double-libmvec-alias-main \ > - test-double-libmvec-alias-avx-main test-double-libmvec-alias-avx2-main \ > - test-float-libmvec-alias test-float-libmvec-alias-avx \ > - test-float-libmvec-alias-avx2 test-float-libmvec-alias-main \ > - test-float-libmvec-alias-avx-main test-float-libmvec-alias-avx2-main \ > - test-double-libmvec-sincos test-double-libmvec-sincos-avx \ > +tests += test-double-libmvec-sincos test-double-libmvec-sincos-avx \ > test-double-libmvec-sincos-avx2 test-float-libmvec-sincosf \ > test-float-libmvec-sincosf-avx test-float-libmvec-sincosf-avx2 > -modules-names += test-double-libmvec-alias-mod \ > - test-double-libmvec-alias-avx-mod \ > - test-double-libmvec-alias-avx2-mod \ > - test-float-libmvec-alias-mod \ > - test-float-libmvec-alias-avx-mod \ > - test-float-libmvec-alias-avx2-mod > -modules-names-tests += test-double-libmvec-alias-mod \ > - test-double-libmvec-alias-avx-mod \ > - test-double-libmvec-alias-avx2-mod \ > - test-float-libmvec-alias-mod \ > - test-float-libmvec-alias-avx-mod \ > - test-float-libmvec-alias-avx2-mod > extra-test-objs += test-double-libmvec-sincos-avx-main.o \ > test-double-libmvec-sincos-avx2-main.o \ > test-double-libmvec-sincos-main.o \ > test-float-libmvec-sincosf-avx-main.o \ > test-float-libmvec-sincosf-avx2-main.o\ > test-float-libmvec-sincosf-main.o Ok. > -test-double-libmvec-alias-mod.so-no-z-defs = yes > -test-double-libmvec-alias-avx-mod.so-no-z-defs = yes > -test-double-libmvec-alias-avx2-mod.so-no-z-defs = yes > -test-float-libmvec-alias-mod.so-no-z-defs = yes > -test-float-libmvec-alias-avx-mod.so-no-z-defs = yes > -test-float-libmvec-alias-avx2-mod.so-no-z-defs = yes > - > -$(objpfx)test-double-libmvec-alias: \ > - $(objpfx)test-double-libmvec-alias-mod.so > -$(objpfx)test-double-libmvec-alias-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-avx: \ > - $(objpfx)test-double-libmvec-alias-avx-mod.so > -$(objpfx)test-double-libmvec-alias-avx-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-avx2: \ > - $(objpfx)test-double-libmvec-alias-avx2-mod.so > -$(objpfx)test-double-libmvec-alias-avx2-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-main: \ > - $(objpfx)test-double-libmvec-alias-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-avx-main: \ > - $(objpfx)test-double-libmvec-alias-avx-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-avx2-main: \ > - $(objpfx)test-double-libmvec-alias-avx2-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias: \ > - $(objpfx)test-float-libmvec-alias-mod.so > -$(objpfx)test-float-libmvec-alias-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx: \ > - $(objpfx)test-float-libmvec-alias-avx-mod.so > -$(objpfx)test-float-libmvec-alias-avx-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx2: \ > - $(objpfx)test-float-libmvec-alias-avx2-mod.so > -$(objpfx)test-float-libmvec-alias-avx2-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-main: \ > - $(objpfx)test-float-libmvec-alias-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx-main: \ > - $(objpfx)test-float-libmvec-alias-avx-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx2-main: \ > - $(objpfx)test-float-libmvec-alias-avx2-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > > $(objpfx)test-double-libmvec-sincos: \ > $(objpfx)test-double-libmvec-sincos.o \ Ok. > @@ -144,38 +66,10 @@ $(objpfx)test-float-libmvec-sincosf-avx2: \ > > ifeq (yes,$(config-cflags-avx512)) > libmvec-tests += double-vlen8 float-vlen16 > -tests += test-double-libmvec-alias-avx512 \ > - test-float-libmvec-alias-avx512 \ > - test-double-libmvec-alias-avx512-main \ > - test-float-libmvec-alias-avx512-main \ > - test-double-libmvec-sincos-avx512 \ > +tests += test-double-libmvec-sincos-avx512 \ > test-float-libmvec-sincosf-avx512 > -modules-names += test-double-libmvec-alias-avx512-mod \ > - test-float-libmvec-alias-avx512-mod > -modules-names-tests += test-double-libmvec-alias-avx512-mod \ > - test-float-libmvec-alias-avx512-mod > extra-test-objs += test-double-libmvec-sincos-avx512-main.o \ > test-float-libmvec-sincosf-avx512-main.o > -test-double-libmvec-alias-avx512-mod.so-no-z-defs = yes > -test-float-libmvec-alias-avx512-mod.so-no-z-defs = yes Ok. > - > -$(objpfx)test-double-libmvec-alias-avx512: \ > - $(objpfx)test-double-libmvec-alias-avx512-mod.so > -$(objpfx)test-double-libmvec-alias-avx512-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-double-libmvec-alias-avx512-main: \ > - $(objpfx)test-double-libmvec-alias-avx512-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx512: \ > - $(objpfx)test-float-libmvec-alias-avx512-mod.so > -$(objpfx)test-float-libmvec-alias-avx512-mod.so: \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > - > -$(objpfx)test-float-libmvec-alias-avx512-main: \ > - $(objpfx)test-float-libmvec-alias-avx512-mod.os \ > - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) > > $(objpfx)test-double-libmvec-sincos-avx512: \ > $(objpfx)test-double-libmvec-sincos-avx512.o \ > @@ -204,17 +98,6 @@ float-vlen8-arch-ext2-cflags = -mavx2 > float-vlen16-arch-ext-cflags = -mavx512f > > libmvec-sincos-cflags = $(libm-test-fast-math-cflags) -fno-inline -fopenmp -Wno-unknown-pragmas > -libmvec-alias-cflags = $(libmvec-sincos-cflags) -ffloat-store -ffinite-math-only > - > -CFLAGS-test-double-libmvec-alias-mod.c = $(libmvec-alias-cflags) > -CFLAGS-test-double-libmvec-alias-avx-mod.c = $(double-vlen4-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX > -CFLAGS-test-double-libmvec-alias-avx2-mod.c = $(double-vlen4-arch-ext2-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX2 > -CFLAGS-test-double-libmvec-alias-avx512-mod.c = $(double-vlen8-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX512F > - > -CFLAGS-test-float-libmvec-alias-mod.c = $(libmvec-alias-cflags) > -CFLAGS-test-float-libmvec-alias-avx-mod.c = $(double-vlen4-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX > -CFLAGS-test-float-libmvec-alias-avx2-mod.c = $(double-vlen4-arch-ext2-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX2 > -CFLAGS-test-float-libmvec-alias-avx512-mod.c = $(double-vlen8-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX512F > > CFLAGS-test-double-vlen4-avx2-wrappers.c = $(double-vlen4-arch-ext2-cflags) > Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S > index 0cf3c3167cc9b0e698dda13e9ca1748c3b6f721c..8673ec8681a28b84d9d04056c248080ef4c99ee3 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S > @@ -207,7 +207,7 @@ ENTRY (_ZGVbN2v_exp_sse4) > shlq $4, %r15 > movsd 200(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > > movsd %xmm0, 264(%rsp,%r15) > jmp .LBL_1_8 > @@ -217,7 +217,7 @@ ENTRY (_ZGVbN2v_exp_sse4) > shlq $4, %r15 > movsd 192(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > > movsd %xmm0, 256(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S > index daa82e060e3dcf3a44c2e9bfffd078ed1cce9d7d..d088b7eba95154518ba781d7ceb2dab59c89c663 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S > @@ -193,7 +193,7 @@ ENTRY (_ZGVdN4v_exp_avx2) > vmovsd 328(%rsp,%r15), %xmm0 > vzeroupper > > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > > vmovsd %xmm0, 392(%rsp,%r15) > jmp .LBL_1_8 > @@ -204,7 +204,7 @@ ENTRY (_ZGVdN4v_exp_avx2) > vmovsd 320(%rsp,%r15), %xmm0 > vzeroupper > > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > > vmovsd %xmm0, 384(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S > index 079a916a3ceb488d6fbe2326ed6f006df4f22b48..241cf35eafafd44bf5f7676f745f66e27d08a083 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S > @@ -223,7 +223,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp > movzbl %r12b, %r15d > shlq $4, %r15 > vmovsd 1160(%rsp,%r15), %xmm0 > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > vmovsd %xmm0, 1224(%rsp,%r15) > jmp .LBL_1_8 > > @@ -231,7 +231,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp > movzbl %r12b, %r15d > shlq $4, %r15 > vmovsd 1152(%rsp,%r15), %xmm0 > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > vmovsd %xmm0, 1216(%rsp,%r15) > jmp .LBL_1_7 > #endif > @@ -438,7 +438,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp > vmovsd 1160(%rsp,%r15), %xmm0 > vzeroupper > vmovsd 1160(%rsp,%r15), %xmm0 > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > vmovsd %xmm0, 1224(%rsp,%r15) > jmp .LBL_2_8 > > @@ -448,7 +448,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp > vmovsd 1152(%rsp,%r15), %xmm0 > vzeroupper > vmovsd 1152(%rsp,%r15), %xmm0 > - call JUMPTARGET(__exp_finite) > + call JUMPTARGET(exp) > vmovsd %xmm0, 1216(%rsp,%r15) > jmp .LBL_2_7 > Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S > index a827211c518f825a8c787e9315bdddb5e34e5724..ac595c5eeced76a672d3c5c1f71ce03ed5f60328 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S > @@ -211,7 +211,7 @@ ENTRY (_ZGVbN2v_log_sse4) > shlq $4, %r15 > movsd 200(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > movsd %xmm0, 264(%rsp,%r15) > jmp .LBL_1_8 > @@ -221,7 +221,7 @@ ENTRY (_ZGVbN2v_log_sse4) > shlq $4, %r15 > movsd 192(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > movsd %xmm0, 256(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S > index 247f267c53e89c2541b64ed4bb5dcaf1f08bcc92..337a3f56039fbdfc1b5a179ee29344057f2ec62d 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S > @@ -191,7 +191,7 @@ ENTRY (_ZGVdN4v_log_avx2) > vmovsd 328(%rsp,%r15), %xmm0 > vzeroupper > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > vmovsd %xmm0, 392(%rsp,%r15) > jmp .LBL_1_8 > @@ -202,7 +202,7 @@ ENTRY (_ZGVdN4v_log_avx2) > vmovsd 320(%rsp,%r15), %xmm0 > vzeroupper > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > vmovsd %xmm0, 384(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S > index abe5a6cae7b532ecd4e8f1db75ce114d759a17dc..a3b5e9eebfc3012db048459acca6157e1f890524 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S > @@ -222,7 +222,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log > movzbl %r12b, %r15d > shlq $4, %r15 > vmovsd 1160(%rsp,%r15), %xmm0 > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > vmovsd %xmm0, 1224(%rsp,%r15) > jmp .LBL_1_8 > > @@ -230,7 +230,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log > movzbl %r12b, %r15d > shlq $4, %r15 > vmovsd 1152(%rsp,%r15), %xmm0 > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > vmovsd %xmm0, 1216(%rsp,%r15) > jmp .LBL_1_7 > #endif > @@ -443,7 +443,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log > vzeroupper > vmovsd 1160(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > vmovsd %xmm0, 1224(%rsp,%r15) > jmp .LBL_2_8 > @@ -455,7 +455,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log > vzeroupper > vmovsd 1152(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__log_finite) > + call JUMPTARGET(log) > > vmovsd %xmm0, 1216(%rsp,%r15) > jmp .LBL_2_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S > index 8f1fb39d6a291afb0f2d9fd5410f6fe878333b18..84e8199f0f4c3f55f263bf6f3a066e9395d963e5 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S > @@ -413,7 +413,7 @@ ENTRY (_ZGVbN2vv_pow_sse4) > movsd 72(%rsp,%r15), %xmm0 > movsd 136(%rsp,%r15), %xmm1 > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > movsd %xmm0, 200(%rsp,%r15) > jmp .LBL_1_8 > @@ -424,7 +424,7 @@ ENTRY (_ZGVbN2vv_pow_sse4) > movsd 64(%rsp,%r15), %xmm0 > movsd 128(%rsp,%r15), %xmm1 > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > movsd %xmm0, 192(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S > index 9bf771a6503e03cd5e596267ea91c11c08111f47..39b601f9f09bcba5217ca8802297bc2237589588 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S > @@ -367,7 +367,7 @@ ENTRY (_ZGVdN4vv_pow_avx2) > vmovsd 264(%rsp,%r15), %xmm1 > vzeroupper > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > vmovsd %xmm0, 328(%rsp,%r15) > jmp .LBL_1_8 > @@ -379,7 +379,7 @@ ENTRY (_ZGVdN4vv_pow_avx2) > vmovsd 256(%rsp,%r15), %xmm1 > vzeroupper > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > vmovsd %xmm0, 320(%rsp,%r15) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S > index 0ced819df4269a87a292232cde334842e9ea294d..861d166af71ea689d926201fba628d39dfab2267 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S > @@ -392,7 +392,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow > shlq $4, %r15 > vmovsd 1160(%rsp,%r15), %xmm0 > vmovsd 1224(%rsp,%r15), %xmm1 > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > vmovsd %xmm0, 1288(%rsp,%r15) > jmp .LBL_1_8 > > @@ -401,7 +401,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow > shlq $4, %r15 > vmovsd 1152(%rsp,%r15), %xmm0 > vmovsd 1216(%rsp,%r15), %xmm1 > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > vmovsd %xmm0, 1280(%rsp,%r15) > jmp .LBL_1_7 > > @@ -720,7 +720,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow > vzeroupper > vmovsd 1160(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > vmovsd %xmm0, 1288(%rsp,%r15) > jmp .LBL_2_8 > @@ -732,7 +732,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow > vzeroupper > vmovsd 1152(%rsp,%r15), %xmm0 > > - call JUMPTARGET(__pow_finite) > + call JUMPTARGET(pow) > > vmovsd %xmm0, 1280(%rsp,%r15) > jmp .LBL_2_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S > index e685b7489e9fdb6ad78f32f443ff460d37626528..c746b353d410bd0ac1be6b8176d59652de76770b 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S > @@ -212,14 +212,14 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf > cfi_restore_state > movzbl %r12b, %r15d > vmovss 1156(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > vmovss %xmm0, 1220(%rsp,%r15,8) > jmp .LBL_1_8 > > .LBL_1_12: > movzbl %r12b, %r15d > vmovss 1152(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > vmovss %xmm0, 1216(%rsp,%r15,8) > jmp .LBL_1_7 > > @@ -422,7 +422,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf > vzeroupper > vmovss 1156(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > vmovss %xmm0, 1220(%rsp,%r15,8) > jmp .LBL_2_8 > @@ -433,7 +433,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf > vzeroupper > vmovss 1152(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > vmovss %xmm0, 1216(%rsp,%r15,8) > jmp .LBL_2_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S > index 2bf2a28ab666108d5bc989349796b85e3808b9b3..b031f4ff7eded23c6bc387eded3ab8b6170a739b 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S > @@ -195,7 +195,7 @@ ENTRY (_ZGVbN4v_expf_sse4) > movzbl %r12b, %r15d > movss 196(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > movss %xmm0, 260(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -204,7 +204,7 @@ ENTRY (_ZGVbN4v_expf_sse4) > movzbl %r12b, %r15d > movss 192(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > movss %xmm0, 256(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S > index 4538ef35eac4cf2482f8c5f51536798f3504e6d3..8d55961afe4898463142dea7628839de37071510 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S > @@ -184,7 +184,7 @@ ENTRY(_ZGVdN8v_expf_avx2) > vmovss 324(%rsp,%r15,8), %xmm0 > vzeroupper > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > vmovss %xmm0, 388(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -194,7 +194,7 @@ ENTRY(_ZGVdN8v_expf_avx2) > vmovss 320(%rsp,%r15,8), %xmm0 > vzeroupper > > - call JUMPTARGET(__expf_finite) > + call JUMPTARGET(expf) > > vmovss %xmm0, 384(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S > index 02b99da9a6a204c1ef5b018c01543cae13e40955..013795ed2a9f3e3f85c91ac389fdd3a58712499f 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S > @@ -197,14 +197,14 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf > cfi_restore_state > movzbl %r12b, %r15d > vmovss 1156(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > vmovss %xmm0, 1220(%rsp,%r15,8) > jmp .LBL_1_8 > > .LBL_1_12: > movzbl %r12b, %r15d > vmovss 1152(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > vmovss %xmm0, 1216(%rsp,%r15,8) > jmp .LBL_1_7 > #endif > @@ -391,7 +391,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf > vzeroupper > vmovss 1156(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > vmovss %xmm0, 1220(%rsp,%r15,8) > jmp .LBL_2_8 > @@ -402,7 +402,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf > vzeroupper > vmovss 1152(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > vmovss %xmm0, 1216(%rsp,%r15,8) > jmp .LBL_2_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S > index 0d2ac78ffbde333adb0419aa386513b65f9dd980..c3a91933d2b30ace6c8f174ece632c0a0fd74a9e 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S > @@ -177,7 +177,7 @@ ENTRY (_ZGVbN4v_logf_sse4) > movzbl %r12b, %r15d > movss 196(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > movss %xmm0, 260(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -186,7 +186,7 @@ ENTRY (_ZGVbN4v_logf_sse4) > movzbl %r12b, %r15d > movss 192(%rsp,%r15,8), %xmm0 > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > movss %xmm0, 256(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S > index 38d35d0ac8a902d342fab9501a14b2ee719b7e74..fceec378a10067ce338df0f13cece0f5f0615c83 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S > @@ -166,7 +166,7 @@ ENTRY(_ZGVdN8v_logf_avx2) > vmovss 324(%rsp,%r15,8), %xmm0 > vzeroupper > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > vmovss %xmm0, 388(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -176,7 +176,7 @@ ENTRY(_ZGVdN8v_logf_avx2) > vmovss 320(%rsp,%r15,8), %xmm0 > vzeroupper > > - call JUMPTARGET(__logf_finite) > + call JUMPTARGET(logf) > > vmovss %xmm0, 384(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S > index 97b66bc9acbbd8dcc9e48286c17539fd45970c1b..237e1cbf90327eed61d30f987ef3d01c6dae233f 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S > @@ -344,7 +344,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf > movzbl %r12b, %r15d > vmovss 1156(%rsp,%r15,8), %xmm0 > vmovss 1220(%rsp,%r15,8), %xmm1 > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > vmovss %xmm0, 1284(%rsp,%r15,8) > jmp .LBL_1_8 > > @@ -352,7 +352,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf > movzbl %r12b, %r15d > vmovss 1152(%rsp,%r15,8), %xmm0 > vmovss 1216(%rsp,%r15,8), %xmm1 > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > vmovss %xmm0, 1280(%rsp,%r15,8) > jmp .LBL_1_7 > #endif > @@ -629,7 +629,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf > vmovss 1156(%rsp,%r15,8), %xmm1 > vzeroupper > vmovss 1092(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > vmovss %xmm0, 1220(%rsp,%r15,8) > jmp .LBL_2_8 > > @@ -638,7 +638,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf > vmovss 1152(%rsp,%r15,8), %xmm1 > vzeroupper > vmovss 1088(%rsp,%r15,8), %xmm0 > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > vmovss %xmm0, 1216(%rsp,%r15,8) > jmp .LBL_2_7 > #endif Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S > index ff5dffa21cb8f3afa264ab9c563056a0b1beacfa..85c0821b93dd698fe767dc6e650bf16eb3865f7b 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S > @@ -356,7 +356,7 @@ ENTRY (_ZGVbN4vv_powf_sse4) > movss 68(%rsp,%r15,8), %xmm0 > movss 132(%rsp,%r15,8), %xmm1 > > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > > movss %xmm0, 196(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -366,7 +366,7 @@ ENTRY (_ZGVbN4vv_powf_sse4) > movss 64(%rsp,%r15,8), %xmm0 > movss 128(%rsp,%r15,8), %xmm1 > > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > > movss %xmm0, 192(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S > index 06f0c7f2d36b49d07c3e26039a9eed7733c713fc..7112962bf0e596e0f1ff846d6fea28019c2f4324 100644 > --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S > +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S > @@ -317,7 +317,7 @@ ENTRY(_ZGVdN8vv_powf_avx2) > vmovss 132(%rsp,%r15,8), %xmm1 > vzeroupper > > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > > vmovss %xmm0, 196(%rsp,%r15,8) > jmp .LBL_1_8 > @@ -328,7 +328,7 @@ ENTRY(_ZGVdN8vv_powf_avx2) > vmovss 128(%rsp,%r15,8), %xmm1 > vzeroupper > > - call JUMPTARGET(__powf_finite) > + call JUMPTARGET(powf) > > vmovss %xmm0, 192(%rsp,%r15,8) > jmp .LBL_1_7 Ok. > diff --git a/sysdeps/x86_64/fpu/svml_d_exp2_core.S b/sysdeps/x86_64/fpu/svml_d_exp2_core.S > index 601f6aa35ff6297184aa5c5c41258cfb156751f7..58390e8c82f5622b34b19b0f88adc567f869f622 100644 > --- a/sysdeps/x86_64/fpu/svml_d_exp2_core.S > +++ b/sysdeps/x86_64/fpu/svml_d_exp2_core.S > @@ -21,7 +21,7 @@ > > .text > ENTRY (_ZGVbN2v_exp) > -WRAPPER_IMPL_SSE2 __exp_finite > +WRAPPER_IMPL_SSE2 exp > END (_ZGVbN2v_exp) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/svml_d_log2_core.S b/sysdeps/x86_64/fpu/svml_d_log2_core.S > index d3373963c68123b0db32306396449c9fe8d59fec..fed3b15c248055241639fd21851ee2ecba9c8e8d 100644 > --- a/sysdeps/x86_64/fpu/svml_d_log2_core.S > +++ b/sysdeps/x86_64/fpu/svml_d_log2_core.S > @@ -21,7 +21,7 @@ > > .text > ENTRY (_ZGVbN2v_log) > -WRAPPER_IMPL_SSE2 __log_finite > +WRAPPER_IMPL_SSE2 log > END (_ZGVbN2v_log) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/svml_d_pow2_core.S b/sysdeps/x86_64/fpu/svml_d_pow2_core.S > index f28c359282cb1bfc56719ae30fc4b1a0c2a52cff..8e6d9ffc26709df85aa0cb11b8ecb972289d0e83 100644 > --- a/sysdeps/x86_64/fpu/svml_d_pow2_core.S > +++ b/sysdeps/x86_64/fpu/svml_d_pow2_core.S > @@ -21,7 +21,7 @@ > > .text > ENTRY (_ZGVbN2vv_pow) > -WRAPPER_IMPL_SSE2_ff __pow_finite > +WRAPPER_IMPL_SSE2_ff pow > END (_ZGVbN2vv_pow) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/svml_finite_alias.S b/sysdeps/x86_64/fpu/svml_finite_alias.S > deleted file mode 100644 > index c6008e9a24730bd3f3d514e13cb99c8d4a98ce7c..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/svml_finite_alias.S > +++ /dev/null > @@ -1,58 +0,0 @@ > -/* These aliases added as workaround to exclude unnecessary symbol > - aliases in libmvec.so while compiler creates the vector names > - based on scalar asm name. Corresponding discussion is at > - <https://gcc.gnu.org/ml/gcc/2015-06/msg00173.html>. > - Copyright (C) 2015-2019 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 <sysdep.h> > - > -#define ALIAS_IMPL(alias, target) \ > -ENTRY (alias); \ > - jmp *target@GOTPCREL(%rip); \ > -END (alias) > - > - .text > -ALIAS_IMPL (_ZGVbN2v___log_finite, _ZGVbN2v_log) > -ALIAS_IMPL (_ZGVcN4v___log_finite, _ZGVcN4v_log) > -ALIAS_IMPL (_ZGVdN4v___log_finite, _ZGVdN4v_log) > -ALIAS_IMPL (_ZGVeN8v___log_finite, _ZGVeN8v_log) > - > -ALIAS_IMPL (_ZGVbN4v___logf_finite, _ZGVbN4v_logf) > -ALIAS_IMPL (_ZGVcN8v___logf_finite, _ZGVcN8v_logf) > -ALIAS_IMPL (_ZGVdN8v___logf_finite, _ZGVdN8v_logf) > -ALIAS_IMPL (_ZGVeN16v___logf_finite, _ZGVeN16v_logf) > - > -ALIAS_IMPL (_ZGVbN2v___exp_finite, _ZGVbN2v_exp) > -ALIAS_IMPL (_ZGVcN4v___exp_finite, _ZGVcN4v_exp) > -ALIAS_IMPL (_ZGVdN4v___exp_finite, _ZGVdN4v_exp) > -ALIAS_IMPL (_ZGVeN8v___exp_finite, _ZGVeN8v_exp) > - > -ALIAS_IMPL (_ZGVbN4v___expf_finite, _ZGVbN4v_expf) > -ALIAS_IMPL (_ZGVcN8v___expf_finite, _ZGVcN8v_expf) > -ALIAS_IMPL (_ZGVdN8v___expf_finite, _ZGVdN8v_expf) > -ALIAS_IMPL (_ZGVeN16v___expf_finite, _ZGVeN16v_expf) > - > -ALIAS_IMPL (_ZGVbN2vv___pow_finite, _ZGVbN2vv_pow) > -ALIAS_IMPL (_ZGVcN4vv___pow_finite, _ZGVcN4vv_pow) > -ALIAS_IMPL (_ZGVdN4vv___pow_finite, _ZGVdN4vv_pow) > -ALIAS_IMPL (_ZGVeN8vv___pow_finite, _ZGVeN8vv_pow) > - > -ALIAS_IMPL (_ZGVbN4vv___powf_finite, _ZGVbN4vv_powf) > -ALIAS_IMPL (_ZGVcN8vv___powf_finite, _ZGVcN8vv_powf) > -ALIAS_IMPL (_ZGVdN8vv___powf_finite, _ZGVdN8vv_powf) > -ALIAS_IMPL (_ZGVeN16vv___powf_finite, _ZGVeN16vv_powf) Ok. > diff --git a/sysdeps/x86_64/fpu/svml_s_expf4_core.S b/sysdeps/x86_64/fpu/svml_s_expf4_core.S > index 426b37f885261adb174b46346bb0040bdaab5089..ed6db8983a428de9f23b639f737cc3a3ff855199 100644 > --- a/sysdeps/x86_64/fpu/svml_s_expf4_core.S > +++ b/sysdeps/x86_64/fpu/svml_s_expf4_core.S > @@ -22,7 +22,7 @@ > > .text > ENTRY (_ZGVbN4v_expf) > -WRAPPER_IMPL_SSE2 __expf_finite > +WRAPPER_IMPL_SSE2 expf > END (_ZGVbN4v_expf) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/svml_s_logf4_core.S b/sysdeps/x86_64/fpu/svml_s_logf4_core.S > index 519ae44bcb93bcaafcf35f670362c82a36ea62e5..33312c4b0de9562518478f58b414b8b8b97ca621 100644 > --- a/sysdeps/x86_64/fpu/svml_s_logf4_core.S > +++ b/sysdeps/x86_64/fpu/svml_s_logf4_core.S > @@ -22,7 +22,7 @@ > > .text > ENTRY (_ZGVbN4v_logf) > -WRAPPER_IMPL_SSE2 __logf_finite > +WRAPPER_IMPL_SSE2 logf > END (_ZGVbN4v_logf) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/svml_s_powf4_core.S b/sysdeps/x86_64/fpu/svml_s_powf4_core.S > index 7e2a02830a8e0052868ab0d84648dfb1c5b5e65e..a8280b2e7c2d65e22a49ed0a9454c3ca723722f9 100644 > --- a/sysdeps/x86_64/fpu/svml_s_powf4_core.S > +++ b/sysdeps/x86_64/fpu/svml_s_powf4_core.S > @@ -21,7 +21,7 @@ > > .text > ENTRY (_ZGVbN4vv_powf) > -WRAPPER_IMPL_SSE2_ff __powf_finite > +WRAPPER_IMPL_SSE2_ff powf > END (_ZGVbN4vv_powf) > > #ifndef USE_MULTIARCH Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c > deleted file mode 100644 > index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c > deleted file mode 100644 > index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c > deleted file mode 100644 > index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c > deleted file mode 100644 > index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-double-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c > deleted file mode 100644 > index e57c00d9241fb1e99a02c16d25158a4f2e247d65..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c > +++ /dev/null > @@ -1,25 +0,0 @@ > -/* Part of test to build shared library to ensure link against > - *_finite aliases from libmvec. > - Copyright (C) 2016-2019 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 <math.h> > -#include <stdlib.h> > -#include <math-tests-arch.h> > - > -#include "test-double.h" > -#include "test-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias.c > deleted file mode 100644 > index 340cf8bb6fbf267ddefc6308b74ad8207cdf67c4..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias.c > +++ /dev/null > @@ -1,29 +0,0 @@ > -/* Part of test to ensure link against *_finite aliases from libmvec. > - Copyright (C) 2016-2019 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/>. */ > - > -extern int > -test_finite_alias (void); > - > -static int > -do_test (void) > -{ > - return test_finite_alias (); > -} > - > -#define TEST_FUNCTION do_test () > -#include "../../../test-skeleton.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c > deleted file mode 100644 > index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c > deleted file mode 100644 > index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c > deleted file mode 100644 > index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c > deleted file mode 100644 > index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c > +++ /dev/null > @@ -1 +0,0 @@ > -#include "test-float-libmvec-alias.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c > deleted file mode 100644 > index abe16ee209a2d0d571362294fc15a93787c5bb9b..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c > +++ /dev/null > @@ -1,25 +0,0 @@ > -/* Part of test to build shared library to ensure link against > - *_finite aliases from libmvec. > - Copyright (C) 2016-2019 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 <math.h> > -#include <stdlib.h> > -#include <math-tests-arch.h> > - > -#include "test-float.h" > -#include "test-libmvec-alias-mod.c" Ok. > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias.c > deleted file mode 100644 > index 340cf8bb6fbf267ddefc6308b74ad8207cdf67c4..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias.c > +++ /dev/null > @@ -1,29 +0,0 @@ > -/* Part of test to ensure link against *_finite aliases from libmvec. > - Copyright (C) 2016-2019 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/>. */ > - > -extern int > -test_finite_alias (void); > - > -static int > -do_test (void) > -{ > - return test_finite_alias (); > -} > - > -#define TEST_FUNCTION do_test () > -#include "../../../test-skeleton.c" Ok. > 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 b5fe71d5b30001e71cf039df4322fe602075a77a..0000000000000000000000000000000000000000 > --- a/sysdeps/x86_64/fpu/test-libmvec-alias-mod.c > +++ /dev/null > @@ -1,66 +0,0 @@ > -/* Part of test to build shared library to ensure link against > - *_finite aliases from libmvec. > - Copyright (C) 2016-2019 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/>. */ > - > -#define N 4000 > -FLOAT log_arg[N]; > -FLOAT exp_arg[N]; > -FLOAT log_res[N]; > -FLOAT exp_res[N]; > -FLOAT pow_res[N]; > -int arch_check = 1; > - > -static void > -init_arg (void) > -{ > - int i; > - > - CHECK_ARCH_EXT; > - > - arch_check = 0; > - > - for (i = 0; i < N; i += 1) > - { > - log_arg[i] = 1.0; > - exp_arg[i] = 0.0; > - } > -} > - > -int > -test_finite_alias (void) > -{ > - int i; > - > - init_arg (); > - > - if (arch_check) return 77; > - > -#pragma omp simd > - for (i = 0; i < N; i += 1) > - { > - log_res[i] = FUNC (log) (log_arg[i]); > - exp_res[i] = FUNC (exp) (exp_arg[i]); > - pow_res[i] = FUNC (pow) (log_arg[i], log_arg[i]); > - } > - > - if (log_res[0] != 0.0) return 1; > - if (exp_res[0] != 1.0) return 1; > - if (pow_res[0] != 1.0) return 1; > - > - return 0; > -} > Ok.
On 16/07/2019 15:19, Adhemerval Zanella wrote: > > > On 26/06/2019 11:00, Wilco Dijkstra wrote: >> Remove _finite tests and references from x86_64. Rather than calling >> __exp_finite, use exp directly (since it's the same entry point). >> >> x86_64 builds and passes testsuite. >> >> ChangeLog: >> >> 2019-06-26 Wilco Dijkstra <wdijkstr@arm.com> >> >> * sysdeps/x86_64/fpu/Makefile: Remove all finite tests. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S: Use powf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S: Use powf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S: Use powf. >> * sysdeps/x86_64/fpu/svml_d_exp2_core.S: Use exp. >> * sysdeps/x86_64/fpu/svml_d_log2_core.S: Use log. >> * sysdeps/x86_64/fpu/svml_d_pow2_core.S: Use pow. >> * sysdeps/x86_64/fpu/svml_finite_alias.S: Remove. >> * sysdeps/x86_64/fpu/svml_s_expf4_core.S: Use expf. >> * sysdeps/x86_64/fpu/svml_s_logf4_core.S: Use logf. >> * sysdeps/x86_64/fpu/svml_s_powf4_core.S: Use powf. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias.c: Remove. >> * sysdeps/x86_64/fpu/test-libmvec-alias-mod.c: Remove. > > LGTM. > > Reviewed-by: Adhemerval Zanella <adhemerval.zanella@linaro.org> I chatted with Wilco and I will commit this patch shortly on his behalf.
On 16/07/2019 15:19, Adhemerval Zanella wrote: > > > On 26/06/2019 11:00, Wilco Dijkstra wrote: >> Remove _finite tests and references from x86_64. Rather than calling >> __exp_finite, use exp directly (since it's the same entry point). >> >> x86_64 builds and passes testsuite. >> >> ChangeLog: >> >> 2019-06-26 Wilco Dijkstra <wdijkstr@arm.com> >> >> * sysdeps/x86_64/fpu/Makefile: Remove all finite tests. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S: Use exp. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S: Use log. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S: Use pow. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S: Use expf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S: Use logf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S: Use powf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S: Use powf. >> * sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S: Use powf. >> * sysdeps/x86_64/fpu/svml_d_exp2_core.S: Use exp. >> * sysdeps/x86_64/fpu/svml_d_log2_core.S: Use log. >> * sysdeps/x86_64/fpu/svml_d_pow2_core.S: Use pow. >> * sysdeps/x86_64/fpu/svml_finite_alias.S: Remove. >> * sysdeps/x86_64/fpu/svml_s_expf4_core.S: Use expf. >> * sysdeps/x86_64/fpu/svml_s_logf4_core.S: Use logf. >> * sysdeps/x86_64/fpu/svml_s_powf4_core.S: Use powf. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-double-libmvec-alias.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c: Remove. >> * sysdeps/x86_64/fpu/test-float-libmvec-alias.c: Remove. >> * sysdeps/x86_64/fpu/test-libmvec-alias-mod.c: Remove. > > LGTM. > > Reviewed-by: Adhemerval Zanella <adhemerval.zanella@linaro.org> > >> >> -- >> >> diff --git a/sysdeps/x86_64/fpu/Makefile b/sysdeps/x86_64/fpu/Makefile >> index 2b7d69bb5044e9917300d1d6759d28b8ba5a66b0..0f03d300730a6442c1bdc777108be001fc55a157 100644 >> --- a/sysdeps/x86_64/fpu/Makefile >> +++ b/sysdeps/x86_64/fpu/Makefile >> @@ -20,9 +20,9 @@ libmvec-support += svml_d_cos2_core svml_d_cos4_core_avx \ >> svml_d_pow_data svml_s_powf4_core svml_s_powf8_core_avx \ >> svml_s_powf8_core svml_s_powf16_core svml_s_powf_data \ >> svml_s_sincosf4_core svml_s_sincosf8_core_avx \ >> - svml_s_sincosf8_core svml_s_sincosf16_core svml_finite_alias >> + svml_s_sincosf8_core svml_s_sincosf16_core >> >> -libmvec-static-only-routines = svml_finite_alias >> +libmvec-static-only-routines = >> endif >> >> # Variables for libmvec tests. > > Ok. By defining it as an empty rule, x86_64 build does not create the libmvec_nonshared.a any longer (since it just contains the finite alias). So we need to remove them from libm.so linker script at math/Makefile as well. I fixed it as well. (I saw it build-many-glibcs that fails on gcc build).
diff --git a/sysdeps/x86_64/fpu/Makefile b/sysdeps/x86_64/fpu/Makefile index 2b7d69bb5044e9917300d1d6759d28b8ba5a66b0..0f03d300730a6442c1bdc777108be001fc55a157 100644 --- a/sysdeps/x86_64/fpu/Makefile +++ b/sysdeps/x86_64/fpu/Makefile @@ -20,9 +20,9 @@ libmvec-support += svml_d_cos2_core svml_d_cos4_core_avx \ svml_d_pow_data svml_s_powf4_core svml_s_powf8_core_avx \ svml_s_powf8_core svml_s_powf16_core svml_s_powf_data \ svml_s_sincosf4_core svml_s_sincosf8_core_avx \ - svml_s_sincosf8_core svml_s_sincosf16_core svml_finite_alias + svml_s_sincosf8_core svml_s_sincosf16_core -libmvec-static-only-routines = svml_finite_alias +libmvec-static-only-routines = endif # Variables for libmvec tests. @@ -30,93 +30,15 @@ ifeq ($(subdir),math) ifeq ($(build-mathvec),yes) libmvec-tests += double-vlen2 double-vlen4 double-vlen4-avx2 \ float-vlen4 float-vlen8 float-vlen8-avx2 -tests += test-double-libmvec-alias test-double-libmvec-alias-avx \ - test-double-libmvec-alias-avx2 test-double-libmvec-alias-main \ - test-double-libmvec-alias-avx-main test-double-libmvec-alias-avx2-main \ - test-float-libmvec-alias test-float-libmvec-alias-avx \ - test-float-libmvec-alias-avx2 test-float-libmvec-alias-main \ - test-float-libmvec-alias-avx-main test-float-libmvec-alias-avx2-main \ - test-double-libmvec-sincos test-double-libmvec-sincos-avx \ +tests += test-double-libmvec-sincos test-double-libmvec-sincos-avx \ test-double-libmvec-sincos-avx2 test-float-libmvec-sincosf \ test-float-libmvec-sincosf-avx test-float-libmvec-sincosf-avx2 -modules-names += test-double-libmvec-alias-mod \ - test-double-libmvec-alias-avx-mod \ - test-double-libmvec-alias-avx2-mod \ - test-float-libmvec-alias-mod \ - test-float-libmvec-alias-avx-mod \ - test-float-libmvec-alias-avx2-mod -modules-names-tests += test-double-libmvec-alias-mod \ - test-double-libmvec-alias-avx-mod \ - test-double-libmvec-alias-avx2-mod \ - test-float-libmvec-alias-mod \ - test-float-libmvec-alias-avx-mod \ - test-float-libmvec-alias-avx2-mod extra-test-objs += test-double-libmvec-sincos-avx-main.o \ test-double-libmvec-sincos-avx2-main.o \ test-double-libmvec-sincos-main.o \ test-float-libmvec-sincosf-avx-main.o \ test-float-libmvec-sincosf-avx2-main.o\ test-float-libmvec-sincosf-main.o -test-double-libmvec-alias-mod.so-no-z-defs = yes -test-double-libmvec-alias-avx-mod.so-no-z-defs = yes -test-double-libmvec-alias-avx2-mod.so-no-z-defs = yes -test-float-libmvec-alias-mod.so-no-z-defs = yes -test-float-libmvec-alias-avx-mod.so-no-z-defs = yes -test-float-libmvec-alias-avx2-mod.so-no-z-defs = yes - -$(objpfx)test-double-libmvec-alias: \ - $(objpfx)test-double-libmvec-alias-mod.so -$(objpfx)test-double-libmvec-alias-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-avx: \ - $(objpfx)test-double-libmvec-alias-avx-mod.so -$(objpfx)test-double-libmvec-alias-avx-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-avx2: \ - $(objpfx)test-double-libmvec-alias-avx2-mod.so -$(objpfx)test-double-libmvec-alias-avx2-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-main: \ - $(objpfx)test-double-libmvec-alias-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-avx-main: \ - $(objpfx)test-double-libmvec-alias-avx-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-avx2-main: \ - $(objpfx)test-double-libmvec-alias-avx2-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias: \ - $(objpfx)test-float-libmvec-alias-mod.so -$(objpfx)test-float-libmvec-alias-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx: \ - $(objpfx)test-float-libmvec-alias-avx-mod.so -$(objpfx)test-float-libmvec-alias-avx-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx2: \ - $(objpfx)test-float-libmvec-alias-avx2-mod.so -$(objpfx)test-float-libmvec-alias-avx2-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-main: \ - $(objpfx)test-float-libmvec-alias-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx-main: \ - $(objpfx)test-float-libmvec-alias-avx-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx2-main: \ - $(objpfx)test-float-libmvec-alias-avx2-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) $(objpfx)test-double-libmvec-sincos: \ $(objpfx)test-double-libmvec-sincos.o \ @@ -144,38 +66,10 @@ $(objpfx)test-float-libmvec-sincosf-avx2: \ ifeq (yes,$(config-cflags-avx512)) libmvec-tests += double-vlen8 float-vlen16 -tests += test-double-libmvec-alias-avx512 \ - test-float-libmvec-alias-avx512 \ - test-double-libmvec-alias-avx512-main \ - test-float-libmvec-alias-avx512-main \ - test-double-libmvec-sincos-avx512 \ +tests += test-double-libmvec-sincos-avx512 \ test-float-libmvec-sincosf-avx512 -modules-names += test-double-libmvec-alias-avx512-mod \ - test-float-libmvec-alias-avx512-mod -modules-names-tests += test-double-libmvec-alias-avx512-mod \ - test-float-libmvec-alias-avx512-mod extra-test-objs += test-double-libmvec-sincos-avx512-main.o \ test-float-libmvec-sincosf-avx512-main.o -test-double-libmvec-alias-avx512-mod.so-no-z-defs = yes -test-float-libmvec-alias-avx512-mod.so-no-z-defs = yes - -$(objpfx)test-double-libmvec-alias-avx512: \ - $(objpfx)test-double-libmvec-alias-avx512-mod.so -$(objpfx)test-double-libmvec-alias-avx512-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-double-libmvec-alias-avx512-main: \ - $(objpfx)test-double-libmvec-alias-avx512-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx512: \ - $(objpfx)test-float-libmvec-alias-avx512-mod.so -$(objpfx)test-float-libmvec-alias-avx512-mod.so: \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) - -$(objpfx)test-float-libmvec-alias-avx512-main: \ - $(objpfx)test-float-libmvec-alias-avx512-mod.os \ - $(objpfx)../mathvec/libmvec_nonshared.a $(libmvec) $(objpfx)test-double-libmvec-sincos-avx512: \ $(objpfx)test-double-libmvec-sincos-avx512.o \ @@ -204,17 +98,6 @@ float-vlen8-arch-ext2-cflags = -mavx2 float-vlen16-arch-ext-cflags = -mavx512f libmvec-sincos-cflags = $(libm-test-fast-math-cflags) -fno-inline -fopenmp -Wno-unknown-pragmas -libmvec-alias-cflags = $(libmvec-sincos-cflags) -ffloat-store -ffinite-math-only - -CFLAGS-test-double-libmvec-alias-mod.c = $(libmvec-alias-cflags) -CFLAGS-test-double-libmvec-alias-avx-mod.c = $(double-vlen4-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX -CFLAGS-test-double-libmvec-alias-avx2-mod.c = $(double-vlen4-arch-ext2-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX2 -CFLAGS-test-double-libmvec-alias-avx512-mod.c = $(double-vlen8-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX512F - -CFLAGS-test-float-libmvec-alias-mod.c = $(libmvec-alias-cflags) -CFLAGS-test-float-libmvec-alias-avx-mod.c = $(double-vlen4-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX -CFLAGS-test-float-libmvec-alias-avx2-mod.c = $(double-vlen4-arch-ext2-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX2 -CFLAGS-test-float-libmvec-alias-avx512-mod.c = $(double-vlen8-arch-ext-cflags) $(libmvec-alias-cflags) -DREQUIRE_AVX512F CFLAGS-test-double-vlen4-avx2-wrappers.c = $(double-vlen4-arch-ext2-cflags) diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S index 0cf3c3167cc9b0e698dda13e9ca1748c3b6f721c..8673ec8681a28b84d9d04056c248080ef4c99ee3 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp2_core_sse4.S @@ -207,7 +207,7 @@ ENTRY (_ZGVbN2v_exp_sse4) shlq $4, %r15 movsd 200(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) movsd %xmm0, 264(%rsp,%r15) jmp .LBL_1_8 @@ -217,7 +217,7 @@ ENTRY (_ZGVbN2v_exp_sse4) shlq $4, %r15 movsd 192(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) movsd %xmm0, 256(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S index daa82e060e3dcf3a44c2e9bfffd078ed1cce9d7d..d088b7eba95154518ba781d7ceb2dab59c89c663 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp4_core_avx2.S @@ -193,7 +193,7 @@ ENTRY (_ZGVdN4v_exp_avx2) vmovsd 328(%rsp,%r15), %xmm0 vzeroupper - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 392(%rsp,%r15) jmp .LBL_1_8 @@ -204,7 +204,7 @@ ENTRY (_ZGVdN4v_exp_avx2) vmovsd 320(%rsp,%r15), %xmm0 vzeroupper - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 384(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S index 079a916a3ceb488d6fbe2326ed6f006df4f22b48..241cf35eafafd44bf5f7676f745f66e27d08a083 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_exp8_core_avx512.S @@ -223,7 +223,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp movzbl %r12b, %r15d shlq $4, %r15 vmovsd 1160(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 1224(%rsp,%r15) jmp .LBL_1_8 @@ -231,7 +231,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp movzbl %r12b, %r15d shlq $4, %r15 vmovsd 1152(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 1216(%rsp,%r15) jmp .LBL_1_7 #endif @@ -438,7 +438,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp vmovsd 1160(%rsp,%r15), %xmm0 vzeroupper vmovsd 1160(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 1224(%rsp,%r15) jmp .LBL_2_8 @@ -448,7 +448,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_exp vmovsd 1152(%rsp,%r15), %xmm0 vzeroupper vmovsd 1152(%rsp,%r15), %xmm0 - call JUMPTARGET(__exp_finite) + call JUMPTARGET(exp) vmovsd %xmm0, 1216(%rsp,%r15) jmp .LBL_2_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S index a827211c518f825a8c787e9315bdddb5e34e5724..ac595c5eeced76a672d3c5c1f71ce03ed5f60328 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log2_core_sse4.S @@ -211,7 +211,7 @@ ENTRY (_ZGVbN2v_log_sse4) shlq $4, %r15 movsd 200(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) movsd %xmm0, 264(%rsp,%r15) jmp .LBL_1_8 @@ -221,7 +221,7 @@ ENTRY (_ZGVbN2v_log_sse4) shlq $4, %r15 movsd 192(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) movsd %xmm0, 256(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S index 247f267c53e89c2541b64ed4bb5dcaf1f08bcc92..337a3f56039fbdfc1b5a179ee29344057f2ec62d 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log4_core_avx2.S @@ -191,7 +191,7 @@ ENTRY (_ZGVdN4v_log_avx2) vmovsd 328(%rsp,%r15), %xmm0 vzeroupper - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 392(%rsp,%r15) jmp .LBL_1_8 @@ -202,7 +202,7 @@ ENTRY (_ZGVdN4v_log_avx2) vmovsd 320(%rsp,%r15), %xmm0 vzeroupper - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 384(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S index abe5a6cae7b532ecd4e8f1db75ce114d759a17dc..a3b5e9eebfc3012db048459acca6157e1f890524 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_log8_core_avx512.S @@ -222,7 +222,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log movzbl %r12b, %r15d shlq $4, %r15 vmovsd 1160(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 1224(%rsp,%r15) jmp .LBL_1_8 @@ -230,7 +230,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log movzbl %r12b, %r15d shlq $4, %r15 vmovsd 1152(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 1216(%rsp,%r15) jmp .LBL_1_7 #endif @@ -443,7 +443,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log vzeroupper vmovsd 1160(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 1224(%rsp,%r15) jmp .LBL_2_8 @@ -455,7 +455,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN4v_log vzeroupper vmovsd 1152(%rsp,%r15), %xmm0 - call JUMPTARGET(__log_finite) + call JUMPTARGET(log) vmovsd %xmm0, 1216(%rsp,%r15) jmp .LBL_2_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S index 8f1fb39d6a291afb0f2d9fd5410f6fe878333b18..84e8199f0f4c3f55f263bf6f3a066e9395d963e5 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow2_core_sse4.S @@ -413,7 +413,7 @@ ENTRY (_ZGVbN2vv_pow_sse4) movsd 72(%rsp,%r15), %xmm0 movsd 136(%rsp,%r15), %xmm1 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) movsd %xmm0, 200(%rsp,%r15) jmp .LBL_1_8 @@ -424,7 +424,7 @@ ENTRY (_ZGVbN2vv_pow_sse4) movsd 64(%rsp,%r15), %xmm0 movsd 128(%rsp,%r15), %xmm1 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) movsd %xmm0, 192(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S index 9bf771a6503e03cd5e596267ea91c11c08111f47..39b601f9f09bcba5217ca8802297bc2237589588 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow4_core_avx2.S @@ -367,7 +367,7 @@ ENTRY (_ZGVdN4vv_pow_avx2) vmovsd 264(%rsp,%r15), %xmm1 vzeroupper - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 328(%rsp,%r15) jmp .LBL_1_8 @@ -379,7 +379,7 @@ ENTRY (_ZGVdN4vv_pow_avx2) vmovsd 256(%rsp,%r15), %xmm1 vzeroupper - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 320(%rsp,%r15) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S index 0ced819df4269a87a292232cde334842e9ea294d..861d166af71ea689d926201fba628d39dfab2267 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_d_pow8_core_avx512.S @@ -392,7 +392,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow shlq $4, %r15 vmovsd 1160(%rsp,%r15), %xmm0 vmovsd 1224(%rsp,%r15), %xmm1 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 1288(%rsp,%r15) jmp .LBL_1_8 @@ -401,7 +401,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow shlq $4, %r15 vmovsd 1152(%rsp,%r15), %xmm0 vmovsd 1216(%rsp,%r15), %xmm1 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 1280(%rsp,%r15) jmp .LBL_1_7 @@ -720,7 +720,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow vzeroupper vmovsd 1160(%rsp,%r15), %xmm0 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 1288(%rsp,%r15) jmp .LBL_2_8 @@ -732,7 +732,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN4vv_pow vzeroupper vmovsd 1152(%rsp,%r15), %xmm0 - call JUMPTARGET(__pow_finite) + call JUMPTARGET(pow) vmovsd %xmm0, 1280(%rsp,%r15) jmp .LBL_2_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S index e685b7489e9fdb6ad78f32f443ff460d37626528..c746b353d410bd0ac1be6b8176d59652de76770b 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf16_core_avx512.S @@ -212,14 +212,14 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf cfi_restore_state movzbl %r12b, %r15d vmovss 1156(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 1220(%rsp,%r15,8) jmp .LBL_1_8 .LBL_1_12: movzbl %r12b, %r15d vmovss 1152(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 1216(%rsp,%r15,8) jmp .LBL_1_7 @@ -422,7 +422,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf vzeroupper vmovss 1156(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 1220(%rsp,%r15,8) jmp .LBL_2_8 @@ -433,7 +433,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_expf vzeroupper vmovss 1152(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 1216(%rsp,%r15,8) jmp .LBL_2_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S index 2bf2a28ab666108d5bc989349796b85e3808b9b3..b031f4ff7eded23c6bc387eded3ab8b6170a739b 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf4_core_sse4.S @@ -195,7 +195,7 @@ ENTRY (_ZGVbN4v_expf_sse4) movzbl %r12b, %r15d movss 196(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) movss %xmm0, 260(%rsp,%r15,8) jmp .LBL_1_8 @@ -204,7 +204,7 @@ ENTRY (_ZGVbN4v_expf_sse4) movzbl %r12b, %r15d movss 192(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) movss %xmm0, 256(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S index 4538ef35eac4cf2482f8c5f51536798f3504e6d3..8d55961afe4898463142dea7628839de37071510 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_expf8_core_avx2.S @@ -184,7 +184,7 @@ ENTRY(_ZGVdN8v_expf_avx2) vmovss 324(%rsp,%r15,8), %xmm0 vzeroupper - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 388(%rsp,%r15,8) jmp .LBL_1_8 @@ -194,7 +194,7 @@ ENTRY(_ZGVdN8v_expf_avx2) vmovss 320(%rsp,%r15,8), %xmm0 vzeroupper - call JUMPTARGET(__expf_finite) + call JUMPTARGET(expf) vmovss %xmm0, 384(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S index 02b99da9a6a204c1ef5b018c01543cae13e40955..013795ed2a9f3e3f85c91ac389fdd3a58712499f 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf16_core_avx512.S @@ -197,14 +197,14 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf cfi_restore_state movzbl %r12b, %r15d vmovss 1156(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 1220(%rsp,%r15,8) jmp .LBL_1_8 .LBL_1_12: movzbl %r12b, %r15d vmovss 1152(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 1216(%rsp,%r15,8) jmp .LBL_1_7 #endif @@ -391,7 +391,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf vzeroupper vmovss 1156(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 1220(%rsp,%r15,8) jmp .LBL_2_8 @@ -402,7 +402,7 @@ WRAPPER_IMPL_AVX512 _ZGVdN8v_logf vzeroupper vmovss 1152(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 1216(%rsp,%r15,8) jmp .LBL_2_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S index 0d2ac78ffbde333adb0419aa386513b65f9dd980..c3a91933d2b30ace6c8f174ece632c0a0fd74a9e 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf4_core_sse4.S @@ -177,7 +177,7 @@ ENTRY (_ZGVbN4v_logf_sse4) movzbl %r12b, %r15d movss 196(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) movss %xmm0, 260(%rsp,%r15,8) jmp .LBL_1_8 @@ -186,7 +186,7 @@ ENTRY (_ZGVbN4v_logf_sse4) movzbl %r12b, %r15d movss 192(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) movss %xmm0, 256(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S index 38d35d0ac8a902d342fab9501a14b2ee719b7e74..fceec378a10067ce338df0f13cece0f5f0615c83 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_logf8_core_avx2.S @@ -166,7 +166,7 @@ ENTRY(_ZGVdN8v_logf_avx2) vmovss 324(%rsp,%r15,8), %xmm0 vzeroupper - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 388(%rsp,%r15,8) jmp .LBL_1_8 @@ -176,7 +176,7 @@ ENTRY(_ZGVdN8v_logf_avx2) vmovss 320(%rsp,%r15,8), %xmm0 vzeroupper - call JUMPTARGET(__logf_finite) + call JUMPTARGET(logf) vmovss %xmm0, 384(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S index 97b66bc9acbbd8dcc9e48286c17539fd45970c1b..237e1cbf90327eed61d30f987ef3d01c6dae233f 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf16_core_avx512.S @@ -344,7 +344,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf movzbl %r12b, %r15d vmovss 1156(%rsp,%r15,8), %xmm0 vmovss 1220(%rsp,%r15,8), %xmm1 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 1284(%rsp,%r15,8) jmp .LBL_1_8 @@ -352,7 +352,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf movzbl %r12b, %r15d vmovss 1152(%rsp,%r15,8), %xmm0 vmovss 1216(%rsp,%r15,8), %xmm1 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 1280(%rsp,%r15,8) jmp .LBL_1_7 #endif @@ -629,7 +629,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf vmovss 1156(%rsp,%r15,8), %xmm1 vzeroupper vmovss 1092(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 1220(%rsp,%r15,8) jmp .LBL_2_8 @@ -638,7 +638,7 @@ WRAPPER_IMPL_AVX512_ff _ZGVdN8vv_powf vmovss 1152(%rsp,%r15,8), %xmm1 vzeroupper vmovss 1088(%rsp,%r15,8), %xmm0 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 1216(%rsp,%r15,8) jmp .LBL_2_7 #endif diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S index ff5dffa21cb8f3afa264ab9c563056a0b1beacfa..85c0821b93dd698fe767dc6e650bf16eb3865f7b 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf4_core_sse4.S @@ -356,7 +356,7 @@ ENTRY (_ZGVbN4vv_powf_sse4) movss 68(%rsp,%r15,8), %xmm0 movss 132(%rsp,%r15,8), %xmm1 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) movss %xmm0, 196(%rsp,%r15,8) jmp .LBL_1_8 @@ -366,7 +366,7 @@ ENTRY (_ZGVbN4vv_powf_sse4) movss 64(%rsp,%r15,8), %xmm0 movss 128(%rsp,%r15,8), %xmm1 - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) movss %xmm0, 192(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S b/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S index 06f0c7f2d36b49d07c3e26039a9eed7733c713fc..7112962bf0e596e0f1ff846d6fea28019c2f4324 100644 --- a/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S +++ b/sysdeps/x86_64/fpu/multiarch/svml_s_powf8_core_avx2.S @@ -317,7 +317,7 @@ ENTRY(_ZGVdN8vv_powf_avx2) vmovss 132(%rsp,%r15,8), %xmm1 vzeroupper - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 196(%rsp,%r15,8) jmp .LBL_1_8 @@ -328,7 +328,7 @@ ENTRY(_ZGVdN8vv_powf_avx2) vmovss 128(%rsp,%r15,8), %xmm1 vzeroupper - call JUMPTARGET(__powf_finite) + call JUMPTARGET(powf) vmovss %xmm0, 192(%rsp,%r15,8) jmp .LBL_1_7 diff --git a/sysdeps/x86_64/fpu/svml_d_exp2_core.S b/sysdeps/x86_64/fpu/svml_d_exp2_core.S index 601f6aa35ff6297184aa5c5c41258cfb156751f7..58390e8c82f5622b34b19b0f88adc567f869f622 100644 --- a/sysdeps/x86_64/fpu/svml_d_exp2_core.S +++ b/sysdeps/x86_64/fpu/svml_d_exp2_core.S @@ -21,7 +21,7 @@ .text ENTRY (_ZGVbN2v_exp) -WRAPPER_IMPL_SSE2 __exp_finite +WRAPPER_IMPL_SSE2 exp END (_ZGVbN2v_exp) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/svml_d_log2_core.S b/sysdeps/x86_64/fpu/svml_d_log2_core.S index d3373963c68123b0db32306396449c9fe8d59fec..fed3b15c248055241639fd21851ee2ecba9c8e8d 100644 --- a/sysdeps/x86_64/fpu/svml_d_log2_core.S +++ b/sysdeps/x86_64/fpu/svml_d_log2_core.S @@ -21,7 +21,7 @@ .text ENTRY (_ZGVbN2v_log) -WRAPPER_IMPL_SSE2 __log_finite +WRAPPER_IMPL_SSE2 log END (_ZGVbN2v_log) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/svml_d_pow2_core.S b/sysdeps/x86_64/fpu/svml_d_pow2_core.S index f28c359282cb1bfc56719ae30fc4b1a0c2a52cff..8e6d9ffc26709df85aa0cb11b8ecb972289d0e83 100644 --- a/sysdeps/x86_64/fpu/svml_d_pow2_core.S +++ b/sysdeps/x86_64/fpu/svml_d_pow2_core.S @@ -21,7 +21,7 @@ .text ENTRY (_ZGVbN2vv_pow) -WRAPPER_IMPL_SSE2_ff __pow_finite +WRAPPER_IMPL_SSE2_ff pow END (_ZGVbN2vv_pow) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/svml_finite_alias.S b/sysdeps/x86_64/fpu/svml_finite_alias.S deleted file mode 100644 index c6008e9a24730bd3f3d514e13cb99c8d4a98ce7c..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/svml_finite_alias.S +++ /dev/null @@ -1,58 +0,0 @@ -/* These aliases added as workaround to exclude unnecessary symbol - aliases in libmvec.so while compiler creates the vector names - based on scalar asm name. Corresponding discussion is at - <https://gcc.gnu.org/ml/gcc/2015-06/msg00173.html>. - Copyright (C) 2015-2019 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 <sysdep.h> - -#define ALIAS_IMPL(alias, target) \ -ENTRY (alias); \ - jmp *target@GOTPCREL(%rip); \ -END (alias) - - .text -ALIAS_IMPL (_ZGVbN2v___log_finite, _ZGVbN2v_log) -ALIAS_IMPL (_ZGVcN4v___log_finite, _ZGVcN4v_log) -ALIAS_IMPL (_ZGVdN4v___log_finite, _ZGVdN4v_log) -ALIAS_IMPL (_ZGVeN8v___log_finite, _ZGVeN8v_log) - -ALIAS_IMPL (_ZGVbN4v___logf_finite, _ZGVbN4v_logf) -ALIAS_IMPL (_ZGVcN8v___logf_finite, _ZGVcN8v_logf) -ALIAS_IMPL (_ZGVdN8v___logf_finite, _ZGVdN8v_logf) -ALIAS_IMPL (_ZGVeN16v___logf_finite, _ZGVeN16v_logf) - -ALIAS_IMPL (_ZGVbN2v___exp_finite, _ZGVbN2v_exp) -ALIAS_IMPL (_ZGVcN4v___exp_finite, _ZGVcN4v_exp) -ALIAS_IMPL (_ZGVdN4v___exp_finite, _ZGVdN4v_exp) -ALIAS_IMPL (_ZGVeN8v___exp_finite, _ZGVeN8v_exp) - -ALIAS_IMPL (_ZGVbN4v___expf_finite, _ZGVbN4v_expf) -ALIAS_IMPL (_ZGVcN8v___expf_finite, _ZGVcN8v_expf) -ALIAS_IMPL (_ZGVdN8v___expf_finite, _ZGVdN8v_expf) -ALIAS_IMPL (_ZGVeN16v___expf_finite, _ZGVeN16v_expf) - -ALIAS_IMPL (_ZGVbN2vv___pow_finite, _ZGVbN2vv_pow) -ALIAS_IMPL (_ZGVcN4vv___pow_finite, _ZGVcN4vv_pow) -ALIAS_IMPL (_ZGVdN4vv___pow_finite, _ZGVdN4vv_pow) -ALIAS_IMPL (_ZGVeN8vv___pow_finite, _ZGVeN8vv_pow) - -ALIAS_IMPL (_ZGVbN4vv___powf_finite, _ZGVbN4vv_powf) -ALIAS_IMPL (_ZGVcN8vv___powf_finite, _ZGVcN8vv_powf) -ALIAS_IMPL (_ZGVdN8vv___powf_finite, _ZGVdN8vv_powf) -ALIAS_IMPL (_ZGVeN16vv___powf_finite, _ZGVeN16vv_powf) diff --git a/sysdeps/x86_64/fpu/svml_s_expf4_core.S b/sysdeps/x86_64/fpu/svml_s_expf4_core.S index 426b37f885261adb174b46346bb0040bdaab5089..ed6db8983a428de9f23b639f737cc3a3ff855199 100644 --- a/sysdeps/x86_64/fpu/svml_s_expf4_core.S +++ b/sysdeps/x86_64/fpu/svml_s_expf4_core.S @@ -22,7 +22,7 @@ .text ENTRY (_ZGVbN4v_expf) -WRAPPER_IMPL_SSE2 __expf_finite +WRAPPER_IMPL_SSE2 expf END (_ZGVbN4v_expf) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/svml_s_logf4_core.S b/sysdeps/x86_64/fpu/svml_s_logf4_core.S index 519ae44bcb93bcaafcf35f670362c82a36ea62e5..33312c4b0de9562518478f58b414b8b8b97ca621 100644 --- a/sysdeps/x86_64/fpu/svml_s_logf4_core.S +++ b/sysdeps/x86_64/fpu/svml_s_logf4_core.S @@ -22,7 +22,7 @@ .text ENTRY (_ZGVbN4v_logf) -WRAPPER_IMPL_SSE2 __logf_finite +WRAPPER_IMPL_SSE2 logf END (_ZGVbN4v_logf) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/svml_s_powf4_core.S b/sysdeps/x86_64/fpu/svml_s_powf4_core.S index 7e2a02830a8e0052868ab0d84648dfb1c5b5e65e..a8280b2e7c2d65e22a49ed0a9454c3ca723722f9 100644 --- a/sysdeps/x86_64/fpu/svml_s_powf4_core.S +++ b/sysdeps/x86_64/fpu/svml_s_powf4_core.S @@ -21,7 +21,7 @@ .text ENTRY (_ZGVbN4vv_powf) -WRAPPER_IMPL_SSE2_ff __powf_finite +WRAPPER_IMPL_SSE2_ff powf END (_ZGVbN4vv_powf) #ifndef USE_MULTIARCH diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c deleted file mode 100644 index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c deleted file mode 100644 index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx2.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c deleted file mode 100644 index 514883dcf983cd45bd6647e3af9a6c9cdb8f6997..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-avx512.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c deleted file mode 100644 index 43914ef0e72df618fc57d824972a0dec7e514881..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-double-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c deleted file mode 100644 index e57c00d9241fb1e99a02c16d25158a4f2e247d65..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias-mod.c +++ /dev/null @@ -1,25 +0,0 @@ -/* Part of test to build shared library to ensure link against - *_finite aliases from libmvec. - Copyright (C) 2016-2019 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 <math.h> -#include <stdlib.h> -#include <math-tests-arch.h> - -#include "test-double.h" -#include "test-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-alias.c b/sysdeps/x86_64/fpu/test-double-libmvec-alias.c deleted file mode 100644 index 340cf8bb6fbf267ddefc6308b74ad8207cdf67c4..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-double-libmvec-alias.c +++ /dev/null @@ -1,29 +0,0 @@ -/* Part of test to ensure link against *_finite aliases from libmvec. - Copyright (C) 2016-2019 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/>. */ - -extern int -test_finite_alias (void); - -static int -do_test (void) -{ - return test_finite_alias (); -} - -#define TEST_FUNCTION do_test () -#include "../../../test-skeleton.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c deleted file mode 100644 index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c deleted file mode 100644 index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx2.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c deleted file mode 100644 index 7fc3d8aedddaa3d8b96e27bd2581c3b088dbf2bd..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512-mod.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-avx512.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c deleted file mode 100644 index f3691cc8e6753cd47f0f8a408e7e4f1003bc80fe..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-main.c +++ /dev/null @@ -1 +0,0 @@ -#include "test-float-libmvec-alias.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c deleted file mode 100644 index abe16ee209a2d0d571362294fc15a93787c5bb9b..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias-mod.c +++ /dev/null @@ -1,25 +0,0 @@ -/* Part of test to build shared library to ensure link against - *_finite aliases from libmvec. - Copyright (C) 2016-2019 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 <math.h> -#include <stdlib.h> -#include <math-tests-arch.h> - -#include "test-float.h" -#include "test-libmvec-alias-mod.c" diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-alias.c b/sysdeps/x86_64/fpu/test-float-libmvec-alias.c deleted file mode 100644 index 340cf8bb6fbf267ddefc6308b74ad8207cdf67c4..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-float-libmvec-alias.c +++ /dev/null @@ -1,29 +0,0 @@ -/* Part of test to ensure link against *_finite aliases from libmvec. - Copyright (C) 2016-2019 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/>. */ - -extern int -test_finite_alias (void); - -static int -do_test (void) -{ - return test_finite_alias (); -} - -#define TEST_FUNCTION do_test () -#include "../../../test-skeleton.c" 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 b5fe71d5b30001e71cf039df4322fe602075a77a..0000000000000000000000000000000000000000 --- a/sysdeps/x86_64/fpu/test-libmvec-alias-mod.c +++ /dev/null @@ -1,66 +0,0 @@ -/* Part of test to build shared library to ensure link against - *_finite aliases from libmvec. - Copyright (C) 2016-2019 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/>. */ - -#define N 4000 -FLOAT log_arg[N]; -FLOAT exp_arg[N]; -FLOAT log_res[N]; -FLOAT exp_res[N]; -FLOAT pow_res[N]; -int arch_check = 1; - -static void -init_arg (void) -{ - int i; - - CHECK_ARCH_EXT; - - arch_check = 0; - - for (i = 0; i < N; i += 1) - { - log_arg[i] = 1.0; - exp_arg[i] = 0.0; - } -} - -int -test_finite_alias (void) -{ - int i; - - init_arg (); - - if (arch_check) return 77; - -#pragma omp simd - for (i = 0; i < N; i += 1) - { - log_res[i] = FUNC (log) (log_arg[i]); - exp_res[i] = FUNC (exp) (exp_arg[i]); - pow_res[i] = FUNC (pow) (log_arg[i], log_arg[i]); - } - - if (log_res[0] != 0.0) return 1; - if (exp_res[0] != 1.0) return 1; - if (pow_res[0] != 1.0) return 1; - - return 0; -}