| SKIP: FAILED |
| |
| <dawn>/src/tint/lang/msl/writer/printer/printer.cc:355 internal compiler error: RenderParams = struct @align(16) { |
| modelViewProjectionMatrix:mat4x4<f32> @offset(0) |
| right:vec3<f32> @offset(64) |
| up:vec3<f32> @offset(80) |
| } |
| |
| VertexOutput = struct @align(16) { |
| position:vec4<f32> @offset(0), @builtin(position) |
| color:vec4<f32> @offset(16), @location(0) |
| quad_pos:vec2<f32> @offset(32), @location(1) |
| } |
| |
| VertexInput = struct @align(16) { |
| position:vec3<f32> @offset(0), @location(0) |
| color:vec4<f32> @offset(16), @location(1) |
| quad_pos:vec2<f32> @offset(32), @location(2) |
| } |
| |
| SimulationParams = struct @align(16) { |
| deltaTime:f32 @offset(0) |
| seed:vec4<f32> @offset(16) |
| } |
| |
| Particle = struct @align(16) { |
| position:vec3<f32> @offset(0) |
| lifetime:f32 @offset(12) |
| color:vec4<f32> @offset(16) |
| velocity:vec2<f32> @offset(32) |
| } |
| |
| Particles = struct @align(16) { |
| particles:array<Particle> @offset(0) |
| } |
| |
| UBO = struct @align(4) { |
| width:u32 @offset(0) |
| } |
| |
| Buffer = struct @align(4) { |
| weights:array<f32> @offset(0) |
| } |
| |
| %b1 = block { # root |
| %rand_seed:ptr<private, vec2<f32>, read_write> = var |
| %render_params:ptr<uniform, RenderParams, read> = var @binding_point(0, 5) |
| %sim_params:ptr<uniform, SimulationParams, read> = var @binding_point(0, 0) |
| %data:ptr<storage, Particles, read_write> = var @binding_point(0, 1) |
| %tint_symbol:ptr<handle, texture_1d<f32>, read> = var @binding_point(0, 2) |
| %ubo:ptr<uniform, UBO, read> = var @binding_point(0, 3) |
| %buf_in:ptr<storage, Buffer, read> = var @binding_point(0, 4) |
| %buf_out:ptr<storage, Buffer, read_write> = var @binding_point(0, 5) |
| %tex_in:ptr<handle, texture_2d<f32>, read> = var @binding_point(0, 6) |
| %tex_out:ptr<handle, texture_storage_2d<rgba8unorm, write>, read> = var @binding_point(0, 7) |
| } |
| |
| %asinh_468a48 = func():void -> %b2 { |
| %b2 = block { |
| %arg_0:ptr<function, f16, read_write> = var, 0.0h |
| %13:f16 = load %arg_0 |
| %14:f16 = asinh %13 |
| %res:ptr<function, f16, read_write> = var, %14 |
| ret |
| } |
| } |
| %vertex_main = @vertex func():vec4<f32> [@position] -> %b3 { |
| %b3 = block { |
| %17:void = call %asinh_468a48 |
| ret vec4<f32>(0.0f) |
| } |
| } |
| %fragment_main = @fragment func():void -> %b4 { |
| %b4 = block { |
| %19:void = call %asinh_468a48 |
| ret |
| } |
| } |
| %rgba32uintin = @compute @workgroup_size(1, 1, 1) func():void -> %b5 { |
| %b5 = block { |
| %21:void = call %asinh_468a48 |
| ret |
| } |
| } |
| %vs_main = @vertex func(%in:VertexInput):VertexOutput -> %b6 { |
| %b6 = block { |
| %24:ptr<uniform, vec3<f32>, read> = access %render_params, 1u |
| %25:vec3<f32> = load %24 |
| %26:ptr<uniform, vec3<f32>, read> = access %render_params, 2u |
| %27:vec3<f32> = load %26 |
| %28:mat2x3<f32> = construct %25, %27 |
| %29:vec2<f32> = access %in, 2u |
| %30:vec3<f32> = mul %28, %29 |
| %quad_pos:ptr<function, vec3<f32>, read_write> = var, %30 |
| %32:vec3<f32> = access %in, 0u |
| %33:vec3<f32> = load %quad_pos |
| %34:vec3<f32> = add %33, 0.00999999977648258209f |
| %35:vec3<f32> = sub %32, %34 |
| %position:ptr<function, vec3<f32>, read_write> = var, %35 |
| %out:ptr<function, VertexOutput, read_write> = var |
| %38:ptr<function, vec4<f32>, read_write> = access %out, 0u |
| %39:ptr<uniform, mat4x4<f32>, read> = access %render_params, 0u |
| %40:mat4x4<f32> = load %39 |
| %41:vec3<f32> = load %position |
| %42:vec4<f32> = construct %41, 1.0f |
| %43:vec4<f32> = mul %40, %42 |
| store %38, %43 |
| %44:ptr<function, vec4<f32>, read_write> = access %out, 1u |
| %45:vec4<f32> = access %in, 1u |
| store %44, %45 |
| %46:ptr<function, vec2<f32>, read_write> = access %out, 2u |
| %47:vec2<f32> = access %in, 2u |
| store %46, %47 |
| %48:VertexOutput = load %out |
| ret %48 |
| } |
| } |
| %simulate = @compute @workgroup_size(64, 1, 1) func(%GlobalInvocationID:vec3<u32> [@global_invocation_id]):void -> %b7 { |
| %b7 = block { |
| %51:ptr<uniform, vec4<f32>, read> = access %sim_params, 1u |
| %52:vec4<f32> = load %51 |
| %53:vec2<f32> = swizzle %52, xy |
| %54:vec2<u32> = swizzle %GlobalInvocationID, xy |
| %55:vec2<f32> = convert %54 |
| %56:vec2<f32> = mul %53, %55 |
| %57:ptr<uniform, vec4<f32>, read> = access %sim_params, 1u |
| %58:vec4<f32> = load %57 |
| %59:vec2<f32> = swizzle %58, zw |
| %60:vec2<f32> = mul %56, %59 |
| store %rand_seed, %60 |
| %idx:u32 = access %GlobalInvocationID, 0u |
| %62:ptr<storage, Particle, read_write> = access %data, 0u, %idx |
| %63:Particle = load %62 |
| %particle:ptr<function, Particle, read_write> = var, %63 |
| %65:ptr<storage, Particle, read_write> = access %data, 0u, %idx |
| %66:Particle = load %particle |
| store %65, %66 |
| ret |
| } |
| } |
| %export_level = @compute @workgroup_size(64, 1, 1) func(%coord:vec3<u32> [@global_invocation_id]):void -> %b8 { |
| %b8 = block { |
| %69:vec2<u32> = swizzle %coord, xy |
| %70:texture_storage_2d<rgba8unorm, write> = load %tex_out |
| %71:vec2<u32> = textureDimensions %70 |
| %72:vec2<u32> = construct %71 |
| %73:vec2<bool> = lt %69, %72 |
| %74:bool = all %73 |
| if %74 [t: %b9] { # if_1 |
| %b9 = block { # true |
| %75:u32 = access %coord, 0u |
| %76:u32 = access %coord, 1u |
| %77:ptr<uniform, u32, read> = access %ubo, 0u |
| %78:u32 = load %77 |
| %79:u32 = mul %76, %78 |
| %dst_offset:u32 = shiftl %75, %79 |
| %81:u32 = access %coord, 0u |
| %82:u32 = sub %81, 2u |
| %83:u32 = access %coord, 1u |
| %84:u32 = shiftr %83, 2u |
| %85:ptr<uniform, u32, read> = access %ubo, 0u |
| %86:u32 = load %85 |
| %87:u32 = mul %84, %86 |
| %src_offset:u32 = add %82, %87 |
| %89:u32 = shiftl %src_offset, 0u |
| %90:ptr<storage, f32, read> = access %buf_in, 0u, %89 |
| %a:f32 = load %90 |
| %92:u32 = add %src_offset, 1u |
| %93:ptr<storage, f32, read> = access %buf_in, 0u, %92 |
| %b:f32 = load %93 |
| %95:u32 = add %src_offset, 1u |
| %96:ptr<uniform, u32, read> = access %ubo, 0u |
| %97:u32 = load %96 |
| %98:u32 = add %95, %97 |
| %99:ptr<storage, f32, read> = access %buf_in, 0u, %98 |
| %c:f32 = load %99 |
| %101:u32 = add %src_offset, 1u |
| %102:ptr<uniform, u32, read> = access %ubo, 0u |
| %103:u32 = load %102 |
| %104:u32 = add %101, %103 |
| %105:ptr<storage, f32, read> = access %buf_in, 0u, %104 |
| %d:f32 = load %105 |
| %107:vec4<f32> = construct %a, %b, %c, %d |
| %sum:f32 = dot %107, vec4<f32>(1.0f) |
| %109:ptr<storage, f32, read_write> = access %buf_out, 0u, %dst_offset |
| %110:f32 = mod %sum, 4.0f |
| store %109, %110 |
| %111:f32 = mul %a, %b |
| %112:f32 = div %a, %b |
| %113:f32 = add %112, %c |
| %114:vec4<f32> = construct %a, %111, %113, %sum |
| %115:f32 = max %sum, 0.0f |
| %probabilities:vec4<f32> = add %114, %115 |
| %117:texture_storage_2d<rgba8unorm, write> = load %tex_out |
| %118:vec2<u32> = swizzle %coord, xy |
| %119:vec2<i32> = convert %118 |
| %120:void = textureStore %117, %119, %probabilities |
| exit_if # if_1 |
| } |
| } |
| ret |
| } |
| } |
| |
| unhandled variable address space |
| ******************************************************************** |
| * The tint shader compiler has encountered an unexpected error. * |
| * * |
| * Please help us fix this issue by submitting a bug report at * |
| * crbug.com/tint with the source program that triggered the bug. * |
| ******************************************************************** |
