x86_64: Add missing libmvec ABI tests

Message ID 20211020212218.2834086-1-skpgkp2@gmail.com
State Committed
Commit 4f690aad9ee50ff54e94a7aac87c2a076d625f26
Headers
Series x86_64: Add missing libmvec ABI tests |

Checks

Context Check Description
dj/TryBot-apply_patch success Patch applied to master at the time it was sent
dj/TryBot-32bit success Build for i686

Commit Message

Sunil Pandey Oct. 20, 2021, 9:22 p.m. UTC
  Add vector ABI tests for cos, exp, log, pow and sin functions.
---
 sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
 .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
 .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
 .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
 .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
 .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
 .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
 .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
 .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
 .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
 .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
 .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
 .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
 .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
 .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
 .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
 .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
 .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
 .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
 .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
 .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
 .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
 .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
 .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
 .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
 .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
 .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
 .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
 .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
 .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
 .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
 sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
 sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46 +++++++++++++++++++
 43 files changed, 152 insertions(+), 8 deletions(-)
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
 create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
 create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
 create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
  

Comments

Noah Goldstein Oct. 20, 2021, 10:48 p.m. UTC | #1
On Wed, Oct 20, 2021 at 4:22 PM Sunil K Pandey <skpgkp2@gmail.com> wrote:
>
> Add vector ABI tests for cos, exp, log, pow and sin functions.
> ---
>  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
>  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
>  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
>  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
>  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
>  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
>  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
>  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
>  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46 +++++++++++++++++++
>  43 files changed, 152 insertions(+), 8 deletions(-)
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>
> diff --git a/sysdeps/x86_64/fpu/Makeconfig b/sysdeps/x86_64/fpu/Makeconfig
> index 0a9341cdd9..24aaee1a43 100644
> --- a/sysdeps/x86_64/fpu/Makeconfig
> +++ b/sysdeps/x86_64/fpu/Makeconfig
> @@ -29,15 +29,10 @@ libmvec-funcs = \
>    sin \
>    sincos \
>
> -# FIXME: Add ABI tests for all libmvec functions and replace
> -# libmvec-abi-funcs with libmvec-funcs.
> -libmvec-abi-funcs = \
> -  sincos
> -
>  # The base libmvec ABI tests.
>  libmvec-abi-func-tests = \
> -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
> -  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-abi-funcs)))
> +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
> +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
>
>  # The AVX libmvec ABI tests.
>  libmvec-abi-func-avx-tests = \
> @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk: $(common-objpfx)config.make
>              echo; \
>            done; \
>          done; \
> -        for t in $(libmvec-abi-funcs); do \
> +        for t in $(libmvec-funcs); do \
>            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
>            echo "  \$$(libmvec-abi-test-cflags)"; \
>            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> new file mode 100644
> index 0000000000..ebc688163e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC cos
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> new file mode 100644
> index 0000000000..fd8143aacc
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC exp
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> new file mode 100644
> index 0000000000..a17a02ca66
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC log
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> new file mode 100644
> index 0000000000..c70e24b663
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC pow
> +#include "test-vector-abi-arg2.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> new file mode 100644
> index 0000000000..bc2fb3c614
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC sin
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> new file mode 100644
> index 0000000000..d8ecea7e6a
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC cosf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> new file mode 100644
> index 0000000000..0c21b9ae83
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC expf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> new file mode 100644
> index 0000000000..964d869e72
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC logf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> new file mode 100644
> index 0000000000..ef8559b0ca
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC powf
> +#include "test-vector-abi-arg2.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> new file mode 100644
> index 0000000000..00d3255ccf
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC sinf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> new file mode 100644
> index 0000000000..962fafcd0b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> @@ -0,0 +1,43 @@
> +/* Test for vector ABI with a single argument.
> +   Copyright (C) 2016-2021 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
> +   <https://www.gnu.org/licenses/>.  */
> +
> +#include <math.h>
> +#include <support/test-driver.h>
> +
> +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> +   defines do_test, reference support_test_main here to include it to
> +   avoid undefined reference to support_test_main.  The libmvec ABI test
> +   doesn't need other symbols in libsupport_nonshared.a.  */
> +__typeof (support_test_main) *support_test_main_p = support_test_main;
> +
> +#define N 1000
> +LIBMVEC_TYPE x[N], c[N];
> +
> +int
> +test_vector_abi (void)
> +{
> +  int i;
> +  for(i = 0; i < N; i++)
> +    c[i] = i / 3;
> +
> +#pragma omp simd

Do we need this?

> +  for(i = 0; i < N; i++)
> +    x[i] = LIBMVEC_FUNC (c[i]);
> +
> +  return 0;
> +}
> diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> new file mode 100644
> index 0000000000..4b7e10d26b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> @@ -0,0 +1,46 @@
> +/* Test for vector ABI with 2 arguments.
> +   Copyright (C) 2016-2021 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
> +   <https://www.gnu.org/licenses/>.  */
> +
> +#include <math.h>
> +#include <support/test-driver.h>
> +
> +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> +   defines do_test, reference support_test_main here to include it to
> +   avoid undefined reference to support_test_main.  The libmvec ABI test
> +   doesn't need other symbols in libsupport_nonshared.a.  */
> +__typeof (support_test_main) *support_test_main_p = support_test_main;
> +
> +#define N 1000
> +LIBMVEC_TYPE x[N], s[N], c[N];
> +
> +int
> +test_vector_abi (void)
> +{
> +  int i;
> +  for(i = 0; i < N; i++)
> +    {
> +      c[i] = i / 3;

Is there a reason for 'i / 3'?

> +      s[i] = c[i];
> +    }
> +
> +#pragma omp simd

Do we need this?

> +  for(i = 0; i < N; i++)
> +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
> +
> +  return 0;
> +}
> --
> 2.31.1
>
  
Sunil Pandey Oct. 21, 2021, 12:10 a.m. UTC | #2
On Wed, Oct 20, 2021 at 3:48 PM Noah Goldstein <goldstein.w.n@gmail.com>
wrote:

