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
66
67
68
69
70
71
72
73
|
/* { dg-do compile { target { aarch64*-*-* } } } */
/* { dg-additional-options "-O3 -march=armv8.2-a+dotprod" } */
#include <arm_neon.h>
/* Unsigned Dot Product instructions. */
uint32x2_t ufoo (uint32x2_t r, uint8x8_t x, uint8x8_t y)
{
return vdot_u32 (r, x, y);
}
uint32x4_t ufooq (uint32x4_t r, uint8x16_t x, uint8x16_t y)
{
return vdotq_u32 (r, x, y);
}
uint32x2_t ufoo_lane (uint32x2_t r, uint8x8_t x, uint8x8_t y)
{
return vdot_lane_u32 (r, x, y, 0);
}
uint32x2_t ufoo_laneq (uint32x2_t r, uint8x8_t x, uint8x16_t y)
{
return vdot_laneq_u32 (r, x, y, 0);
}
uint32x4_t ufooq_lane (uint32x4_t r, uint8x16_t x, uint8x8_t y)
{
return vdotq_lane_u32 (r, x, y, 0);
}
uint32x4_t ufooq_laneq (uint32x4_t r, uint8x16_t x, uint8x16_t y)
{
return vdotq_laneq_u32 (r, x, y, 0);
}
/* Signed Dot Product instructions. */
int32x2_t sfoo (int32x2_t r, int8x8_t x, int8x8_t y)
{
return vdot_s32 (r, x, y);
}
int32x4_t sfooq (int32x4_t r, int8x16_t x, int8x16_t y)
{
return vdotq_s32 (r, x, y);
}
int32x2_t sfoo_lane (int32x2_t r, int8x8_t x, int8x8_t y)
{
return vdot_lane_s32 (r, x, y, 0);
}
int32x2_t sfoo_laneq (int32x2_t r, int8x8_t x, int8x16_t y)
{
return vdot_laneq_s32 (r, x, y, 0);
}
int32x4_t sfooq_lane (int32x4_t r, int8x16_t x, int8x8_t y)
{
return vdotq_lane_s32 (r, x, y, 0);
}
int32x4_t sfooq_laneq (int32x4_t r, int8x16_t x, int8x16_t y)
{
return vdotq_laneq_s32 (r, x, y, 0);
}
/* { dg-final { scan-assembler-times {[us]dot\tv[0-9]+\.2s, v[0-9]+\.8b, v[0-9]+\.8b} 2 } } */
/* { dg-final { scan-assembler-times {[us]dot\tv[0-9]+\.2s, v[0-9]+\.8b, v[0-9]+\.4b\[[0-9]+\]} 4 } } */
/* { dg-final { scan-assembler-times {[us]dot\tv[0-9]+\.4s, v[0-9]+\.16b, v[0-9]+\.16b} 2 } } */
/* { dg-final { scan-assembler-times {[us]dot\tv[0-9]+\.4s, v[0-9]+\.16b, v[0-9]+\.4b\[[0-9]+\]} 4 } } */
|
