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
|
/* { dg-do compile } */
/* { dg-options "-march=rv64gcv -mabi=lp64d -O3" } */
#include "riscv_vector.h"
double __attribute__ ((noinline))
sumation (double sum0, double sum1, double sum2, double sum3)
{
return sum0 + sum1 + sum2 + sum3;
}
double
foo (char const *buf, size_t len)
{
double sum = 0;
size_t vl = __riscv_vsetvlmax_e8m8 ();
size_t step = vl * 4;
const char *it = buf, *end = buf + len;
for (; it + step <= end;)
{
vfloat32m1_t v0 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v1 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v2 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v3 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
asm volatile("nop" ::: "memory");
vint64m2_t vw0 = __riscv_vfwcvt_rtz_x_f_v_i64m2 (v0, vl);
vint64m2_t vw1 = __riscv_vfwcvt_rtz_x_f_v_i64m2 (v1, vl);
vint64m2_t vw2 = __riscv_vfwcvt_rtz_x_f_v_i64m2 (v2, vl);
vint64m2_t vw3 = __riscv_vfwcvt_rtz_x_f_v_i64m2 (v3, vl);
asm volatile("nop" ::: "memory");
double sum0 = __riscv_vmv_x_s_i64m2_i64 (vw0);
double sum1 = __riscv_vmv_x_s_i64m2_i64 (vw1);
double sum2 = __riscv_vmv_x_s_i64m2_i64 (vw2);
double sum3 = __riscv_vmv_x_s_i64m2_i64 (vw3);
sum += sumation (sum0, sum1, sum2, sum3);
}
return sum;
}
double
foo2 (char const *buf, size_t len)
{
double sum = 0;
size_t vl = __riscv_vsetvlmax_e8m8 ();
size_t step = vl * 4;
const char *it = buf, *end = buf + len;
for (; it + step <= end;)
{
vfloat32m1_t v0 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v1 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v2 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
vfloat32m1_t v3 = __riscv_vle32_v_f32m1 ((void *) it, vl);
it += vl;
asm volatile("nop" ::: "memory");
vint64m2_t vw0 = __riscv_vfwcvt_x_f_v_i64m2 (v0, vl);
vint64m2_t vw1 = __riscv_vfwcvt_x_f_v_i64m2 (v1, vl);
vint64m2_t vw2 = __riscv_vfwcvt_x_f_v_i64m2 (v2, vl);
vint64m2_t vw3 = __riscv_vfwcvt_x_f_v_i64m2 (v3, vl);
asm volatile("nop" ::: "memory");
double sum0 = __riscv_vmv_x_s_i64m2_i64 (vw0);
double sum1 = __riscv_vmv_x_s_i64m2_i64 (vw1);
double sum2 = __riscv_vmv_x_s_i64m2_i64 (vw2);
double sum3 = __riscv_vmv_x_s_i64m2_i64 (vw3);
sum += sumation (sum0, sum1, sum2, sum3);
}
return sum;
}
/* { dg-final { scan-assembler-not {vmv1r} } } */
/* { dg-final { scan-assembler-not {vmv2r} } } */
/* { dg-final { scan-assembler-not {vmv4r} } } */
/* { dg-final { scan-assembler-not {vmv8r} } } */
/* { dg-final { scan-assembler-not {csrr} } } */
|