> On Wed, Oct 20, 2021 at 4:22 PM Sunil K Pandey <skpgkp2@gmail.com> wrote:
> >
> > Add vector ABI tests for cos, exp, log, pow and sin functions.
> > ---
> >  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
> >  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
> >  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
> >  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
> >  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
> >  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
> >  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
> >  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
> >  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
> >  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
> >  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
> >  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
> >  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
> >  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
> >  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
> >  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
> >  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
> >  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
> >  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
> >  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
> >  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
> >  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
> >  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
> >  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
> >  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
> >  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
> >  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
> >  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
> >  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
> >  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
> >  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
> >  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
> >  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
> >  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46 +++++++++++++++++++
> >  43 files changed, 152 insertions(+), 8 deletions(-)
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> >
> > diff --git a/sysdeps/x86_64/fpu/Makeconfig
> b/sysdeps/x86_64/fpu/Makeconfig
> > index 0a9341cdd9..24aaee1a43 100644
> > --- a/sysdeps/x86_64/fpu/Makeconfig
> > +++ b/sysdeps/x86_64/fpu/Makeconfig
> > @@ -29,15 +29,10 @@ libmvec-funcs = \
> >    sin \
> >    sincos \
> >
> > -# FIXME: Add ABI tests for all libmvec functions and replace
> > -# libmvec-abi-funcs with libmvec-funcs.
> > -libmvec-abi-funcs = \
> > -  sincos
> > -
> >  # The base libmvec ABI tests.
> >  libmvec-abi-func-tests = \
> > -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
> > -  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-abi-funcs)))
> > +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
> > +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
> >
> >  # The AVX libmvec ABI tests.
> >  libmvec-abi-func-avx-tests = \
> > @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk:
> $(common-objpfx)config.make
> >              echo; \
> >            done; \
> >          done; \
> > -        for t in $(libmvec-abi-funcs); do \
> > +        for t in $(libmvec-funcs); do \
> >            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
> >            echo "  \$$(libmvec-abi-test-cflags)"; \
> >            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> > new file mode 100644
> > index 0000000000..f2b3e8e883
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-cos.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> > new file mode 100644
> > index 0000000000..f2b3e8e883
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-cos.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> > new file mode 100644
> > index 0000000000..f2b3e8e883
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-cos.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> > new file mode 100644
> > index 0000000000..ebc688163e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE double
> > +#define LIBMVEC_FUNC cos
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> > new file mode 100644
> > index 0000000000..fb485c3558
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-exp.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> > new file mode 100644
> > index 0000000000..fb485c3558
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-exp.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> > new file mode 100644
> > index 0000000000..fb485c3558
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-exp.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> > new file mode 100644
> > index 0000000000..fd8143aacc
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE double
> > +#define LIBMVEC_FUNC exp
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> > new file mode 100644
> > index 0000000000..1acdf16a6e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-log.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> > new file mode 100644
> > index 0000000000..1acdf16a6e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-log.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> > new file mode 100644
> > index 0000000000..1acdf16a6e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-log.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> > new file mode 100644
> > index 0000000000..a17a02ca66
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE double
> > +#define LIBMVEC_FUNC log
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> > new file mode 100644
> > index 0000000000..7c921ccad5
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-pow.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> > new file mode 100644
> > index 0000000000..7c921ccad5
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-pow.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> > new file mode 100644
> > index 0000000000..7c921ccad5
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-pow.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> > new file mode 100644
> > index 0000000000..c70e24b663
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE double
> > +#define LIBMVEC_FUNC pow
> > +#include "test-vector-abi-arg2.h"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> > new file mode 100644
> > index 0000000000..c785cd0445
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-sin.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> > new file mode 100644
> > index 0000000000..c785cd0445
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-sin.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> > new file mode 100644
> > index 0000000000..c785cd0445
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-double-libmvec-sin.c"
> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> > new file mode 100644
> > index 0000000000..bc2fb3c614
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE double
> > +#define LIBMVEC_FUNC sin
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> > new file mode 100644
> > index 0000000000..928f4b607b
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-cosf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> > new file mode 100644
> > index 0000000000..928f4b607b
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-cosf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> > new file mode 100644
> > index 0000000000..928f4b607b
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-cosf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> > new file mode 100644
> > index 0000000000..d8ecea7e6a
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE float
> > +#define LIBMVEC_FUNC cosf
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> > new file mode 100644
> > index 0000000000..9e0b6d667c
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-expf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> > new file mode 100644
> > index 0000000000..9e0b6d667c
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-expf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> > new file mode 100644
> > index 0000000000..9e0b6d667c
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-expf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> > new file mode 100644
> > index 0000000000..0c21b9ae83
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE float
> > +#define LIBMVEC_FUNC expf
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> > new file mode 100644
> > index 0000000000..92767c9462
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-logf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> > new file mode 100644
> > index 0000000000..92767c9462
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-logf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> > new file mode 100644
> > index 0000000000..92767c9462
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-logf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> > new file mode 100644
> > index 0000000000..964d869e72
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE float
> > +#define LIBMVEC_FUNC logf
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> > new file mode 100644
> > index 0000000000..e00d4e73e0
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-powf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> > new file mode 100644
> > index 0000000000..e00d4e73e0
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-powf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> > new file mode 100644
> > index 0000000000..e00d4e73e0
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-powf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> > new file mode 100644
> > index 0000000000..ef8559b0ca
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE float
> > +#define LIBMVEC_FUNC powf
> > +#include "test-vector-abi-arg2.h"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> > new file mode 100644
> > index 0000000000..302886760e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-sinf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> > new file mode 100644
> > index 0000000000..302886760e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-sinf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> > new file mode 100644
> > index 0000000000..302886760e
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> > @@ -0,0 +1 @@
> > +#include "test-float-libmvec-sinf.c"
> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> > new file mode 100644
> > index 0000000000..00d3255ccf
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> > @@ -0,0 +1,3 @@
> > +#define LIBMVEC_TYPE float
> > +#define LIBMVEC_FUNC sinf
> > +#include "test-vector-abi-arg1.h"
> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> > new file mode 100644
> > index 0000000000..962fafcd0b
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> > @@ -0,0 +1,43 @@
> > +/* Test for vector ABI with a single argument.
> > +   Copyright (C) 2016-2021 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
> > +   <https://www.gnu.org/licenses/>.  */
> > +
> > +#include <math.h>
> > +#include <support/test-driver.h>
> > +
> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> > +   defines do_test, reference support_test_main here to include it to
> > +   avoid undefined reference to support_test_main.  The libmvec ABI test
> > +   doesn't need other symbols in libsupport_nonshared.a.  */
> > +__typeof (support_test_main) *support_test_main_p = support_test_main;
> > +
> > +#define N 1000
> > +LIBMVEC_TYPE x[N], c[N];
> > +
> > +int
> > +test_vector_abi (void)
> > +{
> > +  int i;
> > +  for(i = 0; i < N; i++)
> > +    c[i] = i / 3;
> > +
> > +#pragma omp simd
>
> Do we need this?
>
Yes, omp pragma forces function to vectorize. Without it, depending on the
gcc version it may or may not vectorize.
For libmvec ABI test LIBMVEC_FUNC needs to be vectorized.
https://sourceware.org/glibc/wiki/libmvec


> > +  for(i = 0; i < N; i++)
> > +    x[i] = LIBMVEC_FUNC (c[i]);
> > +
> > +  return 0;
> > +}
> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> > new file mode 100644
> > index 0000000000..4b7e10d26b
> > --- /dev/null
> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> > @@ -0,0 +1,46 @@
> > +/* Test for vector ABI with 2 arguments.
> > +   Copyright (C) 2016-2021 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
> > +   <https://www.gnu.org/licenses/>.  */
> > +
> > +#include <math.h>
> > +#include <support/test-driver.h>
> > +
> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> > +   defines do_test, reference support_test_main here to include it to
> > +   avoid undefined reference to support_test_main.  The libmvec ABI test
> > +   doesn't need other symbols in libsupport_nonshared.a.  */
> > +__typeof (support_test_main) *support_test_main_p = support_test_main;
> > +
> > +#define N 1000
> > +LIBMVEC_TYPE x[N], s[N], c[N];
> > +
> > +int
> > +test_vector_abi (void)
> > +{
> > +  int i;
> > +  for(i = 0; i < N; i++)
> > +    {
> > +      c[i] = i / 3;
>
> Is there a reason for 'i / 3'?

Nothing special about i/3.  It could be initialized with any float/double
number.

>


> > +      s[i] = c[i];
> > +    }
> > +
> > +#pragma omp simd
>
> Do we need this?
>
Same as above.

>
> > +  for(i = 0; i < N; i++)
> > +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
> > +
> > +  return 0;
> > +}
> > --
> > 2.31.1
> >
>
  
