From patchwork Wed Jun 26 14:00:45 2019 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Wilco Dijkstra X-Patchwork-Id: 33412 Received: (qmail 120898 invoked by alias); 26 Jun 2019 14:01:03 -0000 Mailing-List: contact libc-alpha-help@sourceware.org; run by ezmlm Precedence: bulk List-Id: List-Unsubscribe: List-Subscribe: List-Archive: List-Post: List-Help: , Sender: libc-alpha-owner@sourceware.org Delivered-To: mailing list libc-alpha@sourceware.org Received: (qmail 120888 invoked by uid 89); 26 Jun 2019 14:01:03 -0000 Authentication-Results: sourceware.org; auth=none X-Spam-SWARE-Status: No, score=-18.2 required=5.0 tests=AWL, BAYES_00, GIT_PATCH_0, GIT_PATCH_1, GIT_PATCH_2, GIT_PATCH_3, KAM_LOTSOFHASH, KAM_SHORT, RCVD_IN_DNSWL_NONE, SPF_HELO_PASS, SPF_PASS autolearn=ham version=3.3.1 spammy= X-HELO: EUR04-VI1-obe.outbound.protection.outlook.com DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; s=selector2-armh-onmicrosoft-com; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=ICeyoG0BqgsduXfSjqCJpL3F+HBZxOIJ1h1JAhdE3bc=; b=AvvCZUp+3WWhn0rabfb8txtcQFH3n1yYF0YKrWTbyGQpgJ72ZP6NQK9N+X4SNmptbwEGGg5zk4CI7iWOlFppbR3KmwWCadgWsT1WLU8ePvIkqCIGdfsT6LqJvrLI/a0dDhiVihaLfX96oTgk5CVr5VPVFLZQzFt5Ay7F7Nt397M= From: Wilco Dijkstra To: "libc-alpha@sourceware.org" CC: nd Subject: [PATCH 3/4] Remove x64 _finite tests and references Date: Wed, 26 Jun 2019 14:00:45 +0000 Message-ID: authentication-results: spf=none (sender IP is ) smtp.mailfrom=Wilco.Dijkstra@arm.com; x-ms-exchange-purlcount: 2 x-ms-oob-tlc-oobclassifiers: OLM:49; received-spf: None (protection.outlook.com: arm.com does not designate permitted sender hosts) x-ms-exchange-senderadcheck: 1 MIME-Version: 1.0 X-MS-Exchange-CrossTenant-mailboxtype: HOSTED X-MS-Exchange-CrossTenant-userprincipalname: Wilco.Dijkstra@arm.com 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 * 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. Reviewed-by: Adhemerval Zanella 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 - . - 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 - . */ - -#include - -#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 - . */ - -#include -#include -#include - -#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 - . */ - -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 - . */ - -#include -#include -#include - -#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 - . */ - -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 - . */ - -#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; -}