2022-08-05 15:15:17 +00:00
|
|
|
#include <metal_stdlib>
|
|
|
|
|
|
|
|
using namespace metal;
|
2023-03-06 18:25:08 +00:00
|
|
|
|
|
|
|
template<typename T, size_t N>
|
|
|
|
struct tint_array {
|
|
|
|
const constant T& operator[](size_t i) const constant { return elements[i]; }
|
|
|
|
device T& operator[](size_t i) device { return elements[i]; }
|
|
|
|
const device T& operator[](size_t i) const device { return elements[i]; }
|
|
|
|
thread T& operator[](size_t i) thread { return elements[i]; }
|
|
|
|
const thread T& operator[](size_t i) const thread { return elements[i]; }
|
|
|
|
threadgroup T& operator[](size_t i) threadgroup { return elements[i]; }
|
|
|
|
const threadgroup T& operator[](size_t i) const threadgroup { return elements[i]; }
|
|
|
|
T elements[N];
|
|
|
|
};
|
|
|
|
|
|
|
|
struct tint_packed_vec3_f16_array_element {
|
|
|
|
/* 0x0000 */ packed_half3 elements;
|
|
|
|
/* 0x0006 */ tint_array<int8_t, 2> tint_pad;
|
|
|
|
};
|
|
|
|
|
|
|
|
void assign_and_preserve_padding(device tint_array<tint_packed_vec3_f16_array_element, 2>* const dest, half2x3 value) {
|
|
|
|
(*(dest))[0u].elements = packed_half3(value[0u]);
|
|
|
|
(*(dest))[1u].elements = packed_half3(value[1u]);
|
|
|
|
}
|
|
|
|
|
|
|
|
void transpose_b9ad1f(device tint_array<tint_packed_vec3_f16_array_element, 2>* const tint_symbol_1) {
|
2022-11-10 00:32:12 +00:00
|
|
|
half3x2 arg_0 = half3x2(half2(1.0h), half2(1.0h), half2(1.0h));
|
2022-08-05 15:15:17 +00:00
|
|
|
half2x3 res = transpose(arg_0);
|
2023-03-06 18:25:08 +00:00
|
|
|
assign_and_preserve_padding(tint_symbol_1, res);
|
2022-08-05 15:15:17 +00:00
|
|
|
}
|
|
|
|
|
|
|
|
struct tint_symbol {
|
|
|
|
float4 value [[position]];
|
|
|
|
};
|
|
|
|
|
2023-03-06 18:25:08 +00:00
|
|
|
float4 vertex_main_inner(device tint_array<tint_packed_vec3_f16_array_element, 2>* const tint_symbol_2) {
|
|
|
|
transpose_b9ad1f(tint_symbol_2);
|
2022-08-05 15:15:17 +00:00
|
|
|
return float4(0.0f);
|
|
|
|
}
|
|
|
|
|
2023-03-06 18:25:08 +00:00
|
|
|
vertex tint_symbol vertex_main(device tint_array<tint_packed_vec3_f16_array_element, 2>* tint_symbol_3 [[buffer(0)]]) {
|
|
|
|
float4 const inner_result = vertex_main_inner(tint_symbol_3);
|
2022-08-05 15:15:17 +00:00
|
|
|
tint_symbol wrapper_result = {};
|
|
|
|
wrapper_result.value = inner_result;
|
|
|
|
return wrapper_result;
|
|
|
|
}
|
|
|
|
|
2023-03-06 18:25:08 +00:00
|
|
|
fragment void fragment_main(device tint_array<tint_packed_vec3_f16_array_element, 2>* tint_symbol_4 [[buffer(0)]]) {
|
|
|
|
transpose_b9ad1f(tint_symbol_4);
|
2022-08-05 15:15:17 +00:00
|
|
|
return;
|
|
|
|
}
|
|
|
|
|
2023-03-06 18:25:08 +00:00
|
|
|
kernel void compute_main(device tint_array<tint_packed_vec3_f16_array_element, 2>* tint_symbol_5 [[buffer(0)]]) {
|
|
|
|
transpose_b9ad1f(tint_symbol_5);
|
2022-08-05 15:15:17 +00:00
|
|
|
return;
|
|
|
|
}
|
|
|
|
|