Noah Goldstein Oct. 21, 2021, 1:37 a.m. UTC | #3
On Wed, Oct 20, 2021 at 7:10 PM Sunil Pandey <skpgkp2@gmail.com> wrote:
>
>
>
> On Wed, Oct 20, 2021 at 3:48 PM Noah Goldstein <goldstein.w.n@gmail.com> wrote:
>>
>> On Wed, Oct 20, 2021 at 4:22 PM Sunil K Pandey <skpgkp2@gmail.com> wrote:
>> >
>> > Add vector ABI tests for cos, exp, log, pow and sin functions.
>> > ---
>> >  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
>> >  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
>> >  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
>> >  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
>> >  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
>> >  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
>> >  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
>> >  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
>> >  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
>> >  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
>> >  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
>> >  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
>> >  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
>> >  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
>> >  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
>> >  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
>> >  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
>> >  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
>> >  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
>> >  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
>> >  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
>> >  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
>> >  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
>> >  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
>> >  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
>> >  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
>> >  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
>> >  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
>> >  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
>> >  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
>> >  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
>> >  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
>> >  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
>> >  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46 +++++++++++++++++++
>> >  43 files changed, 152 insertions(+), 8 deletions(-)
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> >
>> > diff --git a/sysdeps/x86_64/fpu/Makeconfig b/sysdeps/x86_64/fpu/Makeconfig
>> > index 0a9341cdd9..24aaee1a43 100644
>> > --- a/sysdeps/x86_64/fpu/Makeconfig
>> > +++ b/sysdeps/x86_64/fpu/Makeconfig
>> > @@ -29,15 +29,10 @@ libmvec-funcs = \
>> >    sin \
>> >    sincos \
>> >
>> > -# FIXME: Add ABI tests for all libmvec functions and replace
>> > -# libmvec-abi-funcs with libmvec-funcs.
>> > -libmvec-abi-funcs = \
>> > -  sincos
>> > -
>> >  # The base libmvec ABI tests.
>> >  libmvec-abi-func-tests = \
>> > -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
>> > -  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-abi-funcs)))
>> > +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
>> > +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
>> >
>> >  # The AVX libmvec ABI tests.
>> >  libmvec-abi-func-avx-tests = \
>> > @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk: $(common-objpfx)config.make
>> >              echo; \
>> >            done; \
>> >          done; \
>> > -        for t in $(libmvec-abi-funcs); do \
>> > +        for t in $(libmvec-funcs); do \
>> >            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
>> >            echo "  \$$(libmvec-abi-test-cflags)"; \
>> >            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> > new file mode 100644
>> > index 0000000000..f2b3e8e883
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-cos.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> > new file mode 100644
>> > index 0000000000..f2b3e8e883
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-cos.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> > new file mode 100644
>> > index 0000000000..f2b3e8e883
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-cos.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> > new file mode 100644
>> > index 0000000000..ebc688163e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE double
>> > +#define LIBMVEC_FUNC cos
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> > new file mode 100644
>> > index 0000000000..fb485c3558
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-exp.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> > new file mode 100644
>> > index 0000000000..fb485c3558
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-exp.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> > new file mode 100644
>> > index 0000000000..fb485c3558
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-exp.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> > new file mode 100644
>> > index 0000000000..fd8143aacc
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE double
>> > +#define LIBMVEC_FUNC exp
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> > new file mode 100644
>> > index 0000000000..1acdf16a6e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-log.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> > new file mode 100644
>> > index 0000000000..1acdf16a6e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-log.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> > new file mode 100644
>> > index 0000000000..1acdf16a6e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-log.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> > new file mode 100644
>> > index 0000000000..a17a02ca66
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE double
>> > +#define LIBMVEC_FUNC log
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> > new file mode 100644
>> > index 0000000000..7c921ccad5
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-pow.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> > new file mode 100644
>> > index 0000000000..7c921ccad5
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-pow.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> > new file mode 100644
>> > index 0000000000..7c921ccad5
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-pow.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> > new file mode 100644
>> > index 0000000000..c70e24b663
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE double
>> > +#define LIBMVEC_FUNC pow
>> > +#include "test-vector-abi-arg2.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> > new file mode 100644
>> > index 0000000000..c785cd0445
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-sin.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> > new file mode 100644
>> > index 0000000000..c785cd0445
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-sin.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> > new file mode 100644
>> > index 0000000000..c785cd0445
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-double-libmvec-sin.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> > new file mode 100644
>> > index 0000000000..bc2fb3c614
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE double
>> > +#define LIBMVEC_FUNC sin
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> > new file mode 100644
>> > index 0000000000..928f4b607b
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-cosf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> > new file mode 100644
>> > index 0000000000..928f4b607b
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-cosf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> > new file mode 100644
>> > index 0000000000..928f4b607b
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-cosf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> > new file mode 100644
>> > index 0000000000..d8ecea7e6a
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE float
>> > +#define LIBMVEC_FUNC cosf
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> > new file mode 100644
>> > index 0000000000..9e0b6d667c
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-expf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> > new file mode 100644
>> > index 0000000000..9e0b6d667c
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-expf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> > new file mode 100644
>> > index 0000000000..9e0b6d667c
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-expf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> > new file mode 100644
>> > index 0000000000..0c21b9ae83
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE float
>> > +#define LIBMVEC_FUNC expf
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> > new file mode 100644
>> > index 0000000000..92767c9462
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-logf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> > new file mode 100644
>> > index 0000000000..92767c9462
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-logf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> > new file mode 100644
>> > index 0000000000..92767c9462
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-logf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> > new file mode 100644
>> > index 0000000000..964d869e72
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE float
>> > +#define LIBMVEC_FUNC logf
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> > new file mode 100644
>> > index 0000000000..e00d4e73e0
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-powf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> > new file mode 100644
>> > index 0000000000..e00d4e73e0
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-powf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> > new file mode 100644
>> > index 0000000000..e00d4e73e0
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-powf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> > new file mode 100644
>> > index 0000000000..ef8559b0ca
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE float
>> > +#define LIBMVEC_FUNC powf
>> > +#include "test-vector-abi-arg2.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> > new file mode 100644
>> > index 0000000000..302886760e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-sinf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> > new file mode 100644
>> > index 0000000000..302886760e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-sinf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> > new file mode 100644
>> > index 0000000000..302886760e
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> > @@ -0,0 +1 @@
>> > +#include "test-float-libmvec-sinf.c"
>> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> > new file mode 100644
>> > index 0000000000..00d3255ccf
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> > @@ -0,0 +1,3 @@
>> > +#define LIBMVEC_TYPE float
>> > +#define LIBMVEC_FUNC sinf
>> > +#include "test-vector-abi-arg1.h"
>> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> > new file mode 100644
>> > index 0000000000..962fafcd0b
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> > @@ -0,0 +1,43 @@
>> > +/* Test for vector ABI with a single argument.
>> > +   Copyright (C) 2016-2021 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
>> > +   <https://www.gnu.org/licenses/>.  */
>> > +
>> > +#include <math.h>
>> > +#include <support/test-driver.h>
>> > +
>> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
>> > +   defines do_test, reference support_test_main here to include it to
>> > +   avoid undefined reference to support_test_main.  The libmvec ABI test
>> > +   doesn't need other symbols in libsupport_nonshared.a.  */
>> > +__typeof (support_test_main) *support_test_main_p = support_test_main;
>> > +
>> > +#define N 1000
>> > +LIBMVEC_TYPE x[N], c[N];
>> > +
>> > +int
>> > +test_vector_abi (void)
>> > +{
>> > +  int i;
>> > +  for(i = 0; i < N; i++)
>> > +    c[i] = i / 3;
>> > +
>> > +#pragma omp simd
>>
>> Do we need this?
>
> Yes, omp pragma forces function to vectorize. Without it, depending on the gcc version it may or may not vectorize.
> For libmvec ABI test LIBMVEC_FUNC needs to be vectorized.
> https://sourceware.org/glibc/wiki/libmvec

I see. Makes sense. Is there any way we can guarantee the correct version is
actually being tested? Or is this test purely that the code will compile / run
with the tested build flags?

>
>>
>> > +  for(i = 0; i < N; i++)
>> > +    x[i] = LIBMVEC_FUNC (c[i]);
>> > +
>> > +  return 0;
>> > +}
>> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> > new file mode 100644
>> > index 0000000000..4b7e10d26b
>> > --- /dev/null
>> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> > @@ -0,0 +1,46 @@
>> > +/* Test for vector ABI with 2 arguments.
>> > +   Copyright (C) 2016-2021 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
>> > +   <https://www.gnu.org/licenses/>.  */
>> > +
>> > +#include <math.h>
>> > +#include <support/test-driver.h>
>> > +
>> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
>> > +   defines do_test, reference support_test_main here to include it to
>> > +   avoid undefined reference to support_test_main.  The libmvec ABI test
>> > +   doesn't need other symbols in libsupport_nonshared.a.  */
>> > +__typeof (support_test_main) *support_test_main_p = support_test_main;
>> > +
>> > +#define N 1000
>> > +LIBMVEC_TYPE x[N], s[N], c[N];
>> > +
>> > +int
>> > +test_vector_abi (void)
>> > +{
>> > +  int i;
>> > +  for(i = 0; i < N; i++)
>> > +    {
>> > +      c[i] = i / 3;
>>
>> Is there a reason for 'i / 3'?
>
> Nothing special about i/3.  It could be initialized with any float/double number.

Maybe 2 for faster initialization. Not important though.
>>
>>
>>
>>
>> > +      s[i] = c[i];
>> > +    }
>> > +
>> > +#pragma omp simd
>>
>> Do we need this?
>
> Same as above.
>>
>>
>> > +  for(i = 0; i < N; i++)
>> > +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
>> > +
>> > +  return 0;
>> > +}
>> > --
>> > 2.31.1
>> >
  
