reader/wgsl: Allow identifiers to start with an underscore

Try to lex identifiers before punctuation, and backtrack if we only
see a single underscore or something that starts with two underscores.

Rename the modf and frexp return types to start with two underscores.

Spec PR:
https://github.com/gpuweb/gpuweb/pull/2326

Change-Id: Id283af100babfe84faa183345cb8a60848140caa
Fixed: tint:1292
Reviewed-on: https://dawn-review.googlesource.com/c/tint/+/70160
Reviewed-by: David Neto <dneto@google.com>
Kokoro: Kokoro <noreply+kokoro@google.com>
Commit-Queue: James Price <jrprice@google.com>

test/bug/chromium/1236161.wgsl.expected.spvasm

@@ -10,15 +10,15 @@
                OpExecutionMode %unused_entry_point LocalSize 1 1 1
                OpName %unused_entry_point "unused_entry_point"
                OpName %tint_symbol "tint_symbol"
-               OpName %_modf_result "_modf_result"
-               OpMemberName %_modf_result 0 "fract"
-               OpMemberName %_modf_result 1 "whole"
-               OpMemberDecorate %_modf_result 0 Offset 0
-               OpMemberDecorate %_modf_result 1 Offset 4
+               OpName %__modf_result "__modf_result"
+               OpMemberName %__modf_result 0 "fract"
+               OpMemberName %__modf_result 1 "whole"
+               OpMemberDecorate %__modf_result 0 Offset 0
+               OpMemberDecorate %__modf_result 1 Offset 4
        %void = OpTypeVoid
           %1 = OpTypeFunction %void
       %float = OpTypeFloat 32
-%_modf_result = OpTypeStruct %float %float
+%__modf_result = OpTypeStruct %float %float
     %float_1 = OpConstant %float 1
 %unused_entry_point = OpFunction %void None %1
           %4 = OpLabel
@@ -26,7 +26,7 @@
                OpFunctionEnd
 %tint_symbol = OpFunction %void None %1
           %6 = OpLabel
-          %7 = OpExtInst %_modf_result %10 ModfStruct %float_1
+          %7 = OpExtInst %__modf_result %10 ModfStruct %float_1
          %12 = OpCompositeExtract %float %7 1
                OpReturn
                OpFunctionEnd

test/intrinsics/frexp.wgsl.expected.spvasm

@@ -9,20 +9,20 @@
                OpEntryPoint GLCompute %main "main"
                OpExecutionMode %main LocalSize 1 1 1
                OpName %main "main"
-               OpName %_frexp_result "_frexp_result"
-               OpMemberName %_frexp_result 0 "sig"
-               OpMemberName %_frexp_result 1 "exp"
-               OpMemberDecorate %_frexp_result 0 Offset 0
-               OpMemberDecorate %_frexp_result 1 Offset 4
+               OpName %__frexp_result "__frexp_result"
+               OpMemberName %__frexp_result 0 "sig"
+               OpMemberName %__frexp_result 1 "exp"
+               OpMemberDecorate %__frexp_result 0 Offset 0
+               OpMemberDecorate %__frexp_result 1 Offset 4
        %void = OpTypeVoid
           %1 = OpTypeFunction %void
       %float = OpTypeFloat 32
         %int = OpTypeInt 32 1
-%_frexp_result = OpTypeStruct %float %int
+%__frexp_result = OpTypeStruct %float %int
 %float_1_23000002 = OpConstant %float 1.23000002
        %main = OpFunction %void None %1
           %4 = OpLabel
-          %5 = OpExtInst %_frexp_result %9 FrexpStruct %float_1_23000002
+          %5 = OpExtInst %__frexp_result %9 FrexpStruct %float_1_23000002
          %11 = OpCompositeExtract %int %5 1
          %12 = OpCompositeExtract %float %5 0
                OpReturn

