| # RUN: llc -start-before=aarch64-asm-printer -o - %s | FileCheck %s |
| |
| # Check that z30_z31 debug info does not crash. |
| |
| # CHECK: .Ldebug_loc0: |
| # CHECK: .byte 4 // DW_LLE_offset_pair |
| # CHECK: .uleb128 .Ltmp2-.Lfunc_begin0 // starting offset |
| # CHECK: .uleb128 .Ltmp3-.Lfunc_begin0 // ending offset |
| # CHECK: .byte 2 // Loc expr size |
| # CHECK: .byte 144 // DW_OP_regx |
| # CHECK: .byte 126 // 126 |
| # CHECK: .byte 4 // DW_LLE_offset_pair |
| # CHECK: .uleb128 .Ltmp3-.Lfunc_begin0 // starting offset |
| # CHECK: .uleb128 .Lfunc_end0-.Lfunc_begin0 // ending offset |
| # CHECK: .byte 6 // Loc expr size |
| # CHECK: .byte 144 // sub-register DW_OP_regx |
| # CHECK: .byte 94 // 94 |
| # CHECK: .byte 147 // DW_OP_piece |
| # CHECK: .byte 16 // 16 |
| # CHECK: .byte 147 // DW_OP_piece |
| # CHECK: .byte 31 // 31 |
| # CHECK: .byte 0 // DW_LLE_end_of_list |
| |
| |
| --- | |
| 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" |
| target triple = "aarch64" |
| |
| define void @_Z10Sort16RowsILi6EEv12SharedTraitsI10TraitsLaneEP22Trans_NS_hwy_float16_tiS4_(i8 %st.coerce, ptr noundef %keys, i32 noundef %0, ptr noundef %1) #2 !dbg !2 { |
| unreachable |
| } |
| |
| 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" } |
| |
| !llvm.dbg.cu = !{!3} |
| !llvm.module.flags = !{!4, !5, !6, !7, !8, !9} |
| !llvm.ident = !{!10} |
| |
| !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) |
| !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) |
| !4 = !{i32 7, !"Dwarf Version", i32 5} |
| !5 = !{i32 2, !"Debug Info Version", i32 3} |
| !6 = !{i32 1, !"wchar_size", i32 4} |
| !7 = !{i32 7, !"uwtable", i32 2} |
| !8 = !{i32 7, !"frame-pointer", i32 1} |
| !9 = !{i32 7, !"debug-info-assignment-tracking", i1 true} |
| !10 = !{!"clang version 22.0.0git (https://github.com/llvm/llvm-project.git)"} |
| !12 = !DIFile(filename: "example.cpp", directory: "/app", checksumkind: CSK_MD5, checksum: "5fbaafea0ede06ddd1ffc371aeee276e") |
| !14 = !DIFile(filename: "/app/example.cpp", directory: "/app", checksumkind: CSK_MD5, checksum: "5fbaafea0ede06ddd1ffc371aeee276e") |
| !17 = !DIBasicType(name: "__fp16", size: 16, encoding: DW_ATE_float) |
| !18 = !DISubroutineType(types: !21) |
| !19 = !{!120} |
| !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} |
| !21 = !{null, !22, !23, !24, !23} |
| !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") |
| !23 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !55, size: 64) |
| !24 = !DIBasicType(name: "int", size: 32, encoding: DW_ATE_signed) |
| !25 = !{!27} |
| !26 = !{!76} |
| !27 = !DIDerivedType(tag: DW_TAG_inheritance, scope: !22, baseType: !28, extraData: i32 0) |
| !28 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "TraitsLane", file: !12, line: 325, size: 8, flags: DIFlagTypePassByValue, elements: !29, identifier: "_ZTS10TraitsLane") |
| !29 = !{!30, !31, !32, !33} |
| !30 = !DIDerivedType(tag: DW_TAG_inheritance, scope: !28, baseType: !34, extraData: i32 0) |
| !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) |
| !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) |
| !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) |
| !34 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "KeyLane", file: !12, line: 307, size: 8, flags: DIFlagTypePassByValue, elements: !35, identifier: "_ZTS7KeyLane") |
| !35 = !{!36, !37, !38} |
| !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) |
| !37 = !DISubprogram(name: "SwapAdjacentPairs", linkageName: "_ZN7KeyLane17SwapAdjacentPairsEu13__SVFloat32_t", scope: !34, file: !12, line: 314, type: !58, scopeLine: 314, flags: DIFlagPrototyped, spFlags: DISPFlagOptimized) |
| !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) |
| !39 = !DISubroutineType(types: !40) |
| !40 = !{!41, !42, !43, !41} |
| !41 = !DIDerivedType(tag: DW_TAG_typedef, name: "Vec<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 270, baseType: !44) |
| !42 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !34, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !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") |
| !44 = !DIDerivedType(tag: DW_TAG_typedef, name: "VFromD<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 142, baseType: !45) |
| !45 = !DIDerivedType(tag: DW_TAG_typedef, name: "svfloat16_t", file: !12, line: 26, baseType: !46) |
| !46 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVFloat16_t", file: !12, baseType: !47) |
| !47 = !DICompositeType(tag: DW_TAG_array_type, baseType: !17, flags: DIFlagVector, elements: !48) |
| !48 = !{!49} |
| !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)) |
| !50 = !{} |
| !51 = !{!52, !53, !54} |
| !52 = !DITemplateTypeParameter(name: "Lane", type: !55) |
| !53 = !DITemplateValueParameter(type: !24, value: i32 1) |
| !54 = !DITemplateValueParameter(name: "kPow2", type: !24, value: i32 0) |
| !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") |
| !56 = !{!57} |
| !57 = !DIDerivedType(tag: DW_TAG_member, name: "native", scope: !55, file: !12, line: 7, baseType: !17, size: 16) |
| !58 = !DISubroutineType(types: !59) |
| !59 = !{!60, !42, !60} |
| !60 = !DIDerivedType(tag: DW_TAG_typedef, name: "Vec<Simd<float, 0, 0> >", file: !12, line: 270, baseType: !61) |
| !61 = !DIDerivedType(tag: DW_TAG_typedef, name: "VFromD<Simd<float, 0, 0> >", file: !12, line: 142, baseType: !62) |
| !62 = !DIDerivedType(tag: DW_TAG_typedef, name: "svfloat32_t", file: !12, line: 27, baseType: !63) |
| !63 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVFloat32_t", file: !12, baseType: !64) |
| !64 = !DICompositeType(tag: DW_TAG_array_type, baseType: !65, flags: DIFlagVector, elements: !66) |
| !65 = !DIBasicType(name: "float", size: 32, encoding: DW_ATE_float) |
| !66 = !{!67} |
| !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)) |
| !68 = !DISubroutineType(types: !69) |
| !69 = !{!41, !42, !43, !41, !41} |
| !70 = !DISubroutineType(types: !71) |
| !71 = !{null, !72, !43, !73, !73} |
| !72 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !28, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !73 = !DIDerivedType(tag: DW_TAG_reference_type, baseType: !41, size: 64) |
| !74 = !DISubroutineType(types: !75) |
| !75 = !{!41, !72, !43, !41} |
| !76 = !DITemplateTypeParameter(name: "Base", type: !28) |
| !77 = !DILocalVariable(name: "st", arg: 1, scope: !2, file: !12, line: 369, type: !22) |
| !78 = !DILocalVariable(name: "keys", arg: 2, scope: !2, file: !12, line: 369, type: !23) |
| !79 = !DILocalVariable(arg: 3, scope: !2, file: !12, line: 369, type: !24) |
| !80 = !DILocalVariable(arg: 4, scope: !2, file: !12, line: 370, type: !23) |
| !81 = !DILocalVariable(name: "d", scope: !2, file: !12, line: 371, type: !106) |
| !82 = !DILocalVariable(name: "v8", scope: !2, file: !12, line: 373, type: !112) |
| !83 = !DILocalVariable(name: "v9", scope: !2, file: !12, line: 373, type: !112) |
| !84 = !DILocalVariable(name: "va", scope: !2, file: !12, line: 373, type: !112) |
| !85 = !DILocalVariable(name: "vb", scope: !2, file: !12, line: 373, type: !112) |
| !86 = !DILocalVariable(name: "vc", scope: !2, file: !12, line: 373, type: !112) |
| !87 = !DILocalVariable(name: "vd", scope: !2, file: !12, line: 373, type: !112) |
| !88 = !DILocalVariable(name: "ve", scope: !2, file: !12, line: 373, type: !112) |
| !89 = !DILocalVariable(name: "vf", scope: !2, file: !12, line: 373, type: !112) |
| !90 = !DILocalVariable(name: "v2", scope: !2, file: !12, line: 373, type: !112) |
| !91 = !DILocalVariable(name: "v4", scope: !2, file: !12, line: 373, type: !112) |
| !92 = !DILocalVariable(name: "v7", scope: !2, file: !12, line: 373, type: !112) |
| !93 = !DILocalVariable(name: "v0", scope: !2, file: !12, line: 374, type: !112) |
| !94 = !DILocalVariable(name: "v3", scope: !2, file: !12, line: 375, type: !112) |
| !95 = !DILocalVariable(name: "v5", scope: !2, file: !12, line: 376, type: !112) |
| !96 = !DILocalVariable(name: "v6", scope: !2, file: !12, line: 377, type: !112) |
| !97 = !DILocalVariable(name: "kIota", scope: !2, file: !12, line: 378, type: !112) |
| !98 = !DILocalVariable(name: "m8", scope: !2, file: !12, line: 379, type: !113) |
| !99 = !DILocalVariable(name: "m9", scope: !2, file: !12, line: 380, type: !113) |
| !100 = !DILocalVariable(name: "ma", scope: !2, file: !12, line: 381, type: !113) |
| !101 = !DILocalVariable(name: "mb", scope: !2, file: !12, line: 382, type: !113) |
| !102 = !DILocalVariable(name: "mc", scope: !2, file: !12, line: 383, type: !113) |
| !103 = !DILocalVariable(name: "md", scope: !2, file: !12, line: 384, type: !113) |
| !104 = !DILocalVariable(name: "me", scope: !2, file: !12, line: 385, type: !113) |
| !105 = !DILocalVariable(name: "mf", scope: !2, file: !12, line: 386, type: !113) |
| !106 = !DIDerivedType(tag: DW_TAG_typedef, name: "CappedTag<Trans_NS_hwy_float16_t, 6>", file: !12, line: 97, baseType: !107) |
| !107 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !108, file: !12, line: 89, baseType: !43) |
| !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") |
| !109 = !{!110, !111} |
| !110 = !DITemplateTypeParameter(name: "T", type: !55) |
| !111 = !DITemplateValueParameter(name: "N", type: !24, value: i32 1) |
| !112 = !DIDerivedType(tag: DW_TAG_typedef, name: "V", scope: !2, file: !12, line: 372, baseType: !41) |
| !113 = !DIDerivedType(tag: DW_TAG_typedef, name: "Mask<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 271, baseType: !114) |
| !114 = !DIDerivedType(tag: DW_TAG_typedef, name: "svbool_t", file: !12, line: 28, baseType: !115) |
| !115 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVBool_t", file: !12, baseType: !116) |
| !116 = !DICompositeType(tag: DW_TAG_array_type, baseType: !117, flags: DIFlagVector, elements: !118) |
| !117 = !DIBasicType(name: "unsigned char", size: 8, encoding: DW_ATE_unsigned_char) |
| !118 = !{!119} |
| !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)) |
| !120 = !DITemplateValueParameter(name: "kKeysPerRow", type: !24, value: i32 6) |
| !121 = !DILocalVariable(name: "this", arg: 1, scope: !122, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !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) |
| !123 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !28, size: 64) |
| !124 = !{!121, !125, !126, !127, !128, !129, !130, !131, !132} |
| !125 = !DILocalVariable(name: "d", arg: 2, scope: !122, file: !12, line: 326, type: !43) |
| !126 = !DILocalVariable(name: "a", arg: 3, scope: !122, file: !12, line: 327, type: !73) |
| !127 = !DILocalVariable(name: "b", arg: 4, scope: !122, file: !12, line: 328, type: !73) |
| !128 = !DILocalVariable(name: "__trans_tmp_52", scope: !122, file: !12, line: 329, type: !41) |
| !129 = !DILocalVariable(name: "a_copy", scope: !122, file: !12, line: 329, type: !41) |
| !130 = !DILocalVariable(name: "__trans_tmp_45", scope: !122, file: !12, line: 330, type: !41) |
| !131 = !DILocalVariable(name: "__trans_tmp_53", scope: !133, file: !12, line: 334, type: !41) |
| !132 = !DILocalVariable(name: "__trans_tmp_29", scope: !134, file: !12, line: 336, type: !45) |
| !133 = distinct !DILexicalBlock(scope: !122, file: !12, line: 333, column: 5) |
| !134 = distinct !DILexicalBlock(scope: !133, file: !12, line: 335, column: 7) |
| !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) |
| !139 = !{!140, !141, !142, !143} |
| !140 = !DILocalVariable(name: "this", arg: 1, scope: !137, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !141 = !DILocalVariable(name: "d", arg: 2, scope: !137, file: !12, line: 344, type: !43) |
| !142 = !DILocalVariable(name: "v", arg: 3, scope: !137, file: !12, line: 345, type: !41) |
| !143 = !DILocalVariable(name: "__trans_tmp_48", scope: !137, file: !12, line: 346, type: !41) |
| !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) |
| !145 = distinct !DILocation(line: 388, column: 3, scope: !2) |
| !146 = !DISubroutineType(types: !149) |
| !147 = !{!164, !165, !166} |
| !148 = !{!151, !152, !153, !154, !155, !156, !157, !158, !159, !160, !161, !162, !163} |
| !149 = !{null, !22, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150, !150} |
| !150 = !DIDerivedType(tag: DW_TAG_reference_type, baseType: !47, size: 64) |
| !151 = !DILocalVariable(name: "st", arg: 1, scope: !144, file: !12, line: 286, type: !22) |
| !152 = !DILocalVariable(name: "v0", arg: 2, scope: !144, file: !12, line: 286, type: !150) |
| !153 = !DILocalVariable(name: "v2", arg: 3, scope: !144, file: !12, line: 286, type: !150) |
| !154 = !DILocalVariable(name: "v5", arg: 4, scope: !144, file: !12, line: 286, type: !150) |
| !155 = !DILocalVariable(name: "v6", arg: 5, scope: !144, file: !12, line: 287, type: !150) |
| !156 = !DILocalVariable(name: "v7", arg: 6, scope: !144, file: !12, line: 287, type: !150) |
| !157 = !DILocalVariable(name: "v9", arg: 7, scope: !144, file: !12, line: 287, type: !150) |
| !158 = !DILocalVariable(name: "va", arg: 8, scope: !144, file: !12, line: 287, type: !150) |
| !159 = !DILocalVariable(name: "vb", arg: 9, scope: !144, file: !12, line: 287, type: !150) |
| !160 = !DILocalVariable(name: "vc", arg: 10, scope: !144, file: !12, line: 288, type: !150) |
| !161 = !DILocalVariable(name: "vd", arg: 11, scope: !144, file: !12, line: 288, type: !150) |
| !162 = !DILocalVariable(name: "ve", arg: 12, scope: !144, file: !12, line: 288, type: !150) |
| !163 = !DILocalVariable(name: "vf", arg: 13, scope: !144, file: !12, line: 288, type: !150) |
| !164 = !DITemplateValueParameter(type: !24, value: i32 6) |
| !165 = !DITemplateTypeParameter(name: "Traits", type: !22) |
| !166 = !DITemplateTypeParameter(name: "V", type: !47) |
| !184 = !DILocalVariable(name: "this", arg: 1, scope: !185, type: !186, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !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) |
| !186 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !22, size: 64) |
| !187 = !DISubroutineType(types: !191) |
| !188 = !{!193} |
| !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) |
| !190 = !{!184, !194, !195, !196, !197} |
| !191 = !{!41, !192, !43, !41} |
| !192 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !22, size: 64, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !193 = !DITemplateTypeParameter(name: "D", type: !43) |
| !194 = !DILocalVariable(name: "d", arg: 2, scope: !185, file: !12, line: 273, type: !43) |
| !195 = !DILocalVariable(name: "v", arg: 3, scope: !185, file: !12, line: 273, type: !41) |
| !196 = !DILocalVariable(name: "base", scope: !185, file: !12, line: 274, type: !28) |
| !197 = !DILocalVariable(name: "swapped", scope: !185, file: !12, line: 275, type: !41) |
| !200 = !DILocation(line: 0, scope: !122, inlinedAt: !201) |
| !201 = distinct !DILocation(line: 358, column: 5, scope: !202, inlinedAt: !203) |
| !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) |
| !203 = distinct !DILocation(line: 298, column: 11, scope: !144, inlinedAt: !145) |
| !204 = !{!205, !206, !207, !208, !209, !210, !211} |
| !205 = !DILocalVariable(name: "this", arg: 1, scope: !202, type: !123, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !206 = !DILocalVariable(name: "d", arg: 2, scope: !202, file: !12, line: 352, type: !43) |
| !207 = !DILocalVariable(name: "v", arg: 3, scope: !202, file: !12, line: 353, type: !41) |
| !208 = !DILocalVariable(name: "__trans_tmp_42", scope: !202, file: !12, line: 354, type: !41) |
| !209 = !DILocalVariable(name: "__trans_tmp_39", scope: !202, file: !12, line: 354, type: !41) |
| !210 = !DILocalVariable(name: "dw", scope: !202, file: !12, line: 355, type: !212) |
| !211 = !DILocalVariable(name: "__trans_tmp_51", scope: !219, file: !12, line: 360, type: !44) |
| !212 = !DIDerivedType(tag: DW_TAG_typedef, name: "RepartitionToWide<Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 103, baseType: !213) |
| !213 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<float, Simd<Trans_NS_hwy_float16_t, 1, 0> >", file: !12, line: 101, baseType: !214) |
| !214 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<float>", scope: !43, file: !12, line: 86, baseType: !215) |
| !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") |
| !216 = !{!217, !218, !54} |
| !217 = !DITemplateTypeParameter(name: "Lane", type: !65) |
| !218 = !DITemplateValueParameter(type: !24, value: i32 0) |
| !219 = distinct !DILexicalBlock(scope: !202, file: !12, line: 359, column: 5) |
| !220 = !DILocalVariable(name: "this", arg: 1, scope: !221, type: !222, flags: DIFlagArtificial | DIFlagObjectPointer) |
| !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) |
| !222 = !DIDerivedType(tag: DW_TAG_pointer_type, baseType: !34, size: 64) |
| !223 = !{!220, !224} |
| !224 = !DILocalVariable(name: "v", arg: 2, scope: !221, file: !12, line: 314, type: !60) |
| !225 = distinct !DILocation(line: 357, column: 38, scope: !202, inlinedAt: !203) |
| !226 = !DILocalVariable(name: "v", arg: 1, scope: !227, file: !12, line: 264, type: !64) |
| !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) |
| !228 = !DISubroutineType(types: !231) |
| !229 = !{!262} |
| !230 = !{!226, !232, !233, !234} |
| !231 = !{!64, !64} |
| !232 = !DILocalVariable(name: "d", scope: !227, file: !12, line: 265, type: !235) |
| !233 = !DILocalVariable(name: "d8", scope: !227, file: !12, line: 266, type: !252) |
| !234 = !DILocalVariable(name: "v8", scope: !227, file: !12, line: 267, type: !257) |
| !235 = !DIDerivedType(tag: DW_TAG_typedef, name: "DFromV<__SVFloat32_t>", file: !12, line: 108, baseType: !236) |
| !236 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !237, file: !12, line: 116, baseType: !238) |
| !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") |
| !238 = !DIDerivedType(tag: DW_TAG_typedef, name: "ScalableTag<float>", file: !12, line: 95, baseType: !241) |
| !239 = !{!240} |
| !240 = !DITemplateTypeParameter(type: !64) |
| !241 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !242, file: !12, line: 92, baseType: !243) |
| !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") |
| !243 = !DIDerivedType(tag: DW_TAG_typedef, name: "type", scope: !246, file: !12, line: 89, baseType: !247) |
| !244 = !{!245} |
| !245 = !DITemplateTypeParameter(name: "T", type: !65) |
| !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") |
| !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") |
| !248 = !{!245, !249} |
| !249 = !DITemplateValueParameter(name: "N", type: !24, value: i32 64) |
| !250 = !{!217, !251, !54} |
| !251 = !DITemplateValueParameter(type: !24, value: i32 64) |
| !252 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char, Simd<float, 64, 0> >", file: !12, line: 101, baseType: !253) |
| !253 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char>", scope: !247, file: !12, line: 86, baseType: !254) |
| !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") |
| !255 = !{!256, !218, !54} |
| !256 = !DITemplateTypeParameter(name: "Lane", type: !117) |
| !257 = !DIDerivedType(tag: DW_TAG_typedef, name: "svuint8_t", file: !12, line: 22, baseType: !258) |
| !258 = !DIDerivedType(tag: DW_TAG_typedef, name: "__SVUint8_t", file: !12, baseType: !259) |
| !259 = !DICompositeType(tag: DW_TAG_array_type, baseType: !117, flags: DIFlagVector, elements: !260) |
| !260 = !{!261} |
| !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)) |
| !262 = !DITemplateTypeParameter(name: "V", type: !64) |
| !263 = !DILocalVariable(name: "hi", arg: 1, scope: !264, file: !12, line: 248, type: !259) |
| !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) |
| !265 = !DISubroutineType(types: !268) |
| !266 = !{!283, !284} |
| !267 = !{!263, !269, !270, !271, !272, !273, !274, !275, !276} |
| !268 = !{!259, !259, !259} |
| !269 = !DILocalVariable(name: "lo", arg: 2, scope: !264, file: !12, line: 248, type: !259) |
| !270 = !DILocalVariable(name: "__trans_tmp_33", scope: !264, file: !12, line: 249, type: !257) |
| !271 = !DILocalVariable(name: "__trans_tmp_15", scope: !264, file: !12, line: 249, type: !257) |
| !272 = !DILocalVariable(name: "__trans_tmp_32", scope: !264, file: !12, line: 250, type: !257) |
| !273 = !DILocalVariable(name: "d8", scope: !264, file: !12, line: 251, type: !277) |
| !274 = !DILocalVariable(name: "__trans_tmp_16", scope: !264, file: !12, line: 252, type: !114) |
| !275 = !DILocalVariable(name: "lo_down", scope: !264, file: !12, line: 254, type: !257) |
| !276 = !DILocalVariable(name: "__trans_tmp_34", scope: !264, file: !12, line: 255, type: !114) |
| !277 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char, Simd<char, 0, 0> >", file: !12, line: 101, baseType: !278) |
| !278 = !DIDerivedType(tag: DW_TAG_typedef, name: "Repartition<unsigned char>", scope: !279, file: !12, line: 86, baseType: !254) |
| !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") |
| !280 = !{!281, !218, !54} |
| !281 = !DITemplateTypeParameter(name: "Lane", type: !282) |
| !282 = !DIBasicType(name: "char", size: 8, encoding: DW_ATE_unsigned_char) |
| !283 = !DITemplateValueParameter(name: "kBytes", type: !24, value: i32 8) |
| !284 = !DITemplateTypeParameter(name: "V", type: !259) |
| !285 = !DILocalVariable(name: "hi", arg: 1, scope: !286, file: !12, line: 216, type: !257) |
| !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) |
| !287 = !DISubroutineType(types: !290) |
| !288 = !{!292} |
| !289 = !{!285, !291} |
| !290 = !{!257, !257, !257} |
| !291 = !DILocalVariable(name: "lo", arg: 2, scope: !286, file: !12, line: 216, type: !257) |
| !292 = !DITemplateValueParameter(name: "kIndex", type: !24, value: i32 8) |
| !293 = !DILocalVariable(name: "a", arg: 1, scope: !294, file: !12, line: 180, type: !47) |
| !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) |
| !295 = !DISubroutineType(types: !298) |
| !296 = !{!166} |
| !297 = !{!293, !299, !300, !301, !302, !303, !304} |
| !298 = !{!47, !47, !47} |
| !299 = !DILocalVariable(name: "b", arg: 2, scope: !294, file: !12, line: 180, type: !47) |
| !300 = !DILocalVariable(name: "__trans_tmp_36", scope: !294, file: !12, line: 181, type: !45) |
| !301 = !DILocalVariable(name: "__trans_tmp_25", scope: !294, file: !12, line: 181, type: !45) |
| !302 = !DILocalVariable(name: "__trans_tmp_27", scope: !294, file: !12, line: 182, type: !114) |
| !303 = !DILocalVariable(name: "__trans_tmp_24", scope: !294, file: !12, line: 183, type: !114) |
| !304 = !DILocalVariable(name: "__trans_tmp_19", scope: !294, file: !12, line: 184, type: !114) |
| !308 = distinct !DILocation(line: 315, column: 12, scope: !221, inlinedAt: !225) |
| !309 = distinct !DILocation(line: 268, column: 21, scope: !227, inlinedAt: !308) |
| !311 = distinct !DILocation(line: 254, column: 18, scope: !264, inlinedAt: !309) |
| !312 = !DILocation(line: 217, column: 10, scope: !286, inlinedAt: !311, atomGroup: 1, atomRank: 2) |
| !313 = !DILocation(line: 257, column: 20, scope: !264, inlinedAt: !309, atomGroup: 5, atomRank: 2) |
| !314 = !DILocation(line: 0, scope: !294, inlinedAt: !315) |
| !315 = distinct !DILocation(line: 331, column: 22, scope: !122, inlinedAt: !201) |
| !316 = !DILocation(line: 185, column: 20, scope: !294, inlinedAt: !315) |
| !317 = !DILocation(line: 403, column: 1, scope: !2, atomGroup: 19449, atomRank: 1) |
| |
| ... |
| --- |
| name: _Z10Sort16RowsILi6EEv12SharedTraitsI10TraitsLaneEP22Trans_NS_hwy_float16_tiS4_ |
| body: | |
| bb.0: |
| liveins: $x1, $z0, $z1, $p0 |
| |
| $z30 = LDR_ZXI $x1, -14 |
| $z31 = LDR_ZXI $x1, -13 |
| $z23 = ORR_ZZZ $z30, $z30 |
| renamable $z2 = EXT_ZZI_B renamable $z30_z31, 8, debug-location !312 |
| renamable $z7 = SEL_ZPZZ_B renamable $p0, renamable $z0, killed renamable $z1, debug-location !313 |
| DBG_VALUE $z30, $noreg, !129, !DIExpression(), debug-location !200 |
| renamable $p3 = nofpexcept FCMGT_PPzZZ_H renamable $p0, renamable $z0, undef renamable $z1, debug-location !316 |
| DBG_VALUE $z30_z31, $noreg, !129, !DIExpression(), debug-location !200 |
| DBG_VALUE $z30_z31, $noreg, !293, !DIExpression(), debug-location !314 |
| RET undef $lr, debug-location !317 |
| ... |
| |