Sunil Pandey Oct. 21, 2021, 3:29 a.m. UTC | #4
On Wed, Oct 20, 2021 at 6:37 PM Noah Goldstein <goldstein.w.n@gmail.com>
wrote:

> On Wed, Oct 20, 2021 at 7:10 PM Sunil Pandey <skpgkp2@gmail.com> wrote:
> >
> >
> >
> > On Wed, Oct 20, 2021 at 3:48 PM Noah Goldstein <goldstein.w.n@gmail.com>
> wrote:
> >>
> >> On Wed, Oct 20, 2021 at 4:22 PM Sunil K Pandey <skpgkp2@gmail.com>
> wrote:
> >> >
> >> > Add vector ABI tests for cos, exp, log, pow and sin functions.
> >> > ---
> >> >  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
> >> >  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
> >> >  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
> >> >  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
> >> >  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
> >> >  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
> >> >  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
> >> >  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
> >> >  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
> >> >  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
> >> >  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
> >> >  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
> >> >  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
> >> >  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
> >> >  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
> >> >  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
> >> >  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
> >> >  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
> >> >  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
> >> >  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
> >> >  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
> >> >  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
> >> >  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
> >> >  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
> >> >  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46
> +++++++++++++++++++
> >> >  43 files changed, 152 insertions(+), 8 deletions(-)
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> >> >  create mode 100644
> sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> >> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> >> >
> >> > diff --git a/sysdeps/x86_64/fpu/Makeconfig
> b/sysdeps/x86_64/fpu/Makeconfig
> >> > index 0a9341cdd9..24aaee1a43 100644
> >> > --- a/sysdeps/x86_64/fpu/Makeconfig
> >> > +++ b/sysdeps/x86_64/fpu/Makeconfig
> >> > @@ -29,15 +29,10 @@ libmvec-funcs = \
> >> >    sin \
> >> >    sincos \
> >> >
> >> > -# FIXME: Add ABI tests for all libmvec functions and replace
> >> > -# libmvec-abi-funcs with libmvec-funcs.
> >> > -libmvec-abi-funcs = \
> >> > -  sincos
> >> > -
> >> >  # The base libmvec ABI tests.
> >> >  libmvec-abi-func-tests = \
> >> > -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
> >> > -  $(addsuffix f,$(addprefix
> test-float-libmvec-,$(libmvec-abi-funcs)))
> >> > +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
> >> > +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
> >> >
> >> >  # The AVX libmvec ABI tests.
> >> >  libmvec-abi-func-avx-tests = \
> >> > @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk:
> $(common-objpfx)config.make
> >> >              echo; \
> >> >            done; \
> >> >          done; \
> >> > -        for t in $(libmvec-abi-funcs); do \
> >> > +        for t in $(libmvec-funcs); do \
> >> >            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
> >> >            echo "  \$$(libmvec-abi-test-cflags)"; \
> >> >            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> >> > new file mode 100644
> >> > index 0000000000..f2b3e8e883
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-cos.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..f2b3e8e883
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-cos.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..f2b3e8e883
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-cos.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> >> > new file mode 100644
> >> > index 0000000000..ebc688163e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE double
> >> > +#define LIBMVEC_FUNC cos
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> >> > new file mode 100644
> >> > index 0000000000..fb485c3558
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-exp.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..fb485c3558
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-exp.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..fb485c3558
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-exp.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> >> > new file mode 100644
> >> > index 0000000000..fd8143aacc
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE double
> >> > +#define LIBMVEC_FUNC exp
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> >> > new file mode 100644
> >> > index 0000000000..1acdf16a6e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-log.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..1acdf16a6e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-log.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..1acdf16a6e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-log.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> >> > new file mode 100644
> >> > index 0000000000..a17a02ca66
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE double
> >> > +#define LIBMVEC_FUNC log
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> >> > new file mode 100644
> >> > index 0000000000..7c921ccad5
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-pow.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..7c921ccad5
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-pow.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..7c921ccad5
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-pow.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> >> > new file mode 100644
> >> > index 0000000000..c70e24b663
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE double
> >> > +#define LIBMVEC_FUNC pow
> >> > +#include "test-vector-abi-arg2.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> >> > new file mode 100644
> >> > index 0000000000..c785cd0445
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-sin.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..c785cd0445
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-sin.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..c785cd0445
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-double-libmvec-sin.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> >> > new file mode 100644
> >> > index 0000000000..bc2fb3c614
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE double
> >> > +#define LIBMVEC_FUNC sin
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> >> > new file mode 100644
> >> > index 0000000000..928f4b607b
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-cosf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..928f4b607b
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-cosf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..928f4b607b
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-cosf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> >> > new file mode 100644
> >> > index 0000000000..d8ecea7e6a
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE float
> >> > +#define LIBMVEC_FUNC cosf
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> >> > new file mode 100644
> >> > index 0000000000..9e0b6d667c
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-expf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..9e0b6d667c
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-expf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..9e0b6d667c
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-expf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> >> > new file mode 100644
> >> > index 0000000000..0c21b9ae83
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE float
> >> > +#define LIBMVEC_FUNC expf
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> >> > new file mode 100644
> >> > index 0000000000..92767c9462
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-logf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..92767c9462
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-logf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..92767c9462
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-logf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> >> > new file mode 100644
> >> > index 0000000000..964d869e72
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE float
> >> > +#define LIBMVEC_FUNC logf
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> >> > new file mode 100644
> >> > index 0000000000..e00d4e73e0
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-powf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..e00d4e73e0
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-powf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..e00d4e73e0
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-powf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> >> > new file mode 100644
> >> > index 0000000000..ef8559b0ca
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE float
> >> > +#define LIBMVEC_FUNC powf
> >> > +#include "test-vector-abi-arg2.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> >> > new file mode 100644
> >> > index 0000000000..302886760e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-sinf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> >> > new file mode 100644
> >> > index 0000000000..302886760e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-sinf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> >> > new file mode 100644
> >> > index 0000000000..302886760e
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> >> > @@ -0,0 +1 @@
> >> > +#include "test-float-libmvec-sinf.c"
> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> >> > new file mode 100644
> >> > index 0000000000..00d3255ccf
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> >> > @@ -0,0 +1,3 @@
> >> > +#define LIBMVEC_TYPE float
> >> > +#define LIBMVEC_FUNC sinf
> >> > +#include "test-vector-abi-arg1.h"
> >> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> >> > new file mode 100644
> >> > index 0000000000..962fafcd0b
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> >> > @@ -0,0 +1,43 @@
> >> > +/* Test for vector ABI with a single argument.
> >> > +   Copyright (C) 2016-2021 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
> >> > +   <https://www.gnu.org/licenses/>.  */
> >> > +
> >> > +#include <math.h>
> >> > +#include <support/test-driver.h>
> >> > +
> >> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o,
> which
> >> > +   defines do_test, reference support_test_main here to include it to
> >> > +   avoid undefined reference to support_test_main.  The libmvec ABI
> test
> >> > +   doesn't need other symbols in libsupport_nonshared.a.  */
> >> > +__typeof (support_test_main) *support_test_main_p =
> support_test_main;
> >> > +
> >> > +#define N 1000
> >> > +LIBMVEC_TYPE x[N], c[N];
> >> > +
> >> > +int
> >> > +test_vector_abi (void)
> >> > +{
> >> > +  int i;
> >> > +  for(i = 0; i < N; i++)
> >> > +    c[i] = i / 3;
> >> > +
> >> > +#pragma omp simd
> >>
> >> Do we need this?
> >
> > Yes, omp pragma forces function to vectorize. Without it, depending on
> the gcc version it may or may not vectorize.
> > For libmvec ABI test LIBMVEC_FUNC needs to be vectorized.
> > https://sourceware.org/glibc/wiki/libmvec
>
> I see. Makes sense. Is there any way we can guarantee the correct version
> is
> actually being tested? Or is this test purely that the code will compile /
> run
> with the tested build flags?
>
This code will just compile/run with tested  build flags.

>
> >
> >>
> >> > +  for(i = 0; i < N; i++)
> >> > +    x[i] = LIBMVEC_FUNC (c[i]);
> >> > +
> >> > +  return 0;
> >> > +}
> >> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> >> > new file mode 100644
> >> > index 0000000000..4b7e10d26b
> >> > --- /dev/null
> >> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> >> > @@ -0,0 +1,46 @@
> >> > +/* Test for vector ABI with 2 arguments.
> >> > +   Copyright (C) 2016-2021 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
> >> > +   <https://www.gnu.org/licenses/>.  */
> >> > +
> >> > +#include <math.h>
> >> > +#include <support/test-driver.h>
> >> > +
> >> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o,
> which
> >> > +   defines do_test, reference support_test_main here to include it to
> >> > +   avoid undefined reference to support_test_main.  The libmvec ABI
> test
> >> > +   doesn't need other symbols in libsupport_nonshared.a.  */
> >> > +__typeof (support_test_main) *support_test_main_p =
> support_test_main;
> >> > +
> >> > +#define N 1000
> >> > +LIBMVEC_TYPE x[N], s[N], c[N];
> >> > +
> >> > +int
> >> > +test_vector_abi (void)
> >> > +{
> >> > +  int i;
> >> > +  for(i = 0; i < N; i++)
> >> > +    {
> >> > +      c[i] = i / 3;
> >>
> >> Is there a reason for 'i / 3'?
> >
> > Nothing special about i/3.  It could be initialized with any
> float/double number.
>
> Maybe 2 for faster initialization. Not important though.

Same code is used for float and double implementation.  Though not very
important in this case, i/3 will create test input with more precision.

>

>>
> >>
> >>
> >>
> >> > +      s[i] = c[i];
> >> > +    }
> >> > +
> >> > +#pragma omp simd
> >>
> >> Do we need this?
> >
> > Same as above.
> >>
> >>
> >> > +  for(i = 0; i < N; i++)
> >> > +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
> >> > +
> >> > +  return 0;
> >> > +}
> >> > --
> >> > 2.31.1
> >> >
>
  
