345 lines · plain
1# RUN: llc -start-before=aarch64-asm-printer -o - %s | FileCheck %s2 3# Check that z30_z31 debug info does not crash.4 5# CHECK: .Ldebug_loc0:6# CHECK: .byte 4 // DW_LLE_offset_pair7# CHECK: .uleb128 .Ltmp2-.Lfunc_begin0 // starting offset8# CHECK: .uleb128 .Ltmp3-.Lfunc_begin0 // ending offset9# CHECK: .byte 2 // Loc expr size10# CHECK: .byte 144 // DW_OP_regx11# CHECK: .byte 126 // 12612# CHECK: .byte 4 // DW_LLE_offset_pair13# CHECK: .uleb128 .Ltmp3-.Lfunc_begin0 // starting offset14# CHECK: .uleb128 .Lfunc_end0-.Lfunc_begin0 // ending offset15# CHECK: .byte 6 // Loc expr size16# CHECK: .byte 144 // sub-register DW_OP_regx17# CHECK: .byte 94 // 9418# CHECK: .byte 147 // DW_OP_piece19# CHECK: .byte 16 // 1620# CHECK: .byte 147 // DW_OP_piece21# CHECK: .byte 31 // 3122# CHECK: .byte 0 // DW_LLE_end_of_list23 24 25--- |26 target datalayout = "e-m:e-p270:32:32-p271:32:32-p272:64:64-i8:8:32-i16:16:32-i64:64-i128:128-n32:64-S128-Fn32"27 target triple = "aarch64"28 29 define void @_Z10Sort16RowsILi6EEv12SharedTraitsI10TraitsLaneEP22Trans_NS_hwy_float16_tiS4_(i8 %st.coerce, ptr noundef %keys, i32 noundef %0, ptr noundef %1) #2 !dbg !2 {30 unreachable31 }32 33 attributes #2 = { mustprogress uwtable vscale_range(1,16) "frame-pointer"="non-leaf" "no-trapping-math"="true" "stack-protector-buffer-size"="8" "target-cpu"="neoverse-n1" "target-features"="+aes,+crc,+dotprod,+fp-armv8,+fullfp16,+lse,+neon,+perfmon,+ras,+rcpc,+rdm,+sha2,+spe,+ssbs,+sve,+sve-aes,+sve2,+sve2-aes,+v8.1a,+v8.2a,+v8a,-fmv" "tune-cpu"="generic" }34 35 !llvm.dbg.cu = !{!3}36 !llvm.module.flags = !{!4, !5, !6, !7, !8, !9}37 !llvm.ident = !{!10}38 39 !2 = distinct !DISubprogram(name: "Sort16Rows<6>", linkageName: "_Z10Sort16RowsILi6EEv12SharedTraitsI10TraitsLaneEP22Trans_NS_hwy_float16_tiS4_", scope: !12, file: !12, line: 369, type: !18, scopeLine: 370, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !19, retainedNodes: !20, keyInstructions: true)40 !3 = distinct !DICompileUnit(language: DW_LANG_C_plus_plus_14, file: !14, producer: "clang version 22.0.0git (https://github.com/llvm/llvm-project.git)", isOptimized: true, runtimeVersion: 0, emissionKind: FullDebug, splitDebugInlining: false, nameTableKind: None)41 !4 = !{i32 7, !"Dwarf Version", i32 5}42 !5 = !{i32 2, !"Debug Info Version", i32 3}43 !6 = !{i32 1, !"wchar_size", i32 4}44 !7 = !{i32 7, !"uwtable", i32 2}45 !8 = !{i32 7, !"frame-pointer", i32 1}46 !9 = !{i32 7, !"debug-info-assignment-tracking", i1 true}47 !10 = !{!"clang version 22.0.0git (https://github.com/llvm/llvm-project.git)"}48 !12 = !DIFile(filename: "example.cpp", directory: "/app", checksumkind: CSK_MD5, checksum: "5fbaafea0ede06ddd1ffc371aeee276e")49 !14 = !DIFile(filename: "/app/example.cpp", directory: "/app", checksumkind: CSK_MD5, checksum: "5fbaafea0ede06ddd1ffc371aeee276e")50 !17 = !DIBasicType(name: "__fp16", size: 16, encoding: DW_ATE_float)51 !18 = !DISubroutineType(types: !21)52 !19 = !{!120}53 !20 = !{!77, !78, !79, !80, !81, !82, !83, !84, !85, !86, !87, !88, !89, !90, !91, !92, !93, !94, !95, !96, !97, !98, !99, !100, !101, !102, !103, !104, !105}54 !21 = !{null, !22, !23, !24, !23}55 !22 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "SharedTraits<TraitsLane>", file: !12, line: 272, size: 8, flags: DIFlagTypePassByValue, elements: !25, templateParams: !26, identifier: "_ZTS12SharedTraitsI10TraitsLaneE")56 !23 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !55, size: 64)57 !24 = !DIBasicType(name: "int", size: 32, encoding: DW_ATE_signed)58 !25 = !{!27}59 !26 = !{!76}60 !27 = !DIDerivedType(tag: DW_TAG_inheritance, scope: !22, baseType: !28, extraData: i32 0)61 !28 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "TraitsLane", file: !12, line: 325, size: 8, flags: DIFlagTypePassByValue, elements: !29, identifier: "_ZTS10TraitsLane")62 !29 = !{!30, !31, !32, !33}63 !30 = !DIDerivedType(tag: DW_TAG_inheritance, scope: !28, baseType: !34, extraData: i32 0)64 !31 = !DISubprogram(name: "Sort2", linkageName: "_ZN10TraitsLane5Sort2E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EERu13__SVFloat16_tS4_", scope: !28, file: !12, line: 326, type: !70, scopeLine: 326, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)65 !32 = !DISubprogram(name: "SortPairsDistance1", linkageName: "_ZN10TraitsLane18SortPairsDistance1E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_t", scope: !28, file: !12, line: 344, type: !74, scopeLine: 344, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)66 !33 = !DISubprogram(name: "SortPairsDistance4", linkageName: "_ZN10TraitsLane18SortPairsDistance4E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_t", scope: !28, file: !12, line: 352, type: !74, scopeLine: 352, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)67 !34 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "KeyLane", file: !12, line: 307, size: 8, flags: DIFlagTypePassByValue, elements: !35, identifier: "_ZTS7KeyLane")68 !35 = !{!36, !37, !38}69 !36 = !DISubprogram(name: "SwapAdjacentPairs", linkageName: "_ZN7KeyLane17SwapAdjacentPairsE4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_t", scope: !34, file: !12, line: 309, type: !39, scopeLine: 309, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)70 !37 = !DISubprogram(name: "SwapAdjacentPairs", linkageName: "_ZN7KeyLane17SwapAdjacentPairsEu13__SVFloat32_t", scope: !34, file: !12, line: 314, type: !58, scopeLine: 314, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)71 !38 = !DISubprogram(name: "OddEvenPairs", linkageName: "_ZN7KeyLane12OddEvenPairsE4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_tS3_", scope: !34, file: !12, line: 318, type: !68, scopeLine: 318, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized)72 !39 = !DISubroutineType(types: !40)73 !40 = !{!41, !42, !43, !41}74 !41 = !DIDerivedType(tag: DW_TAG_typedef, name: "Vec<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 270, baseType: !44)75 !42 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !34, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer)76 !43 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Simd<Trans_NS_hwy_float16_t, 1, 0>", file: !12, line: 83, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !51, identifier: "_ZTS4SimdI22Trans_NS_hwy_float16_tLi1ELi0EE")77 !44 = !DIDerivedType(tag: DW_TAG_typedef, name: "VFromD<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 142, baseType: !45)78 !45 = !DIDerivedType(tag: DW_TAG_typedef, name: "svfloat16_t", file: !12, line: 26, baseType: !46)79 !46 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVFloat16_t", file: !12, baseType: !47)80 !47 = !DICompositeType(tag: DW_TAG_array_type, baseType: !17, flags: DIFlagVector, elements: !48)81 !48 = !{!49}82 !49 = !DISubrange(lowerBound: 0, upperBound: !DIExpression(DW_OP_constu, 4, DW_OP_bregx, 46, 0, DW_OP_mul, DW_OP_constu, 1, DW_OP_minus))83 !50 = !{}84 !51 = !{!52, !53, !54}85 !52 = !DITemplateTypeParameter(name: "Lane", type: !55)86 !53 = !DITemplateValueParameter(type: !24, value: i32 1)87 !54 = !DITemplateValueParameter(name: "kPow2", type: !24, value: i32 0)88 !55 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Trans_NS_hwy_float16_t", file: !12, line: 6, size: 16, flags: DIFlagTypePassByValue, elements: !56, identifier: "_ZTS22Trans_NS_hwy_float16_t")89 !56 = !{!57}90 !57 = !DIDerivedType(tag: DW_TAG_member, name: "native", scope: !55, file: !12, line: 7, baseType: !17, size: 16)91 !58 = !DISubroutineType(types: !59)92 !59 = !{!60, !42, !60}93 !60 = !DIDerivedType(tag: DW_TAG_typedef, name: "Vec<Simd<float, 0, 0> >", file: !12, line: 270, baseType: !61)94 !61 = !DIDerivedType(tag: DW_TAG_typedef, name: "VFromD<Simd<float, 0, 0> >", file: !12, line: 142, baseType: !62)95 !62 = !DIDerivedType(tag: DW_TAG_typedef, name: "svfloat32_t", file: !12, line: 27, baseType: !63)96 !63 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVFloat32_t", file: !12, baseType: !64)97 !64 = !DICompositeType(tag: DW_TAG_array_type, baseType: !65, flags: DIFlagVector, elements: !66)98 !65 = !DIBasicType(name: "float", size: 32, encoding: DW_ATE_float)99 !66 = !{!67}100 !67 = !DISubrange(lowerBound: 0, upperBound: !DIExpression(DW_OP_constu, 2, DW_OP_bregx, 46, 0, DW_OP_mul, DW_OP_constu, 1, DW_OP_minus))101 !68 = !DISubroutineType(types: !69)102 !69 = !{!41, !42, !43, !41, !41}103 !70 = !DISubroutineType(types: !71)104 !71 = !{null, !72, !43, !73, !73}105 !72 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !28, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer)106 !73 = !DIDerivedType(tag: DW_TAG_reference_type, baseType: !41, size: 64)107 !74 = !DISubroutineType(types: !75)108 !75 = !{!41, !72, !43, !41}109 !76 = !DITemplateTypeParameter(name: "Base", type: !28)110 !77 = !DILocalVariable(name: "st", arg: 1, scope: !2, file: !12, line: 369, type: !22)111 !78 = !DILocalVariable(name: "keys", arg: 2, scope: !2, file: !12, line: 369, type: !23)112 !79 = !DILocalVariable(arg: 3, scope: !2, file: !12, line: 369, type: !24)113 !80 = !DILocalVariable(arg: 4, scope: !2, file: !12, line: 370, type: !23)114 !81 = !DILocalVariable(name: "d", scope: !2, file: !12, line: 371, type: !106)115 !82 = !DILocalVariable(name: "v8", scope: !2, file: !12, line: 373, type: !112)116 !83 = !DILocalVariable(name: "v9", scope: !2, file: !12, line: 373, type: !112)117 !84 = !DILocalVariable(name: "va", scope: !2, file: !12, line: 373, type: !112)118 !85 = !DILocalVariable(name: "vb", scope: !2, file: !12, line: 373, type: !112)119 !86 = !DILocalVariable(name: "vc", scope: !2, file: !12, line: 373, type: !112)120 !87 = !DILocalVariable(name: "vd", scope: !2, file: !12, line: 373, type: !112)121 !88 = !DILocalVariable(name: "ve", scope: !2, file: !12, line: 373, type: !112)122 !89 = !DILocalVariable(name: "vf", scope: !2, file: !12, line: 373, type: !112)123 !90 = !DILocalVariable(name: "v2", scope: !2, file: !12, line: 373, type: !112)124 !91 = !DILocalVariable(name: "v4", scope: !2, file: !12, line: 373, type: !112)125 !92 = !DILocalVariable(name: "v7", scope: !2, file: !12, line: 373, type: !112)126 !93 = !DILocalVariable(name: "v0", scope: !2, file: !12, line: 374, type: !112)127 !94 = !DILocalVariable(name: "v3", scope: !2, file: !12, line: 375, type: !112)128 !95 = !DILocalVariable(name: "v5", scope: !2, file: !12, line: 376, type: !112)129 !96 = !DILocalVariable(name: "v6", scope: !2, file: !12, line: 377, type: !112)130 !97 = !DILocalVariable(name: "kIota", scope: !2, file: !12, line: 378, type: !112)131 !98 = !DILocalVariable(name: "m8", scope: !2, file: !12, line: 379, type: !113)132 !99 = !DILocalVariable(name: "m9", scope: !2, file: !12, line: 380, type: !113)133 !100 = !DILocalVariable(name: "ma", scope: !2, file: !12, line: 381, type: !113)134 !101 = !DILocalVariable(name: "mb", scope: !2, file: !12, line: 382, type: !113)135 !102 = !DILocalVariable(name: "mc", scope: !2, file: !12, line: 383, type: !113)136 !103 = !DILocalVariable(name: "md", scope: !2, file: !12, line: 384, type: !113)137 !104 = !DILocalVariable(name: "me", scope: !2, file: !12, line: 385, type: !113)138 !105 = !DILocalVariable(name: "mf", scope: !2, file: !12, line: 386, type: !113)139 !106 = !DIDerivedType(tag: DW_TAG_typedef, name: "CappedTag<Trans_NS_hwy_float16_t, 6>", file: !12, line: 97, baseType: !107)140 !107 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !108, file: !12, line: 89, baseType: !43)141 !108 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "ClampNAndPow2<Trans_NS_hwy_float16_t, 1>", file: !12, line: 88, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !109, identifier: "_ZTS13ClampNAndPow2I22Trans_NS_hwy_float16_tLi1EE")142 !109 = !{!110, !111}143 !110 = !DITemplateTypeParameter(name: "T", type: !55)144 !111 = !DITemplateValueParameter(name: "N", type: !24, value: i32 1)145 !112 = !DIDerivedType(tag: DW_TAG_typedef, name: "V", scope: !2, file: !12, line: 372, baseType: !41)146 !113 = !DIDerivedType(tag: DW_TAG_typedef, name: "Mask<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 271, baseType: !114)147 !114 = !DIDerivedType(tag: DW_TAG_typedef, name: "svbool_t", file: !12, line: 28, baseType: !115)148 !115 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVBool_t", file: !12, baseType: !116)149 !116 = !DICompositeType(tag: DW_TAG_array_type, baseType: !117, flags: DIFlagVector, elements: !118)150 !117 = !DIBasicType(name: "unsigned char", size: 8, encoding: DW_ATE_unsigned_char)151 !118 = !{!119}152 !119 = !DISubrange(lowerBound: 0, upperBound: !DIExpression(DW_OP_constu, 1, DW_OP_bregx, 46, 0, DW_OP_mul, DW_OP_constu, 1, DW_OP_minus))153 !120 = !DITemplateValueParameter(name: "kKeysPerRow", type: !24, value: i32 6)154 !121 = !DILocalVariable(name: "this", arg: 1, scope: !122, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer)155 !122 = distinct !DISubprogram(name: "Sort2", linkageName: "_ZN10TraitsLane5Sort2E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EERu13__SVFloat16_tS4_", scope: !28, file: !12, line: 326, type: !70, scopeLine: 328, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, declaration: !31, retainedNodes: !124, keyInstructions: true)156 !123 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !28, size: 64)157 !124 = !{!121, !125, !126, !127, !128, !129, !130, !131, !132}158 !125 = !DILocalVariable(name: "d", arg: 2, scope: !122, file: !12, line: 326, type: !43)159 !126 = !DILocalVariable(name: "a", arg: 3, scope: !122, file: !12, line: 327, type: !73)160 !127 = !DILocalVariable(name: "b", arg: 4, scope: !122, file: !12, line: 328, type: !73)161 !128 = !DILocalVariable(name: "__trans_tmp_52", scope: !122, file: !12, line: 329, type: !41)162 !129 = !DILocalVariable(name: "a_copy", scope: !122, file: !12, line: 329, type: !41)163 !130 = !DILocalVariable(name: "__trans_tmp_45", scope: !122, file: !12, line: 330, type: !41)164 !131 = !DILocalVariable(name: "__trans_tmp_53", scope: !133, file: !12, line: 334, type: !41)165 !132 = !DILocalVariable(name: "__trans_tmp_29", scope: !134, file: !12, line: 336, type: !45)166 !133 = distinct !DILexicalBlock(scope: !122, file: !12, line: 333, column: 5)167 !134 = distinct !DILexicalBlock(scope: !133, file: !12, line: 335, column: 7)168 !137 = distinct !DISubprogram(name: "SortPairsDistance1", linkageName: "_ZN10TraitsLane18SortPairsDistance1E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_t", scope: !28, file: !12, line: 344, type: !74, scopeLine: 345, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, declaration: !32, retainedNodes: !139, keyInstructions: true)169 !139 = !{!140, !141, !142, !143}170 !140 = !DILocalVariable(name: "this", arg: 1, scope: !137, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer)171 !141 = !DILocalVariable(name: "d", arg: 2, scope: !137, file: !12, line: 344, type: !43)172 !142 = !DILocalVariable(name: "v", arg: 3, scope: !137, file: !12, line: 345, type: !41)173 !143 = !DILocalVariable(name: "__trans_tmp_48", scope: !137, file: !12, line: 346, type: !41)174 !144 = distinct !DISubprogram(name: "Merge16x16<6, SharedTraits<TraitsLane>, __SVFloat16_t>", linkageName: "_Z10Merge16x16ILi6E12SharedTraitsI10TraitsLaneEu13__SVFloat16_tEvT0_RT1_S6_S6_S6_S6_S6_S6_S6_S6_S6_S6_S6_", scope: !12, file: !12, line: 286, type: !146, scopeLine: 288, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !147, retainedNodes: !148, keyInstructions: true)175 !145 = distinct !DILocation(line: 388, column: 3, scope: !2)176 !146 = !DISubroutineType(types: !149)177 !147 = !{!164, !165, !166}178 !148 = !{!151, !152, !153, !154, !155, !156, !157, !158, !159, !160, !161, !162, !163}179 !149 = !{null, !22, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150}180 !150 = !DIDerivedType(tag: DW_TAG_reference_type, baseType: !47, size: 64)181 !151 = !DILocalVariable(name: "st", arg: 1, scope: !144, file: !12, line: 286, type: !22)182 !152 = !DILocalVariable(name: "v0", arg: 2, scope: !144, file: !12, line: 286, type: !150)183 !153 = !DILocalVariable(name: "v2", arg: 3, scope: !144, file: !12, line: 286, type: !150)184 !154 = !DILocalVariable(name: "v5", arg: 4, scope: !144, file: !12, line: 286, type: !150)185 !155 = !DILocalVariable(name: "v6", arg: 5, scope: !144, file: !12, line: 287, type: !150)186 !156 = !DILocalVariable(name: "v7", arg: 6, scope: !144, file: !12, line: 287, type: !150)187 !157 = !DILocalVariable(name: "v9", arg: 7, scope: !144, file: !12, line: 287, type: !150)188 !158 = !DILocalVariable(name: "va", arg: 8, scope: !144, file: !12, line: 287, type: !150)189 !159 = !DILocalVariable(name: "vb", arg: 9, scope: !144, file: !12, line: 287, type: !150)190 !160 = !DILocalVariable(name: "vc", arg: 10, scope: !144, file: !12, line: 288, type: !150)191 !161 = !DILocalVariable(name: "vd", arg: 11, scope: !144, file: !12, line: 288, type: !150)192 !162 = !DILocalVariable(name: "ve", arg: 12, scope: !144, file: !12, line: 288, type: !150)193 !163 = !DILocalVariable(name: "vf", arg: 13, scope: !144, file: !12, line: 288, type: !150)194 !164 = !DITemplateValueParameter(type: !24, value: i32 6)195 !165 = !DITemplateTypeParameter(name: "Traits", type: !22)196 !166 = !DITemplateTypeParameter(name: "V", type: !47)197 !184 = !DILocalVariable(name: "this", arg: 1, scope: !185, type: !186, flags: DIFlagArtificial | DIFlagObjectPointer)198 !185 = distinct !DISubprogram(name: "SortPairsDistance2<Simd<Trans_NS_hwy_float16_t, 1, 0> >", linkageName: "_ZN12SharedTraitsI10TraitsLaneE18SortPairsDistance2I4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEEEDTcl4ZerocvT__EEES6_S7_", scope: !22, file: !12, line: 273, type: !187, scopeLine: 273, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !188, declaration: !189, retainedNodes: !190, keyInstructions: true)199 !186 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !22, size: 64)200 !187 = !DISubroutineType(types: !191)201 !188 = !{!193}202 !189 = !DISubprogram(name: "SortPairsDistance2<Simd<Trans_NS_hwy_float16_t, 1, 0> >", linkageName: "_ZN12SharedTraitsI10TraitsLaneE18SortPairsDistance2I4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEEEDTcl4ZerocvT__EEES6_S7_", scope: !22, file: !12, line: 273, type: !187, scopeLine: 273, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized, templateParams: !188)203 !190 = !{!184, !194, !195, !196, !197}204 !191 = !{!41, !192, !43, !41}205 !192 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !22, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer)206 !193 = !DITemplateTypeParameter(name: "D", type: !43)207 !194 = !DILocalVariable(name: "d", arg: 2, scope: !185, file: !12, line: 273, type: !43)208 !195 = !DILocalVariable(name: "v", arg: 3, scope: !185, file: !12, line: 273, type: !41)209 !196 = !DILocalVariable(name: "base", scope: !185, file: !12, line: 274, type: !28)210 !197 = !DILocalVariable(name: "swapped", scope: !185, file: !12, line: 275, type: !41)211 !200 = !DILocation(line: 0, scope: !122, inlinedAt: !201)212 !201 = distinct !DILocation(line: 358, column: 5, scope: !202, inlinedAt: !203)213 !202 = distinct !DISubprogram(name: "SortPairsDistance4", linkageName: "_ZN10TraitsLane18SortPairsDistance4E4SimdI22Trans_NS_hwy_float16_tLi1ELi0EEu13__SVFloat16_t", scope: !28, file: !12, line: 352, type: !74, scopeLine: 353, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, declaration: !33, retainedNodes: !204, keyInstructions: true)214 !203 = distinct !DILocation(line: 298, column: 11, scope: !144, inlinedAt: !145)215 !204 = !{!205, !206, !207, !208, !209, !210, !211}216 !205 = !DILocalVariable(name: "this", arg: 1, scope: !202, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer)217 !206 = !DILocalVariable(name: "d", arg: 2, scope: !202, file: !12, line: 352, type: !43)218 !207 = !DILocalVariable(name: "v", arg: 3, scope: !202, file: !12, line: 353, type: !41)219 !208 = !DILocalVariable(name: "__trans_tmp_42", scope: !202, file: !12, line: 354, type: !41)220 !209 = !DILocalVariable(name: "__trans_tmp_39", scope: !202, file: !12, line: 354, type: !41)221 !210 = !DILocalVariable(name: "dw", scope: !202, file: !12, line: 355, type: !212)222 !211 = !DILocalVariable(name: "__trans_tmp_51", scope: !219, file: !12, line: 360, type: !44)223 !212 = !DIDerivedType(tag: DW_TAG_typedef, name: "RepartitionToWide<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 103, baseType: !213)224 !213 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<float, Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 101, baseType: !214)225 !214 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<float>", scope: !43, file: !12, line: 86, baseType: !215)226 !215 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Simd<float, 0, 0>", file: !12, line: 83, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !216, identifier: "_ZTS4SimdIfLi0ELi0EE")227 !216 = !{!217, !218, !54}228 !217 = !DITemplateTypeParameter(name: "Lane", type: !65)229 !218 = !DITemplateValueParameter(type: !24, value: i32 0)230 !219 = distinct !DILexicalBlock(scope: !202, file: !12, line: 359, column: 5)231 !220 = !DILocalVariable(name: "this", arg: 1, scope: !221, type: !222, flags: DIFlagArtificial | DIFlagObjectPointer)232 !221 = distinct !DISubprogram(name: "SwapAdjacentPairs", linkageName: "_ZN7KeyLane17SwapAdjacentPairsEu13__SVFloat32_t", scope: !34, file: !12, line: 314, type: !58, scopeLine: 314, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, declaration: !37, retainedNodes: !223, keyInstructions: true)233 !222 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !34, size: 64)234 !223 = !{!220, !224}235 !224 = !DILocalVariable(name: "v", arg: 2, scope: !221, file: !12, line: 314, type: !60)236 !225 = distinct !DILocation(line: 357, column: 38, scope: !202, inlinedAt: !203)237 !226 = !DILocalVariable(name: "v", arg: 1, scope: !227, file: !12, line: 264, type: !64)238 !227 = distinct !DISubprogram(name: "Shuffle1032<__SVFloat32_t>", linkageName: "_Z11Shuffle1032Iu13__SVFloat32_tET_S1_", scope: !12, file: !12, line: 264, type: !228, scopeLine: 264, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !229, retainedNodes: !230, keyInstructions: true)239 !228 = !DISubroutineType(types: !231)240 !229 = !{!262}241 !230 = !{!226, !232, !233, !234}242 !231 = !{!64, !64}243 !232 = !DILocalVariable(name: "d", scope: !227, file: !12, line: 265, type: !235)244 !233 = !DILocalVariable(name: "d8", scope: !227, file: !12, line: 266, type: !252)245 !234 = !DILocalVariable(name: "v8", scope: !227, file: !12, line: 267, type: !257)246 !235 = !DIDerivedType(tag: DW_TAG_typedef, name: "DFromV<__SVFloat32_t>", file: !12, line: 108, baseType: !236)247 !236 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !237, file: !12, line: 116, baseType: !238)248 !237 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "DFromV_t<__SVFloat32_t>", file: !12, line: 115, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !239, identifier: "_ZTS8DFromV_tIu13__SVFloat32_tE")249 !238 = !DIDerivedType(tag: DW_TAG_typedef, name: "ScalableTag<float>", file: !12, line: 95, baseType: !241)250 !239 = !{!240}251 !240 = !DITemplateTypeParameter(type: !64)252 !241 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !242, file: !12, line: 92, baseType: !243)253 !242 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "ScalableTagChecker<float>", file: !12, line: 91, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !244, identifier: "_ZTS18ScalableTagCheckerIfE")254 !243 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !246, file: !12, line: 89, baseType: !247)255 !244 = !{!245}256 !245 = !DITemplateTypeParameter(name: "T", type: !65)257 !246 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "ClampNAndPow2<float, 64>", file: !12, line: 88, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !248, identifier: "_ZTS13ClampNAndPow2IfLi64EE")258 !247 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Simd<float, 64, 0>", file: !12, line: 83, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !250, identifier: "_ZTS4SimdIfLi64ELi0EE")259 !248 = !{!245, !249}260 !249 = !DITemplateValueParameter(name: "N", type: !24, value: i32 64)261 !250 = !{!217, !251, !54}262 !251 = !DITemplateValueParameter(type: !24, value: i32 64)263 !252 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char, Simd<float, 64, 0> >", file: !12, line: 101, baseType: !253)264 !253 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char>", scope: !247, file: !12, line: 86, baseType: !254)265 !254 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Simd<unsigned char, 0, 0>", file: !12, line: 83, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !255, identifier: "_ZTS4SimdIhLi0ELi0EE")266 !255 = !{!256, !218, !54}267 !256 = !DITemplateTypeParameter(name: "Lane", type: !117)268 !257 = !DIDerivedType(tag: DW_TAG_typedef, name: "svuint8_t", file: !12, line: 22, baseType: !258)269 !258 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVUint8_t", file: !12, baseType: !259)270 !259 = !DICompositeType(tag: DW_TAG_array_type, baseType: !117, flags: DIFlagVector, elements: !260)271 !260 = !{!261}272 !261 = !DISubrange(lowerBound: 0, upperBound: !DIExpression(DW_OP_constu, 8, DW_OP_bregx, 46, 0, DW_OP_mul, DW_OP_constu, 1, DW_OP_minus))273 !262 = !DITemplateTypeParameter(name: "V", type: !64)274 !263 = !DILocalVariable(name: "hi", arg: 1, scope: !264, file: !12, line: 248, type: !259)275 !264 = distinct !DISubprogram(name: "CombineShiftRightBytes<8, __SVUint8_t>", linkageName: "_Z22CombineShiftRightBytesILi8Eu11__SVUint8_tET0_S1_S1_", scope: !12, file: !12, line: 248, type: !265, scopeLine: 248, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !266, retainedNodes: !267, keyInstructions: true)276 !265 = !DISubroutineType(types: !268)277 !266 = !{!283, !284}278 !267 = !{!263, !269, !270, !271, !272, !273, !274, !275, !276}279 !268 = !{!259, !259, !259}280 !269 = !DILocalVariable(name: "lo", arg: 2, scope: !264, file: !12, line: 248, type: !259)281 !270 = !DILocalVariable(name: "__trans_tmp_33", scope: !264, file: !12, line: 249, type: !257)282 !271 = !DILocalVariable(name: "__trans_tmp_15", scope: !264, file: !12, line: 249, type: !257)283 !272 = !DILocalVariable(name: "__trans_tmp_32", scope: !264, file: !12, line: 250, type: !257)284 !273 = !DILocalVariable(name: "d8", scope: !264, file: !12, line: 251, type: !277)285 !274 = !DILocalVariable(name: "__trans_tmp_16", scope: !264, file: !12, line: 252, type: !114)286 !275 = !DILocalVariable(name: "lo_down", scope: !264, file: !12, line: 254, type: !257)287 !276 = !DILocalVariable(name: "__trans_tmp_34", scope: !264, file: !12, line: 255, type: !114)288 !277 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char, Simd<char, 0, 0> >", file: !12, line: 101, baseType: !278)289 !278 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char>", scope: !279, file: !12, line: 86, baseType: !254)290 !279 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "Simd<char, 0, 0>", file: !12, line: 83, size: 8, flags: DIFlagTypePassByValue, elements: !50, templateParams: !280, identifier: "_ZTS4SimdIcLi0ELi0EE")291 !280 = !{!281, !218, !54}292 !281 = !DITemplateTypeParameter(name: "Lane", type: !282)293 !282 = !DIBasicType(name: "char", size: 8, encoding: DW_ATE_unsigned_char)294 !283 = !DITemplateValueParameter(name: "kBytes", type: !24, value: i32 8)295 !284 = !DITemplateTypeParameter(name: "V", type: !259)296 !285 = !DILocalVariable(name: "hi", arg: 1, scope: !286, file: !12, line: 216, type: !257)297 !286 = distinct !DISubprogram(name: "Ext<8>", linkageName: "_Z3ExtILi8EEu11__SVUint8_tS0_S0_", scope: !12, file: !12, line: 216, type: !287, scopeLine: 216, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !288, retainedNodes: !289, keyInstructions: true)298 !287 = !DISubroutineType(types: !290)299 !288 = !{!292}300 !289 = !{!285, !291}301 !290 = !{!257, !257, !257}302 !291 = !DILocalVariable(name: "lo", arg: 2, scope: !286, file: !12, line: 216, type: !257)303 !292 = !DITemplateValueParameter(name: "kIndex", type: !24, value: i32 8)304 !293 = !DILocalVariable(name: "a", arg: 1, scope: !294, file: !12, line: 180, type: !47)305 !294 = distinct !DISubprogram(name: "Min<__SVFloat16_t>", linkageName: "_Z3MinIu13__SVFloat16_tET_S1_S1_", scope: !12, file: !12, line: 180, type: !295, scopeLine: 180, flags: DIFlagPrototyped | DIFlagAllCallsDescribed, spFlags: DISPFlagDefinition | DISPFlagOptimized, unit: !3, templateParams: !296, retainedNodes: !297, keyInstructions: true)306 !295 = !DISubroutineType(types: !298)307 !296 = !{!166}308 !297 = !{!293, !299, !300, !301, !302, !303, !304}309 !298 = !{!47, !47, !47}310 !299 = !DILocalVariable(name: "b", arg: 2, scope: !294, file: !12, line: 180, type: !47)311 !300 = !DILocalVariable(name: "__trans_tmp_36", scope: !294, file: !12, line: 181, type: !45)312 !301 = !DILocalVariable(name: "__trans_tmp_25", scope: !294, file: !12, line: 181, type: !45)313 !302 = !DILocalVariable(name: "__trans_tmp_27", scope: !294, file: !12, line: 182, type: !114)314 !303 = !DILocalVariable(name: "__trans_tmp_24", scope: !294, file: !12, line: 183, type: !114)315 !304 = !DILocalVariable(name: "__trans_tmp_19", scope: !294, file: !12, line: 184, type: !114)316 !308 = distinct !DILocation(line: 315, column: 12, scope: !221, inlinedAt: !225)317 !309 = distinct !DILocation(line: 268, column: 21, scope: !227, inlinedAt: !308)318 !311 = distinct !DILocation(line: 254, column: 18, scope: !264, inlinedAt: !309)319 !312 = !DILocation(line: 217, column: 10, scope: !286, inlinedAt: !311, atomGroup: 1, atomRank: 2)320 !313 = !DILocation(line: 257, column: 20, scope: !264, inlinedAt: !309, atomGroup: 5, atomRank: 2)321 !314 = !DILocation(line: 0, scope: !294, inlinedAt: !315)322 !315 = distinct !DILocation(line: 331, column: 22, scope: !122, inlinedAt: !201)323 !316 = !DILocation(line: 185, column: 20, scope: !294, inlinedAt: !315)324 !317 = !DILocation(line: 403, column: 1, scope: !2, atomGroup: 19449, atomRank: 1)325 326...327---328name: _Z10Sort16RowsILi6EEv12SharedTraitsI10TraitsLaneEP22Trans_NS_hwy_float16_tiS4_329body: |330 bb.0:331 liveins: $x1, $z0, $z1, $p0332 333 $z30 = LDR_ZXI $x1, -14334 $z31 = LDR_ZXI $x1, -13335 $z23 = ORR_ZZZ $z30, $z30336 renamable $z2 = EXT_ZZI_B renamable $z30_z31, 8, debug-location !312337 renamable $z7 = SEL_ZPZZ_B renamable $p0, renamable $z0, killed renamable $z1, debug-location !313338 DBG_VALUE $z30, $noreg, !129, !DIExpression(), debug-location !200339 renamable $p3 = nofpexcept FCMGT_PPzZZ_H renamable $p0, renamable $z0, undef renamable $z1, debug-location !316340 DBG_VALUE $z30_z31, $noreg, !129, !DIExpression(), debug-location !200341 DBG_VALUE $z30_z31, $noreg, !293, !DIExpression(), debug-location !314342 RET undef $lr, debug-location !317343...344 345