James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 1 | #include <metal_stdlib> |
| 2 | using namespace metal; |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 3 | |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 4 | struct tint_module_vars_struct { |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 5 | device int* prevent_dce; |
| 6 | }; |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 7 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 8 | struct VertexOutput { |
| 9 | float4 pos; |
| 10 | int prevent_dce; |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 11 | }; |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 12 | |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 13 | struct vertex_main_outputs { |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 14 | float4 VertexOutput_pos [[position]]; |
| 15 | int VertexOutput_prevent_dce [[user(locn0)]] [[flat]]; |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 16 | }; |
dan sinclair | f1f381a | 2023-11-22 09:44:15 +0000 | [diff] [blame] | 17 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 18 | int transpose_b9ad1f() { |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 19 | half3x2 arg_0 = half3x2(half2(1.0h), half2(1.0h), half2(1.0h)); |
| 20 | half2x3 res = transpose(arg_0); |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 21 | return select(0, 1, (res[0][0] == 0.0h)); |
dan sinclair | f1f381a | 2023-11-22 09:44:15 +0000 | [diff] [blame] | 22 | } |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 23 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 24 | fragment void fragment_main(device int* prevent_dce [[buffer(0)]]) { |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 25 | tint_module_vars_struct const tint_module_vars = tint_module_vars_struct{.prevent_dce=prevent_dce}; |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 26 | (*tint_module_vars.prevent_dce) = transpose_b9ad1f(); |
dan sinclair | f1f381a | 2023-11-22 09:44:15 +0000 | [diff] [blame] | 27 | } |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 28 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 29 | kernel void compute_main(device int* prevent_dce [[buffer(0)]]) { |
James Price | 085093d | 2024-06-06 02:09:47 +0000 | [diff] [blame] | 30 | tint_module_vars_struct const tint_module_vars = tint_module_vars_struct{.prevent_dce=prevent_dce}; |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 31 | (*tint_module_vars.prevent_dce) = transpose_b9ad1f(); |
James Price | a30f8dd | 2024-05-10 14:31:43 +0000 | [diff] [blame] | 32 | } |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 33 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 34 | VertexOutput vertex_main_inner() { |
| 35 | VertexOutput out = {}; |
| 36 | out.pos = float4(0.0f); |
| 37 | out.prevent_dce = transpose_b9ad1f(); |
| 38 | return out; |
| 39 | } |
James Price | 48be7e8 | 2024-06-19 22:38:07 +0000 | [diff] [blame] | 40 | |
James Price | 2cc6b3c | 2024-06-13 20:31:41 +0000 | [diff] [blame] | 41 | vertex vertex_main_outputs vertex_main() { |
| 42 | VertexOutput const v = vertex_main_inner(); |
| 43 | return vertex_main_outputs{.VertexOutput_pos=v.pos, .VertexOutput_prevent_dce=v.prevent_dce}; |
dan sinclair | f1f381a | 2023-11-22 09:44:15 +0000 | [diff] [blame] | 44 | } |