Sunil Pandey Oct. 22, 2021, 1:10 p.m. UTC | #5
OK for trunk?

On Wed, Oct 20, 2021 at 8:29 PM Sunil Pandey <skpgkp2@gmail.com> wrote:

>
>
> On Wed, Oct 20, 2021 at 6:37 PM Noah Goldstein <goldstein.w.n@gmail.com>
> wrote:
>
>> On Wed, Oct 20, 2021 at 7:10 PM Sunil Pandey <skpgkp2@gmail.com> wrote:
>> >
>> >
>> >
>> > On Wed, Oct 20, 2021 at 3:48 PM Noah Goldstein <goldstein.w.n@gmail.com>
>> wrote:
>> >>
>> >> On Wed, Oct 20, 2021 at 4:22 PM Sunil K Pandey <skpgkp2@gmail.com>
>> wrote:
>> >> >
>> >> > Add vector ABI tests for cos, exp, log, pow and sin functions.
>> >> > ---
>> >> >  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
>> >> >  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
>> >> >  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
>> >> >  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
>> >> >  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
>> >> >  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
>> >> >  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
>> >> >  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
>> >> >  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
>> >> >  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
>> >> >  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
>> >> >  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
>> >> >  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
>> >> >  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
>> >> >  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
>> >> >  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
>> >> >  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
>> >> >  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
>> >> >  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
>> >> >  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
>> >> >  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
>> >> >  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
>> >> >  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
>> >> >  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
>> >> >  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46
>> +++++++++++++++++++
>> >> >  43 files changed, 152 insertions(+), 8 deletions(-)
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> >> >  create mode 100644
>> sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> >> >  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> >> >
>> >> > diff --git a/sysdeps/x86_64/fpu/Makeconfig
>> b/sysdeps/x86_64/fpu/Makeconfig
>> >> > index 0a9341cdd9..24aaee1a43 100644
>> >> > --- a/sysdeps/x86_64/fpu/Makeconfig
>> >> > +++ b/sysdeps/x86_64/fpu/Makeconfig
>> >> > @@ -29,15 +29,10 @@ libmvec-funcs = \
>> >> >    sin \
>> >> >    sincos \
>> >> >
>> >> > -# FIXME: Add ABI tests for all libmvec functions and replace
>> >> > -# libmvec-abi-funcs with libmvec-funcs.
>> >> > -libmvec-abi-funcs = \
>> >> > -  sincos
>> >> > -
>> >> >  # The base libmvec ABI tests.
>> >> >  libmvec-abi-func-tests = \
>> >> > -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
>> >> > -  $(addsuffix f,$(addprefix
>> test-float-libmvec-,$(libmvec-abi-funcs)))
>> >> > +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
>> >> > +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
>> >> >
>> >> >  # The AVX libmvec ABI tests.
>> >> >  libmvec-abi-func-avx-tests = \
>> >> > @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk:
>> $(common-objpfx)config.make
>> >> >              echo; \
>> >> >            done; \
>> >> >          done; \
>> >> > -        for t in $(libmvec-abi-funcs); do \
>> >> > +        for t in $(libmvec-funcs); do \
>> >> >            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
>> >> >            echo "  \$$(libmvec-abi-test-cflags)"; \
>> >> >            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..f2b3e8e883
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-cos.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..f2b3e8e883
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-cos.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..f2b3e8e883
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-cos.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> >> > new file mode 100644
>> >> > index 0000000000..ebc688163e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE double
>> >> > +#define LIBMVEC_FUNC cos
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..fb485c3558
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-exp.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..fb485c3558
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-exp.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..fb485c3558
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-exp.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> >> > new file mode 100644
>> >> > index 0000000000..fd8143aacc
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE double
>> >> > +#define LIBMVEC_FUNC exp
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..1acdf16a6e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-log.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..1acdf16a6e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-log.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..1acdf16a6e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-log.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> >> > new file mode 100644
>> >> > index 0000000000..a17a02ca66
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE double
>> >> > +#define LIBMVEC_FUNC log
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..7c921ccad5
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-pow.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..7c921ccad5
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-pow.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..7c921ccad5
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-pow.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> >> > new file mode 100644
>> >> > index 0000000000..c70e24b663
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE double
>> >> > +#define LIBMVEC_FUNC pow
>> >> > +#include "test-vector-abi-arg2.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..c785cd0445
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-sin.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..c785cd0445
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-sin.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..c785cd0445
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-double-libmvec-sin.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> >> > new file mode 100644
>> >> > index 0000000000..bc2fb3c614
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE double
>> >> > +#define LIBMVEC_FUNC sin
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..928f4b607b
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-cosf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..928f4b607b
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-cosf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..928f4b607b
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-cosf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> >> > new file mode 100644
>> >> > index 0000000000..d8ecea7e6a
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE float
>> >> > +#define LIBMVEC_FUNC cosf
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..9e0b6d667c
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-expf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..9e0b6d667c
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-expf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..9e0b6d667c
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-expf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> >> > new file mode 100644
>> >> > index 0000000000..0c21b9ae83
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE float
>> >> > +#define LIBMVEC_FUNC expf
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..92767c9462
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-logf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..92767c9462
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-logf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..92767c9462
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-logf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> >> > new file mode 100644
>> >> > index 0000000000..964d869e72
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE float
>> >> > +#define LIBMVEC_FUNC logf
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..e00d4e73e0
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-powf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..e00d4e73e0
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-powf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..e00d4e73e0
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-powf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> >> > new file mode 100644
>> >> > index 0000000000..ef8559b0ca
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE float
>> >> > +#define LIBMVEC_FUNC powf
>> >> > +#include "test-vector-abi-arg2.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> >> > new file mode 100644
>> >> > index 0000000000..302886760e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-sinf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> >> > new file mode 100644
>> >> > index 0000000000..302886760e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-sinf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> >> > new file mode 100644
>> >> > index 0000000000..302886760e
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>> >> > @@ -0,0 +1 @@
>> >> > +#include "test-float-libmvec-sinf.c"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> >> > new file mode 100644
>> >> > index 0000000000..00d3255ccf
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>> >> > @@ -0,0 +1,3 @@
>> >> > +#define LIBMVEC_TYPE float
>> >> > +#define LIBMVEC_FUNC sinf
>> >> > +#include "test-vector-abi-arg1.h"
>> >> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> >> > new file mode 100644
>> >> > index 0000000000..962fafcd0b
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>> >> > @@ -0,0 +1,43 @@
>> >> > +/* Test for vector ABI with a single argument.
>> >> > +   Copyright (C) 2016-2021 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
>> >> > +   <https://www.gnu.org/licenses/>.  */
>> >> > +
>> >> > +#include <math.h>
>> >> > +#include <support/test-driver.h>
>> >> > +
>> >> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o,
>> which
>> >> > +   defines do_test, reference support_test_main here to include it
>> to
>> >> > +   avoid undefined reference to support_test_main.  The libmvec ABI
>> test
>> >> > +   doesn't need other symbols in libsupport_nonshared.a.  */
>> >> > +__typeof (support_test_main) *support_test_main_p =
>> support_test_main;
>> >> > +
>> >> > +#define N 1000
>> >> > +LIBMVEC_TYPE x[N], c[N];
>> >> > +
>> >> > +int
>> >> > +test_vector_abi (void)
>> >> > +{
>> >> > +  int i;
>> >> > +  for(i = 0; i < N; i++)
>> >> > +    c[i] = i / 3;
>> >> > +
>> >> > +#pragma omp simd
>> >>
>> >> Do we need this?
>> >
>> > Yes, omp pragma forces function to vectorize. Without it, depending on
>> the gcc version it may or may not vectorize.
>> > For libmvec ABI test LIBMVEC_FUNC needs to be vectorized.
>> > https://sourceware.org/glibc/wiki/libmvec
>>
>> I see. Makes sense. Is there any way we can guarantee the correct version
>> is
>> actually being tested? Or is this test purely that the code will compile
>> / run
>> with the tested build flags?
>>
> This code will just compile/run with tested  build flags.
>
>>
>> >
>> >>
>> >> > +  for(i = 0; i < N; i++)
>> >> > +    x[i] = LIBMVEC_FUNC (c[i]);
>> >> > +
>> >> > +  return 0;
>> >> > +}
>> >> > diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> >> > new file mode 100644
>> >> > index 0000000000..4b7e10d26b
>> >> > --- /dev/null
>> >> > +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>> >> > @@ -0,0 +1,46 @@
>> >> > +/* Test for vector ABI with 2 arguments.
>> >> > +   Copyright (C) 2016-2021 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
>> >> > +   <https://www.gnu.org/licenses/>.  */
>> >> > +
>> >> > +#include <math.h>
>> >> > +#include <support/test-driver.h>
>> >> > +
>> >> > +/* Since libsupport_nonshared.a is placed before test-libmvec*.o,
>> which
>> >> > +   defines do_test, reference support_test_main here to include it
>> to
>> >> > +   avoid undefined reference to support_test_main.  The libmvec ABI
>> test
>> >> > +   doesn't need other symbols in libsupport_nonshared.a.  */
>> >> > +__typeof (support_test_main) *support_test_main_p =
>> support_test_main;
>> >> > +
>> >> > +#define N 1000
>> >> > +LIBMVEC_TYPE x[N], s[N], c[N];
>> >> > +
>> >> > +int
>> >> > +test_vector_abi (void)
>> >> > +{
>> >> > +  int i;
>> >> > +  for(i = 0; i < N; i++)
>> >> > +    {
>> >> > +      c[i] = i / 3;
>> >>
>> >> Is there a reason for 'i / 3'?
>> >
>> > Nothing special about i/3.  It could be initialized with any
>> float/double number.
>>
>> Maybe 2 for faster initialization. Not important though.
>
> Same code is used for float and double implementation.  Though not very
> important in this case, i/3 will create test input with more precision.
>
>>
>
> >>
>> >>
>> >>
>> >>
>> >> > +      s[i] = c[i];
>> >> > +    }
>> >> > +
>> >> > +#pragma omp simd
>> >>
>> >> Do we need this?
>> >
>> > Same as above.
>> >>
>> >>
>> >> > +  for(i = 0; i < N; i++)
>> >> > +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
>> >> > +
>> >> > +  return 0;
>> >> > +}
>> >> > --
>> >> > 2.31.1
>> >> >
>>
>
  
