Skip to content

Commit 57f6bdd

Browse files
committed
Format C
1 parent 88440f2 commit 57f6bdd

2 files changed

Lines changed: 384 additions & 386 deletions

File tree

backends/gpu/kompjuta/includes/kore3/kompjuta/riscv_vector_util.h

Lines changed: 47 additions & 47 deletions
Original file line numberDiff line numberDiff line change
@@ -8,17 +8,17 @@ extern "C" {
88
#endif
99

1010
typedef struct {
11-
_Alignas(128) float lane[32];
11+
_Alignas(128) float lane[32];
1212
} kore_float_x32;
1313

1414
static inline vfloat32m1_t kore_float_x32_load(const kore_float_x32 *p) {
15-
size_t _vector_length = __riscv_vsetvl_e32m1(32);
16-
return __riscv_vle32_v_f32m1(p->lane, _vector_length);
15+
size_t _vector_length = __riscv_vsetvl_e32m1(32);
16+
return __riscv_vle32_v_f32m1(p->lane, _vector_length);
1717
}
1818

1919
static inline void vec32f_store(kore_float_x32 *p, vfloat32m1_t v) {
20-
size_t _vector_length = __riscv_vsetvl_e32m1(32);
21-
__riscv_vse32_v_f32m1(p->lane, v, _vector_length);
20+
size_t _vector_length = __riscv_vsetvl_e32m1(32);
21+
__riscv_vse32_v_f32m1(p->lane, v, _vector_length);
2222
}
2323

2424
typedef struct kore_float2_x32 {
@@ -40,39 +40,39 @@ typedef struct kore_float4_x32 {
4040
} kore_float4_x32;
4141

4242
/*typedef struct kore_int2x4 {
43-
kore_int32x4 x;
44-
kore_int32x4 y;
43+
kore_int32x4 x;
44+
kore_int32x4 y;
4545
} kore_int2x4;
4646
4747
typedef struct kore_int3x4 {
48-
kore_int32x4 x;
49-
kore_int32x4 y;
50-
kore_int32x4 z;
48+
kore_int32x4 x;
49+
kore_int32x4 y;
50+
kore_int32x4 z;
5151
} kore_int3x4;
5252
5353
typedef struct kore_int4x4 {
54-
kore_int32x4 x;
55-
kore_int32x4 y;
56-
kore_int32x4 z;
57-
kore_int32x4 w;
54+
kore_int32x4 x;
55+
kore_int32x4 y;
56+
kore_int32x4 z;
57+
kore_int32x4 w;
5858
} kore_int4x4;
5959
6060
typedef struct kore_uint2x4 {
61-
kore_uint32x4 x;
62-
kore_uint32x4 y;
61+
kore_uint32x4 x;
62+
kore_uint32x4 y;
6363
} kore_uint2x4;
6464
6565
typedef struct kore_uint3x4 {
66-
kore_uint32x4 x;
67-
kore_uint32x4 y;
68-
kore_uint32x4 z;
66+
kore_uint32x4 x;
67+
kore_uint32x4 y;
68+
kore_uint32x4 z;
6969
} kore_uint3x4;
7070
7171
typedef struct kore_uint4x4 {
72-
kore_uint32x4 x;
73-
kore_uint32x4 y;
74-
kore_uint32x4 z;
75-
kore_uint32x4 w;
72+
kore_uint32x4 x;
73+
kore_uint32x4 y;
74+
kore_uint32x4 z;
75+
kore_uint32x4 w;
7676
} kore_uint4x4;*/
7777

7878
kore_float4 kore_riscv_create_float4(float value0, float value1, float value2, float value3);
@@ -81,11 +81,11 @@ kore_float_x32 kore_riscv_sin_f1_x32(kore_float_x32 value);
8181

8282
kore_float_x32 kore_riscv_length_f2_x32(kore_float2_x32 value);
8383

84-
//kore_int2x4 kore_riscv_int2_u2_x4(kore_uint2x4 value);
84+
// kore_int2x4 kore_riscv_int2_u2_x4(kore_uint2x4 value);
8585

86-
//kore_float2x32 kore_riscv_create_float2_i2_x4(kore_int2x4 value);
86+
// kore_float2x32 kore_riscv_create_float2_i2_x4(kore_int2x4 value);
8787

88-
//kore_float32x32 kore_riscv_create_float_u1_x4(kore_uint32x4 value);
88+
// kore_float32x32 kore_riscv_create_float_u1_x4(kore_uint32x4 value);
8989

9090
static inline kore_float4_x32 kore_riscv_create_float4_f1_f1_f1_f1_x32(vfloat32m1_t value0, vfloat32m1_t value1, vfloat32m1_t value2, vfloat32m1_t value3) {
9191
kore_float4_x32 value;
@@ -96,69 +96,69 @@ static inline kore_float4_x32 kore_riscv_create_float4_f1_f1_f1_f1_x32(vfloat32m
9696
return value;
9797
}
9898

99-
//kore_int2x4 kore_riscv_sub_i2_i1_x4(kore_int2x4 value0, kore_int32x4 value1);
99+
// kore_int2x4 kore_riscv_sub_i2_i1_x4(kore_int2x4 value0, kore_int32x4 value1);
100100

101101
kore_float2_x32 kore_riscv_div_f2_f1_x32(kore_float2_x32 value0, kore_float_x32 value1);
102102

103-
//kore_uint32x4 kore_riscv_add_u1_u1_x4(kore_uint32x4 value0, kore_uint32x4 value1);
103+
// kore_uint32x4 kore_riscv_add_u1_u1_x4(kore_uint32x4 value0, kore_uint32x4 value1);
104104

105105
kore_float_x32 kore_riscv_mult_f1_f1_x32(kore_float_x32 value0, kore_float_x32 value1);
106106

107107
kore_float_x32 kore_riscv_add_f1_f1_x32(kore_float_x32 value0, kore_float_x32 value1);
108108

109109
kore_float_x32 kore_riscv_sub_f1_f1_x32(kore_float_x32 value0, kore_float_x32 value1);
110110

111-
//kore_int32x4 kore_riscv_mult_u1_i1_x4(kore_uint32x4 value0, kore_int32x4 value1);
111+
// kore_int32x4 kore_riscv_mult_u1_i1_x4(kore_uint32x4 value0, kore_int32x4 value1);
112112

113-
//kore_int32x4 kore_riscv_add_u1_i1_x4(kore_uint32x4 value0, kore_int32x4 value1);
113+
// kore_int32x4 kore_riscv_add_u1_i1_x4(kore_uint32x4 value0, kore_int32x4 value1);
114114

115-
//kore_uint2x4 kore_riscv_swizzle_xy_u3_x4(kore_uint3x4 value);
115+
// kore_uint2x4 kore_riscv_swizzle_xy_u3_x4(kore_uint3x4 value);
116116

117-
//kore_uint32x4 kore_riscv_swizzle_x_u2_x4(kore_uint2x4 value);
117+
// kore_uint32x4 kore_riscv_swizzle_x_u2_x4(kore_uint2x4 value);
118118

119-
//kore_uint32x4 kore_riscv_swizzle_y_u2_x4(kore_uint2x4 value);
119+
// kore_uint32x4 kore_riscv_swizzle_y_u2_x4(kore_uint2x4 value);
120120

121-
//kore_uint32x4 kore_riscv_swizzle_x_u3_x4(kore_uint3x4 value);
121+
// kore_uint32x4 kore_riscv_swizzle_x_u3_x4(kore_uint3x4 value);
122122

123-
//kore_uint32x4 kore_riscv_swizzle_y_u3_x4(kore_uint3x4 value);
123+
// kore_uint32x4 kore_riscv_swizzle_y_u3_x4(kore_uint3x4 value);
124124

125125
float kore_riscv_sin_f1_x1(float value);
126126

127127
float kore_riscv_length_f2_x1(kore_float2 value);
128128

129-
//kore_int2 kore_riscv_int2_u2_x1(kore_uint2 value);
129+
// kore_int2 kore_riscv_int2_u2_x1(kore_uint2 value);
130130

131-
//kore_float2 kore_riscv_create_float2_i2_x1(kore_int2 value);
131+
// kore_float2 kore_riscv_create_float2_i2_x1(kore_int2 value);
132132

133-
//float kore_riscv_create_float_u1_x1(uint32_t value);
133+
// float kore_riscv_create_float_u1_x1(uint32_t value);
134134

135135
kore_float4 kore_riscv_create_float4_f1_f1_f1_f1_x1(float value0, float value1, float value2, float value3);
136136

137-
//kore_int2 kore_riscv_sub_i2_i1_x1(kore_int2 value0, int value1);
137+
// kore_int2 kore_riscv_sub_i2_i1_x1(kore_int2 value0, int value1);
138138

139139
kore_float2 kore_riscv_div_f2_f1_x1(kore_float2 value0, float value1);
140140

141-
//uint32_t kore_riscv_add_u1_u1_x1(uint32_t value0, uint32_t value1);
141+
// uint32_t kore_riscv_add_u1_u1_x1(uint32_t value0, uint32_t value1);
142142

143143
float kore_riscv_mult_f1_f1_x1(float value0, float value1);
144144

145145
float kore_riscv_add_f1_f1_x1(float value0, float value1);
146146

147147
float kore_riscv_sub_f1_f1_x1(float value0, float value1);
148148

149-
//int kore_riscv_mult_u1_i1_x1(uint32_t value0, int value1);
149+
// int kore_riscv_mult_u1_i1_x1(uint32_t value0, int value1);
150150

151-
//int kore_riscv_add_u1_i1_x1(uint32_t value0, int value1);
151+
// int kore_riscv_add_u1_i1_x1(uint32_t value0, int value1);
152152

153-
//kore_uint2 kore_riscv_swizzle_xy_u3_x1(kore_uint3 value);
153+
// kore_uint2 kore_riscv_swizzle_xy_u3_x1(kore_uint3 value);
154154

155-
//uint32_t kore_riscv_swizzle_x_u2_x1(kore_uint2 value);
155+
// uint32_t kore_riscv_swizzle_x_u2_x1(kore_uint2 value);
156156

157-
//uint32_t kore_riscv_swizzle_y_u2_x1(kore_uint2 value);
157+
// uint32_t kore_riscv_swizzle_y_u2_x1(kore_uint2 value);
158158

159-
//uint32_t kore_riscv_swizzle_x_u3_x1(kore_uint3 value);
159+
// uint32_t kore_riscv_swizzle_x_u3_x1(kore_uint3 value);
160160

161-
//uint32_t kore_riscv_swizzle_y_u3_x1(kore_uint3 value);
161+
// uint32_t kore_riscv_swizzle_y_u3_x1(kore_uint3 value);
162162

163163
#ifdef __cplusplus
164164
}

0 commit comments

Comments
 (0)