test/intrinsics/gen/frexp/368997.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn frexp(vec<3, f32>) -> _frexp_result_vec<3>
-fn frexp_a0eb3b() {
+// fn frexp(vec<3, f32>) -> __frexp_result_vec<3>
+fn frexp_368997() {
   var res = frexp(vec3<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_a0eb3b();
+  frexp_368997();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_a0eb3b();
+  frexp_368997();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_a0eb3b();
+  frexp_368997();
 }

test/intrinsics/gen/frexp/368997.wgsl.expected.glsl

@@ -15,7 +15,7 @@ frexp_result_vec3 tint_frexp(vec3 param_0) {
 }
 
 
-void frexp_a0eb3b() {
+void frexp_368997() {
   frexp_result_vec3 res = tint_frexp(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  frexp_a0eb3b();
+  frexp_368997();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ frexp_result_vec3 tint_frexp(vec3 param_0) {
 }
 
 
-void frexp_a0eb3b() {
+void frexp_368997() {
   frexp_result_vec3 res = tint_frexp(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ frexp_result_vec3 tint_frexp(vec3 param_0) {
 }
 
 
-void frexp_a0eb3b() {
+void frexp_368997() {
   frexp_result_vec3 res = tint_frexp(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }
 void main() {

test/intrinsics/gen/frexp/368997.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ frexp_result_vec3 tint_frexp(float3 param_0) {
   return result;
 }
 
-void frexp_a0eb3b() {
+void frexp_368997() {
   frexp_result_vec3 res = tint_frexp(float3(0.0f, 0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  frexp_a0eb3b();
+  frexp_368997();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }

test/intrinsics/gen/frexp/368997.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void frexp_a0eb3b() {
+void frexp_368997() {
   frexp_result_vec3 res = tint_frexp(float3());
 }
 
 float4 vertex_main_inner() {
-  frexp_a0eb3b();
+  frexp_368997();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }
 
 kernel void compute_main() {
-  frexp_a0eb3b();
+  frexp_368997();
   return;
 }
 

test/intrinsics/gen/frexp/368997.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %frexp_a0eb3b "frexp_a0eb3b"
-               OpName %_frexp_result_vec3 "_frexp_result_vec3"
-               OpMemberName %_frexp_result_vec3 0 "sig"
-               OpMemberName %_frexp_result_vec3 1 "exp"
+               OpName %frexp_368997 "frexp_368997"
+               OpName %__frexp_result_vec3 "__frexp_result_vec3"
+               OpMemberName %__frexp_result_vec3 0 "sig"
+               OpMemberName %__frexp_result_vec3 1 "exp"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_frexp_result_vec3 0 Offset 0
-               OpMemberDecorate %_frexp_result_vec3 1 Offset 16
+               OpMemberDecorate %__frexp_result_vec3 0 Offset 0
+               OpMemberDecorate %__frexp_result_vec3 1 Offset 16
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -39,22 +39,22 @@
     %v3float = OpTypeVector %float 3
         %int = OpTypeInt 32 1
       %v3int = OpTypeVector %int 3
-%_frexp_result_vec3 = OpTypeStruct %v3float %v3int
+%__frexp_result_vec3 = OpTypeStruct %v3float %v3int
          %19 = OpConstantNull %v3float
-%_ptr_Function__frexp_result_vec3 = OpTypePointer Function %_frexp_result_vec3
-         %22 = OpConstantNull %_frexp_result_vec3
+%_ptr_Function___frexp_result_vec3 = OpTypePointer Function %__frexp_result_vec3
+         %22 = OpConstantNull %__frexp_result_vec3
          %23 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%frexp_a0eb3b = OpFunction %void None %9
+%frexp_368997 = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__frexp_result_vec3 Function %22
-         %13 = OpExtInst %_frexp_result_vec3 %18 FrexpStruct %19
+        %res = OpVariable %_ptr_Function___frexp_result_vec3 Function %22
+         %13 = OpExtInst %__frexp_result_vec3 %18 FrexpStruct %19
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %23
          %25 = OpLabel
-         %26 = OpFunctionCall %void %frexp_a0eb3b
+         %26 = OpFunctionCall %void %frexp_368997
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -66,11 +66,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %32 = OpLabel
-         %33 = OpFunctionCall %void %frexp_a0eb3b
+         %33 = OpFunctionCall %void %frexp_368997
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %35 = OpLabel
-         %36 = OpFunctionCall %void %frexp_a0eb3b
+         %36 = OpFunctionCall %void %frexp_368997
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/frexp/368997.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn frexp_a0eb3b() {
+fn frexp_368997() {
   var res = frexp(vec3<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_a0eb3b();
+  frexp_368997();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_a0eb3b();
+  frexp_368997();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_a0eb3b();
+  frexp_368997();
 }

test/intrinsics/gen/frexp/3c4f48.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn frexp(vec<4, f32>) -> _frexp_result_vec<4>
-fn frexp_d80367() {
+// fn frexp(vec<4, f32>) -> __frexp_result_vec<4>
+fn frexp_3c4f48() {
   var res = frexp(vec4<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_d80367();
+  frexp_3c4f48();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_d80367();
+  frexp_3c4f48();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_d80367();
+  frexp_3c4f48();
 }

test/intrinsics/gen/frexp/3c4f48.wgsl.expected.glsl

@@ -15,7 +15,7 @@ frexp_result_vec4 tint_frexp(vec4 param_0) {
 }
 
 
-void frexp_d80367() {
+void frexp_3c4f48() {
   frexp_result_vec4 res = tint_frexp(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  frexp_d80367();
+  frexp_3c4f48();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ frexp_result_vec4 tint_frexp(vec4 param_0) {
 }
 
 
-void frexp_d80367() {
+void frexp_3c4f48() {
   frexp_result_vec4 res = tint_frexp(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ frexp_result_vec4 tint_frexp(vec4 param_0) {
 }
 
 
-void frexp_d80367() {
+void frexp_3c4f48() {
   frexp_result_vec4 res = tint_frexp(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }
 void main() {

test/intrinsics/gen/frexp/3c4f48.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ frexp_result_vec4 tint_frexp(float4 param_0) {
   return result;
 }
 
-void frexp_d80367() {
+void frexp_3c4f48() {
   frexp_result_vec4 res = tint_frexp(float4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  frexp_d80367();
+  frexp_3c4f48();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }

test/intrinsics/gen/frexp/3c4f48.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void frexp_d80367() {
+void frexp_3c4f48() {
   frexp_result_vec4 res = tint_frexp(float4());
 }
 
 float4 vertex_main_inner() {
-  frexp_d80367();
+  frexp_3c4f48();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }
 
 kernel void compute_main() {
-  frexp_d80367();
+  frexp_3c4f48();
   return;
 }
 

test/intrinsics/gen/frexp/3c4f48.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %frexp_d80367 "frexp_d80367"
-               OpName %_frexp_result_vec4 "_frexp_result_vec4"
-               OpMemberName %_frexp_result_vec4 0 "sig"
-               OpMemberName %_frexp_result_vec4 1 "exp"
+               OpName %frexp_3c4f48 "frexp_3c4f48"
+               OpName %__frexp_result_vec4 "__frexp_result_vec4"
+               OpMemberName %__frexp_result_vec4 0 "sig"
+               OpMemberName %__frexp_result_vec4 1 "exp"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_frexp_result_vec4 0 Offset 0
-               OpMemberDecorate %_frexp_result_vec4 1 Offset 16
+               OpMemberDecorate %__frexp_result_vec4 0 Offset 0
+               OpMemberDecorate %__frexp_result_vec4 1 Offset 16
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -38,21 +38,21 @@
           %9 = OpTypeFunction %void
         %int = OpTypeInt 32 1
       %v4int = OpTypeVector %int 4
-%_frexp_result_vec4 = OpTypeStruct %v4float %v4int
-%_ptr_Function__frexp_result_vec4 = OpTypePointer Function %_frexp_result_vec4
-         %20 = OpConstantNull %_frexp_result_vec4
+%__frexp_result_vec4 = OpTypeStruct %v4float %v4int
+%_ptr_Function___frexp_result_vec4 = OpTypePointer Function %__frexp_result_vec4
+         %20 = OpConstantNull %__frexp_result_vec4
          %21 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%frexp_d80367 = OpFunction %void None %9
+%frexp_3c4f48 = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__frexp_result_vec4 Function %20
-         %13 = OpExtInst %_frexp_result_vec4 %17 FrexpStruct %5
+        %res = OpVariable %_ptr_Function___frexp_result_vec4 Function %20
+         %13 = OpExtInst %__frexp_result_vec4 %17 FrexpStruct %5
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %21
          %23 = OpLabel
-         %24 = OpFunctionCall %void %frexp_d80367
+         %24 = OpFunctionCall %void %frexp_3c4f48
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -64,11 +64,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %30 = OpLabel
-         %31 = OpFunctionCall %void %frexp_d80367
+         %31 = OpFunctionCall %void %frexp_3c4f48
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %33 = OpLabel
-         %34 = OpFunctionCall %void %frexp_d80367
+         %34 = OpFunctionCall %void %frexp_3c4f48
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/frexp/3c4f48.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn frexp_d80367() {
+fn frexp_3c4f48() {
   var res = frexp(vec4<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_d80367();
+  frexp_3c4f48();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_d80367();
+  frexp_3c4f48();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_d80367();
+  frexp_3c4f48();
 }

test/intrinsics/gen/frexp/4bdfc7.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn frexp(vec<2, f32>) -> _frexp_result_vec<2>
-fn frexp_db0637() {
+// fn frexp(vec<2, f32>) -> __frexp_result_vec<2>
+fn frexp_4bdfc7() {
   var res = frexp(vec2<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_db0637();
+  frexp_4bdfc7();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
 }

test/intrinsics/gen/frexp/4bdfc7.wgsl.expected.glsl

@@ -15,7 +15,7 @@ frexp_result_vec2 tint_frexp(vec2 param_0) {
 }
 
 
-void frexp_db0637() {
+void frexp_4bdfc7() {
   frexp_result_vec2 res = tint_frexp(vec2(0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ frexp_result_vec2 tint_frexp(vec2 param_0) {
 }
 
 
-void frexp_db0637() {
+void frexp_4bdfc7() {
   frexp_result_vec2 res = tint_frexp(vec2(0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ frexp_result_vec2 tint_frexp(vec2 param_0) {
 }
 
 
-void frexp_db0637() {
+void frexp_4bdfc7() {
   frexp_result_vec2 res = tint_frexp(vec2(0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }
 void main() {

test/intrinsics/gen/frexp/4bdfc7.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ frexp_result_vec2 tint_frexp(float2 param_0) {
   return result;
 }
 
-void frexp_db0637() {
+void frexp_4bdfc7() {
   frexp_result_vec2 res = tint_frexp(float2(0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }

test/intrinsics/gen/frexp/4bdfc7.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void frexp_db0637() {
+void frexp_4bdfc7() {
   frexp_result_vec2 res = tint_frexp(float2());
 }
 
 float4 vertex_main_inner() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }
 
 kernel void compute_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
   return;
 }
 

test/intrinsics/gen/frexp/4bdfc7.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %frexp_db0637 "frexp_db0637"
-               OpName %_frexp_result_vec2 "_frexp_result_vec2"
-               OpMemberName %_frexp_result_vec2 0 "sig"
-               OpMemberName %_frexp_result_vec2 1 "exp"
+               OpName %frexp_4bdfc7 "frexp_4bdfc7"
+               OpName %__frexp_result_vec2 "__frexp_result_vec2"
+               OpMemberName %__frexp_result_vec2 0 "sig"
+               OpMemberName %__frexp_result_vec2 1 "exp"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_frexp_result_vec2 0 Offset 0
-               OpMemberDecorate %_frexp_result_vec2 1 Offset 8
+               OpMemberDecorate %__frexp_result_vec2 0 Offset 0
+               OpMemberDecorate %__frexp_result_vec2 1 Offset 8
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -39,22 +39,22 @@
     %v2float = OpTypeVector %float 2
         %int = OpTypeInt 32 1
       %v2int = OpTypeVector %int 2
-%_frexp_result_vec2 = OpTypeStruct %v2float %v2int
+%__frexp_result_vec2 = OpTypeStruct %v2float %v2int
          %19 = OpConstantNull %v2float
-%_ptr_Function__frexp_result_vec2 = OpTypePointer Function %_frexp_result_vec2
-         %22 = OpConstantNull %_frexp_result_vec2
+%_ptr_Function___frexp_result_vec2 = OpTypePointer Function %__frexp_result_vec2
+         %22 = OpConstantNull %__frexp_result_vec2
          %23 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%frexp_db0637 = OpFunction %void None %9
+%frexp_4bdfc7 = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__frexp_result_vec2 Function %22
-         %13 = OpExtInst %_frexp_result_vec2 %18 FrexpStruct %19
+        %res = OpVariable %_ptr_Function___frexp_result_vec2 Function %22
+         %13 = OpExtInst %__frexp_result_vec2 %18 FrexpStruct %19
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %23
          %25 = OpLabel
-         %26 = OpFunctionCall %void %frexp_db0637
+         %26 = OpFunctionCall %void %frexp_4bdfc7
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -66,11 +66,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %32 = OpLabel
-         %33 = OpFunctionCall %void %frexp_db0637
+         %33 = OpFunctionCall %void %frexp_4bdfc7
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %35 = OpLabel
-         %36 = OpFunctionCall %void %frexp_db0637
+         %36 = OpFunctionCall %void %frexp_4bdfc7
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/frexp/4bdfc7.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn frexp_db0637() {
+fn frexp_4bdfc7() {
   var res = frexp(vec2<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_db0637();
+  frexp_4bdfc7();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_db0637();
+  frexp_4bdfc7();
 }

test/intrinsics/gen/frexp/eabd40.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn frexp(f32) -> _frexp_result
-fn frexp_12f1da() {
+// fn frexp(f32) -> __frexp_result
+fn frexp_eabd40() {
   var res = frexp(1.0);
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_12f1da();
+  frexp_eabd40();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_12f1da();
+  frexp_eabd40();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_12f1da();
+  frexp_eabd40();
 }

test/intrinsics/gen/frexp/eabd40.wgsl.expected.glsl

@@ -15,7 +15,7 @@ frexp_result tint_frexp(float param_0) {
 }
 
 
-void frexp_12f1da() {
+void frexp_eabd40() {
   frexp_result res = tint_frexp(1.0f);
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  frexp_12f1da();
+  frexp_eabd40();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ frexp_result tint_frexp(float param_0) {
 }
 
 
-void frexp_12f1da() {
+void frexp_eabd40() {
   frexp_result res = tint_frexp(1.0f);
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ frexp_result tint_frexp(float param_0) {
 }
 
 
-void frexp_12f1da() {
+void frexp_eabd40() {
   frexp_result res = tint_frexp(1.0f);
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }
 void main() {

test/intrinsics/gen/frexp/eabd40.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ frexp_result tint_frexp(float param_0) {
   return result;
 }
 
-void frexp_12f1da() {
+void frexp_eabd40() {
   frexp_result res = tint_frexp(1.0f);
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  frexp_12f1da();
+  frexp_eabd40();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }

test/intrinsics/gen/frexp/eabd40.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void frexp_12f1da() {
+void frexp_eabd40() {
   frexp_result res = tint_frexp(1.0f);
 }
 
 float4 vertex_main_inner() {
-  frexp_12f1da();
+  frexp_eabd40();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }
 
 kernel void compute_main() {
-  frexp_12f1da();
+  frexp_eabd40();
   return;
 }
 

test/intrinsics/gen/frexp/eabd40.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %frexp_12f1da "frexp_12f1da"
-               OpName %_frexp_result "_frexp_result"
-               OpMemberName %_frexp_result 0 "sig"
-               OpMemberName %_frexp_result 1 "exp"
+               OpName %frexp_eabd40 "frexp_eabd40"
+               OpName %__frexp_result "__frexp_result"
+               OpMemberName %__frexp_result 0 "sig"
+               OpMemberName %__frexp_result 1 "exp"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_frexp_result 0 Offset 0
-               OpMemberDecorate %_frexp_result 1 Offset 4
+               OpMemberDecorate %__frexp_result 0 Offset 0
+               OpMemberDecorate %__frexp_result 1 Offset 4
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -37,21 +37,21 @@
        %void = OpTypeVoid
           %9 = OpTypeFunction %void
         %int = OpTypeInt 32 1
-%_frexp_result = OpTypeStruct %float %int
+%__frexp_result = OpTypeStruct %float %int
     %float_1 = OpConstant %float 1
-%_ptr_Function__frexp_result = OpTypePointer Function %_frexp_result
-         %20 = OpConstantNull %_frexp_result
+%_ptr_Function___frexp_result = OpTypePointer Function %__frexp_result
+         %20 = OpConstantNull %__frexp_result
          %21 = OpTypeFunction %v4float
-%frexp_12f1da = OpFunction %void None %9
+%frexp_eabd40 = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__frexp_result Function %20
-         %13 = OpExtInst %_frexp_result %16 FrexpStruct %float_1
+        %res = OpVariable %_ptr_Function___frexp_result Function %20
+         %13 = OpExtInst %__frexp_result %16 FrexpStruct %float_1
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %21
          %23 = OpLabel
-         %24 = OpFunctionCall %void %frexp_12f1da
+         %24 = OpFunctionCall %void %frexp_eabd40
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -63,11 +63,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %29 = OpLabel
-         %30 = OpFunctionCall %void %frexp_12f1da
+         %30 = OpFunctionCall %void %frexp_eabd40
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %32 = OpLabel
-         %33 = OpFunctionCall %void %frexp_12f1da
+         %33 = OpFunctionCall %void %frexp_eabd40
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/frexp/eabd40.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn frexp_12f1da() {
+fn frexp_eabd40() {
   var res = frexp(1.0);
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  frexp_12f1da();
+  frexp_eabd40();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  frexp_12f1da();
+  frexp_eabd40();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  frexp_12f1da();
+  frexp_eabd40();
 }

test/intrinsics/gen/modf/180fed.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn modf(f32) -> _modf_result
-fn modf_684d46() {
+// fn modf(f32) -> __modf_result
+fn modf_180fed() {
   var res = modf(1.0);
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_684d46();
+  modf_180fed();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_684d46();
+  modf_180fed();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_684d46();
+  modf_180fed();
 }

test/intrinsics/gen/modf/180fed.wgsl.expected.glsl

@@ -15,7 +15,7 @@ modf_result tint_modf(float param_0) {
 }
 
 
-void modf_684d46() {
+void modf_180fed() {
   modf_result res = tint_modf(1.0f);
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  modf_684d46();
+  modf_180fed();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ modf_result tint_modf(float param_0) {
 }
 
 
-void modf_684d46() {
+void modf_180fed() {
   modf_result res = tint_modf(1.0f);
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ modf_result tint_modf(float param_0) {
 }
 
 
-void modf_684d46() {
+void modf_180fed() {
   modf_result res = tint_modf(1.0f);
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }
 void main() {

test/intrinsics/gen/modf/180fed.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ modf_result tint_modf(float param_0) {
   return result;
 }
 
-void modf_684d46() {
+void modf_180fed() {
   modf_result res = tint_modf(1.0f);
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  modf_684d46();
+  modf_180fed();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }

test/intrinsics/gen/modf/180fed.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void modf_684d46() {
+void modf_180fed() {
   modf_result res = tint_modf(1.0f);
 }
 
 float4 vertex_main_inner() {
-  modf_684d46();
+  modf_180fed();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }
 
 kernel void compute_main() {
-  modf_684d46();
+  modf_180fed();
   return;
 }
 

test/intrinsics/gen/modf/180fed.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %modf_684d46 "modf_684d46"
-               OpName %_modf_result "_modf_result"
-               OpMemberName %_modf_result 0 "fract"
-               OpMemberName %_modf_result 1 "whole"
+               OpName %modf_180fed "modf_180fed"
+               OpName %__modf_result "__modf_result"
+               OpMemberName %__modf_result 0 "fract"
+               OpMemberName %__modf_result 1 "whole"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_modf_result 0 Offset 0
-               OpMemberDecorate %_modf_result 1 Offset 4
+               OpMemberDecorate %__modf_result 0 Offset 0
+               OpMemberDecorate %__modf_result 1 Offset 4
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -36,21 +36,21 @@
 %vertex_point_size = OpVariable %_ptr_Output_float Output %8
        %void = OpTypeVoid
           %9 = OpTypeFunction %void
-%_modf_result = OpTypeStruct %float %float
+%__modf_result = OpTypeStruct %float %float
     %float_1 = OpConstant %float 1
-%_ptr_Function__modf_result = OpTypePointer Function %_modf_result
-         %19 = OpConstantNull %_modf_result
+%_ptr_Function___modf_result = OpTypePointer Function %__modf_result
+         %19 = OpConstantNull %__modf_result
          %20 = OpTypeFunction %v4float
-%modf_684d46 = OpFunction %void None %9
+%modf_180fed = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__modf_result Function %19
-         %13 = OpExtInst %_modf_result %15 ModfStruct %float_1
+        %res = OpVariable %_ptr_Function___modf_result Function %19
+         %13 = OpExtInst %__modf_result %15 ModfStruct %float_1
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %20
          %22 = OpLabel
-         %23 = OpFunctionCall %void %modf_684d46
+         %23 = OpFunctionCall %void %modf_180fed
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -62,11 +62,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %28 = OpLabel
-         %29 = OpFunctionCall %void %modf_684d46
+         %29 = OpFunctionCall %void %modf_180fed
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %31 = OpLabel
-         %32 = OpFunctionCall %void %modf_684d46
+         %32 = OpFunctionCall %void %modf_180fed
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/modf/180fed.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn modf_684d46() {
+fn modf_180fed() {
   var res = modf(1.0);
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_684d46();
+  modf_180fed();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_684d46();
+  modf_180fed();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_684d46();
+  modf_180fed();
 }

test/intrinsics/gen/modf/9b75f7.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn modf(vec<3, f32>) -> _modf_result_vec<3>
-fn modf_2199f1() {
+// fn modf(vec<3, f32>) -> __modf_result_vec<3>
+fn modf_9b75f7() {
   var res = modf(vec3<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_2199f1();
+  modf_9b75f7();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_2199f1();
+  modf_9b75f7();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_2199f1();
+  modf_9b75f7();
 }

test/intrinsics/gen/modf/9b75f7.wgsl.expected.glsl

@@ -15,7 +15,7 @@ modf_result_vec3 tint_modf(vec3 param_0) {
 }
 
 
-void modf_2199f1() {
+void modf_9b75f7() {
   modf_result_vec3 res = tint_modf(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  modf_2199f1();
+  modf_9b75f7();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ modf_result_vec3 tint_modf(vec3 param_0) {
 }
 
 
-void modf_2199f1() {
+void modf_9b75f7() {
   modf_result_vec3 res = tint_modf(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ modf_result_vec3 tint_modf(vec3 param_0) {
 }
 
 
-void modf_2199f1() {
+void modf_9b75f7() {
   modf_result_vec3 res = tint_modf(vec3(0.0f, 0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }
 void main() {

test/intrinsics/gen/modf/9b75f7.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ modf_result_vec3 tint_modf(float3 param_0) {
   return result;
 }
 
-void modf_2199f1() {
+void modf_9b75f7() {
   modf_result_vec3 res = tint_modf(float3(0.0f, 0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  modf_2199f1();
+  modf_9b75f7();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }

test/intrinsics/gen/modf/9b75f7.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void modf_2199f1() {
+void modf_9b75f7() {
   modf_result_vec3 res = tint_modf(float3());
 }
 
 float4 vertex_main_inner() {
-  modf_2199f1();
+  modf_9b75f7();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }
 
 kernel void compute_main() {
-  modf_2199f1();
+  modf_9b75f7();
   return;
 }
 

test/intrinsics/gen/modf/9b75f7.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %modf_2199f1 "modf_2199f1"
-               OpName %_modf_result_vec3 "_modf_result_vec3"
-               OpMemberName %_modf_result_vec3 0 "fract"
-               OpMemberName %_modf_result_vec3 1 "whole"
+               OpName %modf_9b75f7 "modf_9b75f7"
+               OpName %__modf_result_vec3 "__modf_result_vec3"
+               OpMemberName %__modf_result_vec3 0 "fract"
+               OpMemberName %__modf_result_vec3 1 "whole"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_modf_result_vec3 0 Offset 0
-               OpMemberDecorate %_modf_result_vec3 1 Offset 16
+               OpMemberDecorate %__modf_result_vec3 0 Offset 0
+               OpMemberDecorate %__modf_result_vec3 1 Offset 16
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -37,22 +37,22 @@
        %void = OpTypeVoid
           %9 = OpTypeFunction %void
     %v3float = OpTypeVector %float 3
-%_modf_result_vec3 = OpTypeStruct %v3float %v3float
+%__modf_result_vec3 = OpTypeStruct %v3float %v3float
          %17 = OpConstantNull %v3float
-%_ptr_Function__modf_result_vec3 = OpTypePointer Function %_modf_result_vec3
-         %20 = OpConstantNull %_modf_result_vec3
+%_ptr_Function___modf_result_vec3 = OpTypePointer Function %__modf_result_vec3
+         %20 = OpConstantNull %__modf_result_vec3
          %21 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%modf_2199f1 = OpFunction %void None %9
+%modf_9b75f7 = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__modf_result_vec3 Function %20
-         %13 = OpExtInst %_modf_result_vec3 %16 ModfStruct %17
+        %res = OpVariable %_ptr_Function___modf_result_vec3 Function %20
+         %13 = OpExtInst %__modf_result_vec3 %16 ModfStruct %17
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %21
          %23 = OpLabel
-         %24 = OpFunctionCall %void %modf_2199f1
+         %24 = OpFunctionCall %void %modf_9b75f7
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -64,11 +64,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %30 = OpLabel
-         %31 = OpFunctionCall %void %modf_2199f1
+         %31 = OpFunctionCall %void %modf_9b75f7
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %33 = OpLabel
-         %34 = OpFunctionCall %void %modf_2199f1
+         %34 = OpFunctionCall %void %modf_9b75f7
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/modf/9b75f7.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn modf_2199f1() {
+fn modf_9b75f7() {
   var res = modf(vec3<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_2199f1();
+  modf_9b75f7();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_2199f1();
+  modf_9b75f7();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_2199f1();
+  modf_9b75f7();
 }

test/intrinsics/gen/modf/ec2dbc.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn modf(vec<4, f32>) -> _modf_result_vec<4>
-fn modf_9b44a9() {
+// fn modf(vec<4, f32>) -> __modf_result_vec<4>
+fn modf_ec2dbc() {
   var res = modf(vec4<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_9b44a9();
+  modf_ec2dbc();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
 }

test/intrinsics/gen/modf/ec2dbc.wgsl.expected.glsl

@@ -15,7 +15,7 @@ modf_result_vec4 tint_modf(vec4 param_0) {
 }
 
 
-void modf_9b44a9() {
+void modf_ec2dbc() {
   modf_result_vec4 res = tint_modf(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ modf_result_vec4 tint_modf(vec4 param_0) {
 }
 
 
-void modf_9b44a9() {
+void modf_ec2dbc() {
   modf_result_vec4 res = tint_modf(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ modf_result_vec4 tint_modf(vec4 param_0) {
 }
 
 
-void modf_9b44a9() {
+void modf_ec2dbc() {
   modf_result_vec4 res = tint_modf(vec4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }
 void main() {

test/intrinsics/gen/modf/ec2dbc.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ modf_result_vec4 tint_modf(float4 param_0) {
   return result;
 }
 
-void modf_9b44a9() {
+void modf_ec2dbc() {
   modf_result_vec4 res = tint_modf(float4(0.0f, 0.0f, 0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }

test/intrinsics/gen/modf/ec2dbc.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void modf_9b44a9() {
+void modf_ec2dbc() {
   modf_result_vec4 res = tint_modf(float4());
 }
 
 float4 vertex_main_inner() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }
 
 kernel void compute_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
   return;
 }
 

test/intrinsics/gen/modf/ec2dbc.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %modf_9b44a9 "modf_9b44a9"
-               OpName %_modf_result_vec4 "_modf_result_vec4"
-               OpMemberName %_modf_result_vec4 0 "fract"
-               OpMemberName %_modf_result_vec4 1 "whole"
+               OpName %modf_ec2dbc "modf_ec2dbc"
+               OpName %__modf_result_vec4 "__modf_result_vec4"
+               OpMemberName %__modf_result_vec4 0 "fract"
+               OpMemberName %__modf_result_vec4 1 "whole"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_modf_result_vec4 0 Offset 0
-               OpMemberDecorate %_modf_result_vec4 1 Offset 16
+               OpMemberDecorate %__modf_result_vec4 0 Offset 0
+               OpMemberDecorate %__modf_result_vec4 1 Offset 16
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -36,21 +36,21 @@
 %vertex_point_size = OpVariable %_ptr_Output_float Output %8
        %void = OpTypeVoid
           %9 = OpTypeFunction %void
-%_modf_result_vec4 = OpTypeStruct %v4float %v4float
-%_ptr_Function__modf_result_vec4 = OpTypePointer Function %_modf_result_vec4
-         %18 = OpConstantNull %_modf_result_vec4
+%__modf_result_vec4 = OpTypeStruct %v4float %v4float
+%_ptr_Function___modf_result_vec4 = OpTypePointer Function %__modf_result_vec4
+         %18 = OpConstantNull %__modf_result_vec4
          %19 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%modf_9b44a9 = OpFunction %void None %9
+%modf_ec2dbc = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__modf_result_vec4 Function %18
-         %13 = OpExtInst %_modf_result_vec4 %15 ModfStruct %5
+        %res = OpVariable %_ptr_Function___modf_result_vec4 Function %18
+         %13 = OpExtInst %__modf_result_vec4 %15 ModfStruct %5
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %19
          %21 = OpLabel
-         %22 = OpFunctionCall %void %modf_9b44a9
+         %22 = OpFunctionCall %void %modf_ec2dbc
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -62,11 +62,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %28 = OpLabel
-         %29 = OpFunctionCall %void %modf_9b44a9
+         %29 = OpFunctionCall %void %modf_ec2dbc
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %31 = OpLabel
-         %32 = OpFunctionCall %void %modf_9b44a9
+         %32 = OpFunctionCall %void %modf_ec2dbc
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/modf/ec2dbc.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn modf_9b44a9() {
+fn modf_ec2dbc() {
   var res = modf(vec4<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_9b44a9();
+  modf_ec2dbc();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_9b44a9();
+  modf_ec2dbc();
 }

test/intrinsics/gen/modf/f5f20d.wgsl

@@ -23,23 +23,23 @@
 ////////////////////////////////////////////////////////////////////////////////
 
 
-// fn modf(vec<2, f32>) -> _modf_result_vec<2>
-fn modf_c87851() {
+// fn modf(vec<2, f32>) -> __modf_result_vec<2>
+fn modf_f5f20d() {
   var res = modf(vec2<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_c87851();
+  modf_f5f20d();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_c87851();
+  modf_f5f20d();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_c87851();
+  modf_f5f20d();
 }

test/intrinsics/gen/modf/f5f20d.wgsl.expected.glsl

@@ -15,7 +15,7 @@ modf_result_vec2 tint_modf(vec2 param_0) {
 }
 
 
-void modf_c87851() {
+void modf_f5f20d() {
   modf_result_vec2 res = tint_modf(vec2(0.0f, 0.0f));
 }
 
@@ -24,7 +24,7 @@ struct tint_symbol {
 };
 
 vec4 vertex_main_inner() {
-  modf_c87851();
+  modf_f5f20d();
   return vec4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -64,7 +64,7 @@ modf_result_vec2 tint_modf(vec2 param_0) {
 }
 
 
-void modf_c87851() {
+void modf_f5f20d() {
   modf_result_vec2 res = tint_modf(vec2(0.0f, 0.0f));
 }
 
@@ -73,7 +73,7 @@ struct tint_symbol {
 };
 
 void fragment_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }
 void main() {
@@ -103,7 +103,7 @@ modf_result_vec2 tint_modf(vec2 param_0) {
 }
 
 
-void modf_c87851() {
+void modf_f5f20d() {
   modf_result_vec2 res = tint_modf(vec2(0.0f, 0.0f));
 }
 
@@ -113,7 +113,7 @@ struct tint_symbol {
 
 layout(local_size_x = 1, local_size_y = 1, local_size_z = 1) in;
 void compute_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }
 void main() {

test/intrinsics/gen/modf/f5f20d.wgsl.expected.hlsl

@@ -9,7 +9,7 @@ modf_result_vec2 tint_modf(float2 param_0) {
   return result;
 }
 
-void modf_c87851() {
+void modf_f5f20d() {
   modf_result_vec2 res = tint_modf(float2(0.0f, 0.0f));
 }
 
@@ -18,7 +18,7 @@ struct tint_symbol {
 };
 
 float4 vertex_main_inner() {
-  modf_c87851();
+  modf_f5f20d();
   return float4(0.0f, 0.0f, 0.0f, 0.0f);
 }
 
@@ -30,12 +30,12 @@ tint_symbol vertex_main() {
 }
 
 void fragment_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }
 
 [numthreads(1, 1, 1)]
 void compute_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }

test/intrinsics/gen/modf/f5f20d.wgsl.expected.msl

@@ -16,12 +16,12 @@ struct tint_symbol {
   float4 value [[position]];
 };
 
-void modf_c87851() {
+void modf_f5f20d() {
   modf_result_vec2 res = tint_modf(float2());
 }
 
 float4 vertex_main_inner() {
-  modf_c87851();
+  modf_f5f20d();
   return float4();
 }
 
@@ -33,12 +33,12 @@ vertex tint_symbol vertex_main() {
 }
 
 fragment void fragment_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }
 
 kernel void compute_main() {
-  modf_c87851();
+  modf_f5f20d();
   return;
 }
 

test/intrinsics/gen/modf/f5f20d.wgsl.expected.spvasm

@@ -13,10 +13,10 @@
                OpExecutionMode %compute_main LocalSize 1 1 1
                OpName %value "value"
                OpName %vertex_point_size "vertex_point_size"
-               OpName %modf_c87851 "modf_c87851"
-               OpName %_modf_result_vec2 "_modf_result_vec2"
-               OpMemberName %_modf_result_vec2 0 "fract"
-               OpMemberName %_modf_result_vec2 1 "whole"
+               OpName %modf_f5f20d "modf_f5f20d"
+               OpName %__modf_result_vec2 "__modf_result_vec2"
+               OpMemberName %__modf_result_vec2 0 "fract"
+               OpMemberName %__modf_result_vec2 1 "whole"
                OpName %res "res"
                OpName %vertex_main_inner "vertex_main_inner"
                OpName %vertex_main "vertex_main"
@@ -24,8 +24,8 @@
                OpName %compute_main "compute_main"
                OpDecorate %value BuiltIn Position
                OpDecorate %vertex_point_size BuiltIn PointSize
-               OpMemberDecorate %_modf_result_vec2 0 Offset 0
-               OpMemberDecorate %_modf_result_vec2 1 Offset 8
+               OpMemberDecorate %__modf_result_vec2 0 Offset 0
+               OpMemberDecorate %__modf_result_vec2 1 Offset 8
       %float = OpTypeFloat 32
     %v4float = OpTypeVector %float 4
 %_ptr_Output_v4float = OpTypePointer Output %v4float
@@ -37,22 +37,22 @@
        %void = OpTypeVoid
           %9 = OpTypeFunction %void
     %v2float = OpTypeVector %float 2
-%_modf_result_vec2 = OpTypeStruct %v2float %v2float
+%__modf_result_vec2 = OpTypeStruct %v2float %v2float
          %17 = OpConstantNull %v2float
-%_ptr_Function__modf_result_vec2 = OpTypePointer Function %_modf_result_vec2
-         %20 = OpConstantNull %_modf_result_vec2
+%_ptr_Function___modf_result_vec2 = OpTypePointer Function %__modf_result_vec2
+         %20 = OpConstantNull %__modf_result_vec2
          %21 = OpTypeFunction %v4float
     %float_1 = OpConstant %float 1
-%modf_c87851 = OpFunction %void None %9
+%modf_f5f20d = OpFunction %void None %9
          %12 = OpLabel
-        %res = OpVariable %_ptr_Function__modf_result_vec2 Function %20
-         %13 = OpExtInst %_modf_result_vec2 %16 ModfStruct %17
+        %res = OpVariable %_ptr_Function___modf_result_vec2 Function %20
+         %13 = OpExtInst %__modf_result_vec2 %16 ModfStruct %17
                OpStore %res %13
                OpReturn
                OpFunctionEnd
 %vertex_main_inner = OpFunction %v4float None %21
          %23 = OpLabel
-         %24 = OpFunctionCall %void %modf_c87851
+         %24 = OpFunctionCall %void %modf_f5f20d
                OpReturnValue %5
                OpFunctionEnd
 %vertex_main = OpFunction %void None %9
@@ -64,11 +64,11 @@
                OpFunctionEnd
 %fragment_main = OpFunction %void None %9
          %30 = OpLabel
-         %31 = OpFunctionCall %void %modf_c87851
+         %31 = OpFunctionCall %void %modf_f5f20d
                OpReturn
                OpFunctionEnd
 %compute_main = OpFunction %void None %9
          %33 = OpLabel
-         %34 = OpFunctionCall %void %modf_c87851
+         %34 = OpFunctionCall %void %modf_f5f20d
                OpReturn
                OpFunctionEnd

test/intrinsics/gen/modf/f5f20d.wgsl.expected.wgsl

@@ -1,19 +1,19 @@
-fn modf_c87851() {
+fn modf_f5f20d() {
   var res = modf(vec2<f32>());
 }
 
 [[stage(vertex)]]
 fn vertex_main() -> [[builtin(position)]] vec4<f32> {
-  modf_c87851();
+  modf_f5f20d();
   return vec4<f32>();
 }
 
 [[stage(fragment)]]
 fn fragment_main() {
-  modf_c87851();
+  modf_f5f20d();
 }
 
 [[stage(compute), workgroup_size(1)]]
 fn compute_main() {
-  modf_c87851();
+  modf_f5f20d();
 }

test/intrinsics/modf.wgsl.expected.spvasm

@@ -9,19 +9,19 @@
                OpEntryPoint GLCompute %main "main"
                OpExecutionMode %main LocalSize 1 1 1
                OpName %main "main"
-               OpName %_modf_result "_modf_result"
-               OpMemberName %_modf_result 0 "fract"
-               OpMemberName %_modf_result 1 "whole"
-               OpMemberDecorate %_modf_result 0 Offset 0
-               OpMemberDecorate %_modf_result 1 Offset 4
+               OpName %__modf_result "__modf_result"
+               OpMemberName %__modf_result 0 "fract"
+               OpMemberName %__modf_result 1 "whole"
+               OpMemberDecorate %__modf_result 0 Offset 0
+               OpMemberDecorate %__modf_result 1 Offset 4
        %void = OpTypeVoid
           %1 = OpTypeFunction %void
       %float = OpTypeFloat 32
-%_modf_result = OpTypeStruct %float %float
+%__modf_result = OpTypeStruct %float %float
 %float_1_23000002 = OpConstant %float 1.23000002
        %main = OpFunction %void None %1
           %4 = OpLabel
-          %5 = OpExtInst %_modf_result %8 ModfStruct %float_1_23000002
+          %5 = OpExtInst %__modf_result %8 ModfStruct %float_1_23000002
          %10 = OpCompositeExtract %float %5 0
          %11 = OpCompositeExtract %float %5 1
                OpReturn