H.J. Lu Oct. 22, 2021, 1:17 p.m. UTC | #6
On Wed, Oct 20, 2021 at 2:22 PM Sunil K Pandey <skpgkp2@gmail.com> wrote:
>
> Add vector ABI tests for cos, exp, log, pow and sin functions.
> ---
>  sysdeps/x86_64/fpu/Makeconfig                 | 11 ++---
>  .../x86_64/fpu/test-double-libmvec-cos-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-cos-avx2.c |  1 +
>  .../fpu/test-double-libmvec-cos-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-cos.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-exp-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-exp-avx2.c |  1 +
>  .../fpu/test-double-libmvec-exp-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-exp.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-log-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-log-avx2.c |  1 +
>  .../fpu/test-double-libmvec-log-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-log.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-pow-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-pow-avx2.c |  1 +
>  .../fpu/test-double-libmvec-pow-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-pow.c  |  3 ++
>  .../x86_64/fpu/test-double-libmvec-sin-avx.c  |  1 +
>  .../x86_64/fpu/test-double-libmvec-sin-avx2.c |  1 +
>  .../fpu/test-double-libmvec-sin-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-double-libmvec-sin.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-cosf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-cosf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-cosf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-cosf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-expf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-expf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-expf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-expf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-logf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-logf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-logf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-logf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-powf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-powf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-powf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-powf.c  |  3 ++
>  .../x86_64/fpu/test-float-libmvec-sinf-avx.c  |  1 +
>  .../x86_64/fpu/test-float-libmvec-sinf-avx2.c |  1 +
>  .../fpu/test-float-libmvec-sinf-avx512f.c     |  1 +
>  sysdeps/x86_64/fpu/test-float-libmvec-sinf.c  |  3 ++
>  sysdeps/x86_64/fpu/test-vector-abi-arg1.h     | 43 +++++++++++++++++
>  sysdeps/x86_64/fpu/test-vector-abi-arg2.h     | 46 +++++++++++++++++++
>  43 files changed, 152 insertions(+), 8 deletions(-)
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-cos.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-exp.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-log.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-pow.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-double-libmvec-sin.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-expf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-logf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-powf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
>  create mode 100644 sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
>  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg1.h
>  create mode 100644 sysdeps/x86_64/fpu/test-vector-abi-arg2.h
>
> diff --git a/sysdeps/x86_64/fpu/Makeconfig b/sysdeps/x86_64/fpu/Makeconfig
> index 0a9341cdd9..24aaee1a43 100644
> --- a/sysdeps/x86_64/fpu/Makeconfig
> +++ b/sysdeps/x86_64/fpu/Makeconfig
> @@ -29,15 +29,10 @@ libmvec-funcs = \
>    sin \
>    sincos \
>
> -# FIXME: Add ABI tests for all libmvec functions and replace
> -# libmvec-abi-funcs with libmvec-funcs.
> -libmvec-abi-funcs = \
> -  sincos
> -
>  # The base libmvec ABI tests.
>  libmvec-abi-func-tests = \
> -  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
> -  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-abi-funcs)))
> +  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
> +  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
>
>  # The AVX libmvec ABI tests.
>  libmvec-abi-func-avx-tests = \
> @@ -62,7 +57,7 @@ $(common-objpfx)libmvec.mk: $(common-objpfx)config.make
>              echo; \
>            done; \
>          done; \
> -        for t in $(libmvec-abi-funcs); do \
> +        for t in $(libmvec-funcs); do \
>            echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
>            echo "  \$$(libmvec-abi-test-cflags)"; \
>            echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> new file mode 100644
> index 0000000000..f2b3e8e883
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-cos.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> new file mode 100644
> index 0000000000..ebc688163e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC cos
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> new file mode 100644
> index 0000000000..fb485c3558
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-exp.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> new file mode 100644
> index 0000000000..fd8143aacc
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC exp
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> new file mode 100644
> index 0000000000..1acdf16a6e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-log.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> new file mode 100644
> index 0000000000..a17a02ca66
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC log
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> new file mode 100644
> index 0000000000..7c921ccad5
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-pow.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> new file mode 100644
> index 0000000000..c70e24b663
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC pow
> +#include "test-vector-abi-arg2.h"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> new file mode 100644
> index 0000000000..c785cd0445
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-double-libmvec-sin.c"
> diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> new file mode 100644
> index 0000000000..bc2fb3c614
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE double
> +#define LIBMVEC_FUNC sin
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> new file mode 100644
> index 0000000000..928f4b607b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-cosf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> new file mode 100644
> index 0000000000..d8ecea7e6a
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC cosf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> new file mode 100644
> index 0000000000..9e0b6d667c
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-expf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> new file mode 100644
> index 0000000000..0c21b9ae83
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC expf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> new file mode 100644
> index 0000000000..92767c9462
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-logf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> new file mode 100644
> index 0000000000..964d869e72
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC logf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> new file mode 100644
> index 0000000000..e00d4e73e0
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-powf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> new file mode 100644
> index 0000000000..ef8559b0ca
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC powf
> +#include "test-vector-abi-arg2.h"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> new file mode 100644
> index 0000000000..302886760e
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
> @@ -0,0 +1 @@
> +#include "test-float-libmvec-sinf.c"
> diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> new file mode 100644
> index 0000000000..00d3255ccf
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
> @@ -0,0 +1,3 @@
> +#define LIBMVEC_TYPE float
> +#define LIBMVEC_FUNC sinf
> +#include "test-vector-abi-arg1.h"
> diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> new file mode 100644
> index 0000000000..962fafcd0b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
> @@ -0,0 +1,43 @@
> +/* Test for vector ABI with a single argument.
> +   Copyright (C) 2016-2021 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
> +   <https://www.gnu.org/licenses/>.  */
> +
> +#include <math.h>
> +#include <support/test-driver.h>
> +
> +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> +   defines do_test, reference support_test_main here to include it to
> +   avoid undefined reference to support_test_main.  The libmvec ABI test
> +   doesn't need other symbols in libsupport_nonshared.a.  */
> +__typeof (support_test_main) *support_test_main_p = support_test_main;
> +
> +#define N 1000
> +LIBMVEC_TYPE x[N], c[N];
> +
> +int
> +test_vector_abi (void)
> +{
> +  int i;
> +  for(i = 0; i < N; i++)
> +    c[i] = i / 3;
> +
> +#pragma omp simd
> +  for(i = 0; i < N; i++)
> +    x[i] = LIBMVEC_FUNC (c[i]);
> +
> +  return 0;
> +}
> diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> new file mode 100644
> index 0000000000..4b7e10d26b
> --- /dev/null
> +++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
> @@ -0,0 +1,46 @@
> +/* Test for vector ABI with 2 arguments.
> +   Copyright (C) 2016-2021 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
> +   <https://www.gnu.org/licenses/>.  */
> +
> +#include <math.h>
> +#include <support/test-driver.h>
> +
> +/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
> +   defines do_test, reference support_test_main here to include it to
> +   avoid undefined reference to support_test_main.  The libmvec ABI test
> +   doesn't need other symbols in libsupport_nonshared.a.  */
> +__typeof (support_test_main) *support_test_main_p = support_test_main;
> +
> +#define N 1000
> +LIBMVEC_TYPE x[N], s[N], c[N];
> +
> +int
> +test_vector_abi (void)
> +{
> +  int i;
> +  for(i = 0; i < N; i++)
> +    {
> +      c[i] = i / 3;
> +      s[i] = c[i];
> +    }
> +
> +#pragma omp simd
> +  for(i = 0; i < N; i++)
> +    x[i] = LIBMVEC_FUNC (s[i], c[i]);
> +
> +  return 0;
> +}
> --
> 2.31.1
>

