/* { dg-final { check-function-bodies "**" "" "-DCHECK_ASM" } } */

#include "test_sve_acle.h"

/*
** tmad_0_f32_tied1:
**	ftmad	z0\.s, z0\.s, z1\.s, #0
**	ret
*/
TEST_UNIFORM_Z (tmad_0_f32_tied1, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 0),
		z0 = svtmad (z0, z1, 0))

/*
** tmad_0_f32_tied2:
**	mov	(z[0-9]+)\.d, z0\.d
**	movprfx	z0, z1
**	ftmad	z0\.s, z0\.s, \1\.s, #0
**	ret
*/
TEST_UNIFORM_Z (tmad_0_f32_tied2, svfloat32_t,
		z0 = svtmad_f32 (z1, z0, 0),
		z0 = svtmad (z1, z0, 0))

/*
** tmad_0_f32_untied:
**	movprfx	z0, z1
**	ftmad	z0\.s, z0\.s, z2\.s, #0
**	ret
*/
TEST_UNIFORM_Z (tmad_0_f32_untied, svfloat32_t,
		z0 = svtmad_f32 (z1, z2, 0),
		z0 = svtmad (z1, z2, 0))

/*
** tmad_1_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #1
**	ret
*/
TEST_UNIFORM_Z (tmad_1_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 1),
		z0 = svtmad (z0, z1, 1))

/*
** tmad_2_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #2
**	ret
*/
TEST_UNIFORM_Z (tmad_2_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 2),
		z0 = svtmad (z0, z1, 2))

/*
** tmad_3_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #3
**	ret
*/
TEST_UNIFORM_Z (tmad_3_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 3),
		z0 = svtmad (z0, z1, 3))

/*
** tmad_4_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #4
**	ret
*/
TEST_UNIFORM_Z (tmad_4_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 4),
		z0 = svtmad (z0, z1, 4))

/*
** tmad_5_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #5
**	ret
*/
TEST_UNIFORM_Z (tmad_5_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 5),
		z0 = svtmad (z0, z1, 5))

/*
** tmad_6_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #6
**	ret
*/
TEST_UNIFORM_Z (tmad_6_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 6),
		z0 = svtmad (z0, z1, 6))

/*
** tmad_7_f32:
**	ftmad	z0\.s, z0\.s, z1\.s, #7
**	ret
*/
TEST_UNIFORM_Z (tmad_7_f32, svfloat32_t,
		z0 = svtmad_f32 (z0, z1, 7),
		z0 = svtmad (z0, z1, 7))