Viewing file:  test_passing_m512.c (11.47 KB) -rw-r--r--
Select action/file-type:
 (+) |  (+) |  (+) | Code (+) | Session (+) |  (+) | SDB (+) |  (+) |  (+) |  (+) |  (+) |  (+) |
#include <stdio.h>
#include "avx512fp16-zmm-check.h"
#include "args.h"
struct IntegerRegisters iregs;
struct FloatRegisters fregs;
unsigned int num_iregs, num_fregs;
/* This struct holds values for argument checking. */
struct
{
ZMM_T i0, i1, i2, i3, i4, i5, i6, i7, i8, i9, i10, i11, i12, i13, i14, i15,
i16, i17, i18, i19, i20, i21, i22, i23;
} values;
char *pass;
int failed = 0;
#undef assert
#define assert(c) do { \
if (!(c)) {failed++; printf ("failed %s\n", pass); } \
} while (0)
#define compare(X1,X2,T) do { \
assert (memcmp (&X1, &X2, sizeof (T)) == 0); \
} while (0)
fun_check_passing_m512_8_values (__m512 i0 ATTRIBUTE_UNUSED,
__m512 i1 ATTRIBUTE_UNUSED,
__m512 i2 ATTRIBUTE_UNUSED,
__m512 i3 ATTRIBUTE_UNUSED,
__m512 i4 ATTRIBUTE_UNUSED,
__m512 i5 ATTRIBUTE_UNUSED,
__m512 i6 ATTRIBUTE_UNUSED,
__m512 i7 ATTRIBUTE_UNUSED)
{
/* Check argument values. */
compare (values.i0, i0, __m512);
compare (values.i1, i1, __m512);
compare (values.i2, i2, __m512);
compare (values.i3, i3, __m512);
compare (values.i4, i4, __m512);
compare (values.i5, i5, __m512);
compare (values.i6, i6, __m512);
compare (values.i7, i7, __m512);
}
fun_check_passing_m512h_8_values (__m512h i0 ATTRIBUTE_UNUSED,
__m512h i1 ATTRIBUTE_UNUSED,
__m512h i2 ATTRIBUTE_UNUSED,
__m512h i3 ATTRIBUTE_UNUSED,
__m512h i4 ATTRIBUTE_UNUSED,
__m512h i5 ATTRIBUTE_UNUSED,
__m512h i6 ATTRIBUTE_UNUSED,
__m512h i7 ATTRIBUTE_UNUSED)
{
/* Check argument values. */
compare (values.i0, i0, __m512h);
compare (values.i1, i1, __m512h);
compare (values.i2, i2, __m512h);
compare (values.i3, i3, __m512h);
compare (values.i4, i4, __m512h);
compare (values.i5, i5, __m512h);
compare (values.i6, i6, __m512h);
compare (values.i7, i7, __m512h);
}
void
fun_check_passing_m512_8_regs (__m512 i0 ATTRIBUTE_UNUSED,
__m512 i1 ATTRIBUTE_UNUSED,
__m512 i2 ATTRIBUTE_UNUSED,
__m512 i3 ATTRIBUTE_UNUSED,
__m512 i4 ATTRIBUTE_UNUSED,
__m512 i5 ATTRIBUTE_UNUSED,
__m512 i6 ATTRIBUTE_UNUSED,
__m512 i7 ATTRIBUTE_UNUSED)
{
/* Check register contents. */
check_m512_arguments;
}
void
fun_check_passing_m512h_8_regs (__m512h i0 ATTRIBUTE_UNUSED,
__m512h i1 ATTRIBUTE_UNUSED,
__m512h i2 ATTRIBUTE_UNUSED,
__m512h i3 ATTRIBUTE_UNUSED,
__m512h i4 ATTRIBUTE_UNUSED,
__m512h i5 ATTRIBUTE_UNUSED,
__m512h i6 ATTRIBUTE_UNUSED,
__m512h i7 ATTRIBUTE_UNUSED)
{
/* Check register contents. */
check_m512_arguments;
}
void
fun_check_passing_m512_20_values (__m512 i0 ATTRIBUTE_UNUSED,
__m512 i1 ATTRIBUTE_UNUSED,
__m512 i2 ATTRIBUTE_UNUSED,
__m512 i3 ATTRIBUTE_UNUSED,
__m512 i4 ATTRIBUTE_UNUSED,
__m512 i5 ATTRIBUTE_UNUSED,
__m512 i6 ATTRIBUTE_UNUSED,
__m512 i7 ATTRIBUTE_UNUSED,
__m512 i8 ATTRIBUTE_UNUSED,
__m512 i9 ATTRIBUTE_UNUSED,
__m512 i10 ATTRIBUTE_UNUSED,
__m512 i11 ATTRIBUTE_UNUSED,
__m512 i12 ATTRIBUTE_UNUSED,
__m512 i13 ATTRIBUTE_UNUSED,
__m512 i14 ATTRIBUTE_UNUSED,
__m512 i15 ATTRIBUTE_UNUSED,
__m512 i16 ATTRIBUTE_UNUSED,
__m512 i17 ATTRIBUTE_UNUSED,
__m512 i18 ATTRIBUTE_UNUSED,
__m512 i19 ATTRIBUTE_UNUSED)
{
/* Check argument values. */
compare (values.i0, i0, __m512);
compare (values.i1, i1, __m512);
compare (values.i2, i2, __m512);
compare (values.i3, i3, __m512);
compare (values.i4, i4, __m512);
compare (values.i5, i5, __m512);
compare (values.i6, i6, __m512);
compare (values.i7, i7, __m512);
compare (values.i8, i8, __m512);
compare (values.i9, i9, __m512);
compare (values.i10, i10, __m512);
compare (values.i11, i11, __m512);
compare (values.i12, i12, __m512);
compare (values.i13, i13, __m512);
compare (values.i14, i14, __m512);
compare (values.i15, i15, __m512);
compare (values.i16, i16, __m512);
compare (values.i17, i17, __m512);
compare (values.i18, i18, __m512);
compare (values.i19, i19, __m512);
}
void
fun_check_passing_m512h_20_values (__m512h i0 ATTRIBUTE_UNUSED,
__m512h i1 ATTRIBUTE_UNUSED,
__m512h i2 ATTRIBUTE_UNUSED,
__m512h i3 ATTRIBUTE_UNUSED,
__m512h i4 ATTRIBUTE_UNUSED,
__m512h i5 ATTRIBUTE_UNUSED,
__m512h i6 ATTRIBUTE_UNUSED,
__m512h i7 ATTRIBUTE_UNUSED,
__m512h i8 ATTRIBUTE_UNUSED,
__m512h i9 ATTRIBUTE_UNUSED,
__m512h i10 ATTRIBUTE_UNUSED,
__m512h i11 ATTRIBUTE_UNUSED,
__m512h i12 ATTRIBUTE_UNUSED,
__m512h i13 ATTRIBUTE_UNUSED,
__m512h i14 ATTRIBUTE_UNUSED,
__m512h i15 ATTRIBUTE_UNUSED,
__m512h i16 ATTRIBUTE_UNUSED,
__m512h i17 ATTRIBUTE_UNUSED,
__m512h i18 ATTRIBUTE_UNUSED,
__m512h i19 ATTRIBUTE_UNUSED)
{
/* Check argument values. */
compare (values.i0, i0, __m512h);
compare (values.i1, i1, __m512h);
compare (values.i2, i2, __m512h);
compare (values.i3, i3, __m512h);
compare (values.i4, i4, __m512h);
compare (values.i5, i5, __m512h);
compare (values.i6, i6, __m512h);
compare (values.i7, i7, __m512h);
compare (values.i8, i8, __m512h);
compare (values.i9, i9, __m512h);
compare (values.i10, i10, __m512h);
compare (values.i11, i11, __m512h);
compare (values.i12, i12, __m512h);
compare (values.i13, i13, __m512h);
compare (values.i14, i14, __m512h);
compare (values.i15, i15, __m512h);
compare (values.i16, i16, __m512h);
compare (values.i17, i17, __m512h);
compare (values.i18, i18, __m512h);
compare (values.i19, i19, __m512h);
}
void
fun_check_passing_m512_20_regs (__m512 i0 ATTRIBUTE_UNUSED,
__m512 i1 ATTRIBUTE_UNUSED,
__m512 i2 ATTRIBUTE_UNUSED,
__m512 i3 ATTRIBUTE_UNUSED,
__m512 i4 ATTRIBUTE_UNUSED,
__m512 i5 ATTRIBUTE_UNUSED,
__m512 i6 ATTRIBUTE_UNUSED,
__m512 i7 ATTRIBUTE_UNUSED,
__m512 i8 ATTRIBUTE_UNUSED,
__m512 i9 ATTRIBUTE_UNUSED,
__m512 i10 ATTRIBUTE_UNUSED,
__m512 i11 ATTRIBUTE_UNUSED,
__m512 i12 ATTRIBUTE_UNUSED,
__m512 i13 ATTRIBUTE_UNUSED,
__m512 i14 ATTRIBUTE_UNUSED,
__m512 i15 ATTRIBUTE_UNUSED,
__m512 i16 ATTRIBUTE_UNUSED,
__m512 i17 ATTRIBUTE_UNUSED,
__m512 i18 ATTRIBUTE_UNUSED,
__m512 i19 ATTRIBUTE_UNUSED)
{
/* Check register contents. */
check_m512_arguments;
}
void
fun_check_passing_m512h_20_regs (__m512h i0 ATTRIBUTE_UNUSED,
__m512h i1 ATTRIBUTE_UNUSED,
__m512h i2 ATTRIBUTE_UNUSED,
__m512h i3 ATTRIBUTE_UNUSED,
__m512h i4 ATTRIBUTE_UNUSED,
__m512h i5 ATTRIBUTE_UNUSED,
__m512h i6 ATTRIBUTE_UNUSED,
__m512h i7 ATTRIBUTE_UNUSED,
__m512h i8 ATTRIBUTE_UNUSED,
__m512h i9 ATTRIBUTE_UNUSED,
__m512h i10 ATTRIBUTE_UNUSED,
__m512h i11 ATTRIBUTE_UNUSED,
__m512h i12 ATTRIBUTE_UNUSED,
__m512h i13 ATTRIBUTE_UNUSED,
__m512h i14 ATTRIBUTE_UNUSED,
__m512h i15 ATTRIBUTE_UNUSED,
__m512h i16 ATTRIBUTE_UNUSED,
__m512h i17 ATTRIBUTE_UNUSED,
__m512h i18 ATTRIBUTE_UNUSED,
__m512h i19 ATTRIBUTE_UNUSED)
{
/* Check register contents. */
check_m512_arguments;
}
#define def_check_passing8(_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7, _func1, _func2, TYPE) \
values.i0.TYPE[0] = _i0; \
values.i1.TYPE[0] = _i1; \
values.i2.TYPE[0] = _i2; \
values.i3.TYPE[0] = _i3; \
values.i4.TYPE[0] = _i4; \
values.i5.TYPE[0] = _i5; \
values.i6.TYPE[0] = _i6; \
values.i7.TYPE[0] = _i7; \
WRAP_CALL(_func1) (_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7); \
\
clear_struct_registers; \
fregs.F0.TYPE[0] = _i0; \
fregs.F1.TYPE[0] = _i1; \
fregs.F2.TYPE[0] = _i2; \
fregs.F3.TYPE[0] = _i3; \
fregs.F4.TYPE[0] = _i4; \
fregs.F5.TYPE[0] = _i5; \
fregs.F6.TYPE[0] = _i6; \
fregs.F7.TYPE[0] = _i7; \
num_fregs = 8; \
WRAP_CALL(_func2) (_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7);
#define def_check_passing20(_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7, _i8, _i9, \
_i10, _i11, _i12, _i13, _i14, _i15, _i16, _i17, \
_i18, _i19, _func1, _func2, TYPE) \
values.i0.TYPE[0] = _i0; \
values.i1.TYPE[0] = _i1; \
values.i2.TYPE[0] = _i2; \
values.i3.TYPE[0] = _i3; \
values.i4.TYPE[0] = _i4; \
values.i5.TYPE[0] = _i5; \
values.i6.TYPE[0] = _i6; \
values.i7.TYPE[0] = _i7; \
values.i8.TYPE[0] = _i8; \
values.i9.TYPE[0] = _i9; \
values.i10.TYPE[0] = _i10; \
values.i11.TYPE[0] = _i11; \
values.i12.TYPE[0] = _i12; \
values.i13.TYPE[0] = _i13; \
values.i14.TYPE[0] = _i14; \
values.i15.TYPE[0] = _i15; \
values.i16.TYPE[0] = _i16; \
values.i17.TYPE[0] = _i17; \
values.i18.TYPE[0] = _i18; \
values.i19.TYPE[0] = _i19; \
WRAP_CALL(_func1) (_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7, _i8, _i9, \
_i10, _i11, _i12, _i13, _i14, _i15, _i16, _i17, \
_i18, _i19); \
\
clear_struct_registers; \
fregs.F0.TYPE[0] = _i0; \
fregs.F1.TYPE[0] = _i1; \
fregs.F2.TYPE[0] = _i2; \
fregs.F3.TYPE[0] = _i3; \
fregs.F4.TYPE[0] = _i4; \
fregs.F5.TYPE[0] = _i5; \
fregs.F6.TYPE[0] = _i6; \
fregs.F7.TYPE[0] = _i7; \
num_fregs = 8; \
WRAP_CALL(_func2) (_i0, _i1, _i2, _i3, _i4, _i5, _i6, _i7, _i8, _i9, \
_i10, _i11, _i12, _i13, _i14, _i15, _i16, _i17, \
_i18, _i19);
void
test_m512_on_stack ()
{
__m512 x[8];
int i;
for (i = 0; i < 8; i++)
x[i] = (__m512){32 + i, 0, 0, 0, 0, 0, 0, 0};
pass = "m512-8";
def_check_passing8 (x[0], x[1], x[2], x[3], x[4], x[5], x[6], x[7],
fun_check_passing_m512_8_values,
fun_check_passing_m512_8_regs, _m512);
}
void
test_m512h_on_stack ()
{
__m512h x[8];
int i;
for (i = 0; i < 8; i++)
x[i] = (__m512h){1.1f16 + i, 2.2f16 + i, 3.3f16 + i, 4.4f16 + i,
5.5f16 + i, 6.6f16 + i, 7.7f16 + i, 8.8f16 + i,
9.9f16 + i, 10.10f16 + i, 11.11f16 + i, 12.12f16 + i,
13.13f16 + i, 14.14f16 + i, 15.15f16 + i, 16.16f16 + i,
17.17f16 + i, 18.18f16 + i, 19.19f16 + i, 20.20f16 + i,
21.21f16 + i, 22.22f16 + i, 23.23f16 + i, 24.24f16 + i,
25.25f16 + i, 26.26f16 + i, 27.27f16 + i, 28.28f16 + i,
29.29f16 + i, 30.30f16 + i, 31.31f16 + i, 32.32f16 + i};
pass = "m512h-8";
def_check_passing8 (x[0], x[1], x[2], x[3], x[4], x[5], x[6], x[7],
fun_check_passing_m512h_8_values,
fun_check_passing_m512h_8_regs, _m512h);
}
void
test_too_many_m512 ()
{
__m512 x[20];
int i;
for (i = 0; i < 20; i++)
x[i] = (__m512){32 + i, 0, 0, 0, 0, 0, 0, 0};
pass = "m512-20";
def_check_passing20 (x[0], x[1], x[2], x[3], x[4], x[5], x[6], x[7], x[8],
x[9], x[10], x[11], x[12], x[13], x[14], x[15], x[16],
x[17], x[18], x[19], fun_check_passing_m512_20_values,
fun_check_passing_m512_20_regs, _m512);
}
void
test_too_many_m512h ()
{
__m512h x[20];
int i;
for (i = 0; i < 20; i++)
x[i] = (__m512h){ 1.1f16 + i, 2.2f16 + i, 3.3f16 + i, 4.4f16 + i,
5.5f16 + i, 6.6f16 + i, 7.7f16 + i, 8.8f16 + i,
9.9f16 + i, 10.10f16 + i, 11.11f16 + i, 12.12f16 + i,
13.13f16 + i, 14.14f16 + i, 15.15f16 + i, 16.16f16 + i,
17.17f16 + i, 18.18f16 + i, 19.19f16 + i, 20.20f16 + i,
21.21f16 + i, 22.22f16 + i, 23.23f16 + i, 24.24f16 + i,
25.25f16 + i, 26.26f16 + i, 27.27f16 + i, 28.28f16 + i,
29.29f16 + i, 30.30f16 + i, 31.31f16 + i, 32.32f16 + i};
pass = "m512h-20";
def_check_passing20 (x[0], x[1], x[2], x[3], x[4], x[5], x[6], x[7], x[8],
x[9], x[10], x[11], x[12], x[13], x[14], x[15], x[16],
x[17], x[18], x[19], fun_check_passing_m512h_20_values,
fun_check_passing_m512h_20_regs, _m512h);
}
static void
do_test (void)
{
test_m512_on_stack ();
test_too_many_m512 ();
test_m512h_on_stack ();
test_too_many_m512h ();
if (failed)
abort ();
}
|