LGTM.

Reviewed-by: H.J. Lu <hjl.tools@gmail.com>

Thanks.
  

Patch

diff --git a/sysdeps/x86_64/fpu/Makeconfig b/sysdeps/x86_64/fpu/Makeconfig
index 0a9341cdd9..24aaee1a43 100644
--- a/sysdeps/x86_64/fpu/Makeconfig
+++ b/sysdeps/x86_64/fpu/Makeconfig
@@ -29,15 +29,10 @@  libmvec-funcs = \
   sin \
   sincos \
 
-# FIXME: Add ABI tests for all libmvec functions and replace
-# libmvec-abi-funcs with libmvec-funcs.
-libmvec-abi-funcs = \
-  sincos
-
 # The base libmvec ABI tests.
 libmvec-abi-func-tests = \
-  $(addprefix test-double-libmvec-,$(libmvec-abi-funcs)) \
-  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-abi-funcs)))
+  $(addprefix test-double-libmvec-,$(libmvec-funcs)) \
+  $(addsuffix f,$(addprefix test-float-libmvec-,$(libmvec-funcs)))
 
 # The AVX libmvec ABI tests.
 libmvec-abi-func-avx-tests = \
@@ -62,7 +57,7 @@  $(common-objpfx)libmvec.mk: $(common-objpfx)config.make
 	     echo; \
 	   done; \
 	 done; \
