1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
|
#include "avx512f-check.h"
#include "args.h"
struct IntegerRegisters iregs;
struct FloatRegisters fregs;
unsigned int num_iregs, num_fregs;
struct m512_struct
{
__m512 x;
};
struct m512_2_struct
{
__m512 x1, x2;
};
/* Check that the struct is passed as the individual members in fregs. */
void
check_struct_passing1 (struct m512_struct ms1 ATTRIBUTE_UNUSED,
struct m512_struct ms2 ATTRIBUTE_UNUSED,
struct m512_struct ms3 ATTRIBUTE_UNUSED,
struct m512_struct ms4 ATTRIBUTE_UNUSED,
struct m512_struct ms5 ATTRIBUTE_UNUSED,
struct m512_struct ms6 ATTRIBUTE_UNUSED,
struct m512_struct ms7 ATTRIBUTE_UNUSED,
struct m512_struct ms8 ATTRIBUTE_UNUSED)
{
/* Check register contents. */
check_m512_arguments;
}
void
check_struct_passing2 (struct m512_2_struct ms ATTRIBUTE_UNUSED)
{
/* Check the passing on the stack by comparing the address of the
stack elements to the expected place on the stack. */
assert ((unsigned long)&ms.x1 == rsp+8);
assert ((unsigned long)&ms.x2 == rsp+72);
}
static void
avx512f_test (void)
{
struct m512_struct m512s [8];
struct m512_2_struct m512_2s = {
{ 48.394, 39.3, -397.9, 3484.9, -8.394, -93.3, 7.9, 84.94,
48.3941, 39.31, -397.91, 3484.91, -8.3941, -93.31, 7.91, 84.941 },
{ -8.394, -3.3, -39.9, 34.9, 7.9, 84.94, -48.394, 39.3,
-8.3942, -3.32, -39.92, 34.92, 7.92, 84.942, -48.3942, 39.32 }
};
int i;
for (i = 0; i < 8; i++)
m512s[i].x = (__m512){32+i, 0, i, 0, -i, 0, i - 12, i + 8,
32+i, 0, i, 0, -i, 0, i - 12, i + 8};
clear_struct_registers;
for (i = 0; i < 8; i++)
(&fregs.zmm0)[i]._m512[0] = m512s[i].x;
num_fregs = 8;
WRAP_CALL (check_struct_passing1)(m512s[0], m512s[1], m512s[2], m512s[3],
m512s[4], m512s[5], m512s[6], m512s[7]);
WRAP_CALL (check_struct_passing2)(m512_2s);
}
|
