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
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
|
/* { dg-do compile } */
/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */
#include "riscv_vector.h"
size_t __attribute__ ((noinline))
sumation (size_t sum0, size_t sum1, size_t sum2, size_t sum3, size_t sum4,
size_t sum5, size_t sum6, size_t sum7, size_t sum8, size_t sum9,
size_t sum10, size_t sum11, size_t sum12, size_t sum13, size_t sum14,
size_t sum15)
{
return sum0 + sum1 + sum2 + sum3 + sum4 + sum5 + sum6 + sum7 + sum8 + sum9
+ sum10 + sum11 + sum12 + sum13 + sum14 + sum15;
}
size_t
foo (char const *buf, size_t len)
{
size_t sum = 0;
size_t vl = __riscv_vsetvlmax_e8m8 ();
size_t step = vl * 4;
const char *it = buf, *end = buf + len;
for (; it + step <= end;)
{
vuint8m1_t v0 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v1 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v2 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v3 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v4 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v5 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v6 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v7 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v8 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v9 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v10 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v11 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v12 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v13 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v14 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
vuint8m1_t v15 = __riscv_vle8_v_u8m1 ((void *) it, vl);
it += vl;
asm volatile("nop" ::: "memory");
vint16m2_t vw0 = __riscv_vluxei8_v_i16m2 ((void *) it, v0, vl);
vint16m2_t vw1 = __riscv_vluxei8_v_i16m2 ((void *) it, v1, vl);
vint16m2_t vw2 = __riscv_vluxei8_v_i16m2 ((void *) it, v2, vl);
vint16m2_t vw3 = __riscv_vluxei8_v_i16m2 ((void *) it, v3, vl);
vint16m2_t vw4 = __riscv_vluxei8_v_i16m2 ((void *) it, v4, vl);
vint16m2_t vw5 = __riscv_vluxei8_v_i16m2 ((void *) it, v5, vl);
vint16m2_t vw6 = __riscv_vluxei8_v_i16m2 ((void *) it, v6, vl);
vint16m2_t vw7 = __riscv_vluxei8_v_i16m2 ((void *) it, v7, vl);
vint16m2_t vw8 = __riscv_vluxei8_v_i16m2 ((void *) it, v8, vl);
vint16m2_t vw9 = __riscv_vluxei8_v_i16m2 ((void *) it, v9, vl);
vint16m2_t vw10 = __riscv_vluxei8_v_i16m2 ((void *) it, v10, vl);
vint16m2_t vw11 = __riscv_vluxei8_v_i16m2 ((void *) it, v11, vl);
vint16m2_t vw12 = __riscv_vluxei8_v_i16m2 ((void *) it, v12, vl);
vint16m2_t vw13 = __riscv_vluxei8_v_i16m2 ((void *) it, v13, vl);
vint16m2_t vw14 = __riscv_vluxei8_v_i16m2 ((void *) it, v14, vl);
vbool8_t mask = *(vbool8_t*)it;
vint16m2_t vw15 = __riscv_vluxei8_v_i16m2_m (mask, (void *) it, v15, vl);
asm volatile("nop" ::: "memory");
size_t sum0 = __riscv_vmv_x_s_i16m2_i16 (vw0);
size_t sum1 = __riscv_vmv_x_s_i16m2_i16 (vw1);
size_t sum2 = __riscv_vmv_x_s_i16m2_i16 (vw2);
size_t sum3 = __riscv_vmv_x_s_i16m2_i16 (vw3);
size_t sum4 = __riscv_vmv_x_s_i16m2_i16 (vw4);
size_t sum5 = __riscv_vmv_x_s_i16m2_i16 (vw5);
size_t sum6 = __riscv_vmv_x_s_i16m2_i16 (vw6);
size_t sum7 = __riscv_vmv_x_s_i16m2_i16 (vw7);
size_t sum8 = __riscv_vmv_x_s_i16m2_i16 (vw8);
size_t sum9 = __riscv_vmv_x_s_i16m2_i16 (vw9);
size_t sum10 = __riscv_vmv_x_s_i16m2_i16 (vw10);
size_t sum11 = __riscv_vmv_x_s_i16m2_i16 (vw11);
size_t sum12 = __riscv_vmv_x_s_i16m2_i16 (vw12);
size_t sum13 = __riscv_vmv_x_s_i16m2_i16 (vw13);
size_t sum14 = __riscv_vmv_x_s_i16m2_i16 (vw14);
size_t sum15 = __riscv_vmv_x_s_i16m2_i16 (vw15);
sum += sumation (sum0, sum1, sum2, sum3, sum4, sum5, sum6, sum7, sum8,
sum9, sum10, sum11, sum12, sum13, sum14, sum15);
}
return sum;
}
/* { dg-final { scan-assembler-not {vluxei8\.v\tv0,\s*\([a-x0-9]+\),\s*v[0-9]+,\s*v0.t} { xfail riscv*-*-* } } } */
|