-	 for t in $(libmvec-abi-funcs); do \
+	 for t in $(libmvec-funcs); do \
 	   echo "CFLAGS-test-double-libmvec-$$t.c = \\"; \
 	   echo "  \$$(libmvec-abi-test-cflags)"; \
 	   echo "CFLAGS-test-double-libmvec-$$t-avx.c = \\"; \
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
new file mode 100644
index 0000000000..f2b3e8e883
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-cos.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
new file mode 100644
index 0000000000..f2b3e8e883
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx2.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-cos.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
new file mode 100644
index 0000000000..f2b3e8e883
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-cos.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-cos.c b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
new file mode 100644
index 0000000000..ebc688163e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-cos.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE double
+#define LIBMVEC_FUNC cos
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
new file mode 100644
index 0000000000..fb485c3558
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-exp.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
new file mode 100644
index 0000000000..fb485c3558
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx2.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-exp.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
new file mode 100644
index 0000000000..fb485c3558
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-exp.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-exp.c b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
new file mode 100644
index 0000000000..fd8143aacc
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-exp.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE double
+#define LIBMVEC_FUNC exp
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
new file mode 100644
index 0000000000..1acdf16a6e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-log.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
new file mode 100644
index 0000000000..1acdf16a6e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx2.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-log.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
new file mode 100644
index 0000000000..1acdf16a6e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-log-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-log.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-log.c b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
new file mode 100644
index 0000000000..a17a02ca66
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-log.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE double
+#define LIBMVEC_FUNC log
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
new file mode 100644
index 0000000000..7c921ccad5
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-pow.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
new file mode 100644
index 0000000000..7c921ccad5
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx2.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-pow.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
new file mode 100644
index 0000000000..7c921ccad5
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-pow.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-pow.c b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
new file mode 100644
index 0000000000..c70e24b663
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-pow.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE double
+#define LIBMVEC_FUNC pow
+#include "test-vector-abi-arg2.h"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
new file mode 100644
index 0000000000..c785cd0445
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-sin.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
new file mode 100644
index 0000000000..c785cd0445
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx2.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-sin.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
new file mode 100644
index 0000000000..c785cd0445
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-double-libmvec-sin.c"
diff --git a/sysdeps/x86_64/fpu/test-double-libmvec-sin.c b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
new file mode 100644
index 0000000000..bc2fb3c614
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-double-libmvec-sin.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE double
+#define LIBMVEC_FUNC sin
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
new file mode 100644
index 0000000000..928f4b607b
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-cosf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
new file mode 100644
index 0000000000..928f4b607b
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx2.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-cosf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
new file mode 100644
index 0000000000..928f4b607b
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-cosf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
new file mode 100644
index 0000000000..d8ecea7e6a
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-cosf.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE float
+#define LIBMVEC_FUNC cosf
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
new file mode 100644
index 0000000000..9e0b6d667c
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-expf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
new file mode 100644
index 0000000000..9e0b6d667c
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx2.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-expf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
new file mode 100644
index 0000000000..9e0b6d667c
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-expf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-expf.c b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
new file mode 100644
index 0000000000..0c21b9ae83
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-expf.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE float
+#define LIBMVEC_FUNC expf
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
new file mode 100644
index 0000000000..92767c9462
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-logf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
new file mode 100644
index 0000000000..92767c9462
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx2.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-logf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
new file mode 100644
index 0000000000..92767c9462
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-logf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-logf.c b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
new file mode 100644
index 0000000000..964d869e72
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-logf.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE float
+#define LIBMVEC_FUNC logf
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
new file mode 100644
index 0000000000..e00d4e73e0
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-powf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
new file mode 100644
index 0000000000..e00d4e73e0
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx2.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-powf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
new file mode 100644
index 0000000000..e00d4e73e0
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-powf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-powf.c b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
new file mode 100644
index 0000000000..ef8559b0ca
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-powf.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE float
+#define LIBMVEC_FUNC powf
+#include "test-vector-abi-arg2.h"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
new file mode 100644
index 0000000000..302886760e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-sinf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
new file mode 100644
index 0000000000..302886760e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx2.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-sinf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
new file mode 100644
index 0000000000..302886760e
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf-avx512f.c
@@ -0,0 +1 @@ 
+#include "test-float-libmvec-sinf.c"
diff --git a/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
new file mode 100644
index 0000000000..00d3255ccf
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-float-libmvec-sinf.c
@@ -0,0 +1,3 @@ 
+#define LIBMVEC_TYPE float
+#define LIBMVEC_FUNC sinf
+#include "test-vector-abi-arg1.h"
diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg1.h b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
new file mode 100644
index 0000000000..962fafcd0b
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-vector-abi-arg1.h
@@ -0,0 +1,43 @@ 
+/* Test for vector ABI with a single argument.
+   Copyright (C) 2016-2021 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
+   <https://www.gnu.org/licenses/>.  */
+
+#include <math.h>
+#include <support/test-driver.h>
+
+/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
+   defines do_test, reference support_test_main here to include it to
+   avoid undefined reference to support_test_main.  The libmvec ABI test
+   doesn't need other symbols in libsupport_nonshared.a.  */
+__typeof (support_test_main) *support_test_main_p = support_test_main;
+
+#define N 1000
+LIBMVEC_TYPE x[N], c[N];
+
+int
+test_vector_abi (void)
+{
+  int i;
+  for(i = 0; i < N; i++)
+    c[i] = i / 3;
+
+#pragma omp simd
+  for(i = 0; i < N; i++)
+    x[i] = LIBMVEC_FUNC (c[i]);
+
+  return 0;
+}
diff --git a/sysdeps/x86_64/fpu/test-vector-abi-arg2.h b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
new file mode 100644
index 0000000000..4b7e10d26b
--- /dev/null
+++ b/sysdeps/x86_64/fpu/test-vector-abi-arg2.h
@@ -0,0 +1,46 @@ 
+/* Test for vector ABI with 2 arguments.
+   Copyright (C) 2016-2021 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
+   <https://www.gnu.org/licenses/>.  */
+
+#include <math.h>
+#include <support/test-driver.h>
+
+/* Since libsupport_nonshared.a is placed before test-libmvec*.o, which
+   defines do_test, reference support_test_main here to include it to
+   avoid undefined reference to support_test_main.  The libmvec ABI test
+   doesn't need other symbols in libsupport_nonshared.a.  */
+__typeof (support_test_main) *support_test_main_p = support_test_main;
+
+#define N 1000
+LIBMVEC_TYPE x[N], s[N], c[N];
+
+int
+test_vector_abi (void)
+{
+  int i;
+  for(i = 0; i < N; i++)
+    {
+      c[i] = i / 3;
+      s[i] = c[i];
+    }
+
+#pragma omp simd
+  for(i = 0; i < N; i++)
+    x[i] = LIBMVEC_FUNC (s[i], c[i]);
+
+  return 0;
+}