mirror of
https://github.com/RPCS3/llvm-mirror.git
synced 2024-10-21 20:12:56 +02:00
fb3abba237
Currently each Function points to a DISubprogram and DISubprogram has a scope field. For member functions the scope is a DICompositeType. DIScopes point to the DICompileUnit to facilitate type uniquing. Distinct DISubprograms (with isDefinition: true) are not part of the type hierarchy and cannot be uniqued. This change removes the subprograms list from DICompileUnit and instead adds a pointer to the owning compile unit to distinct DISubprograms. This would make it easy for ThinLTO to strip unneeded DISubprograms and their transitively referenced debug info. Motivation ---------- Materializing DISubprograms is currently the most expensive operation when doing a ThinLTO build of clang. We want the DISubprogram to be stored in a separate Bitcode block (or the same block as the function body) so we can avoid having to expensively deserialize all DISubprograms together with the global metadata. If a function has been inlined into another subprogram we need to store a reference the block containing the inlined subprogram. Attached to https://llvm.org/bugs/show_bug.cgi?id=27284 is a python script that updates LLVM IR testcases to the new format. http://reviews.llvm.org/D19034 <rdar://problem/25256815> llvm-svn: 266446
44 lines
1.5 KiB
LLVM
44 lines
1.5 KiB
LLVM
; RUN: llc < %s -mtriple=nvptx64-nvidia-cuda | FileCheck %s
|
|
|
|
; // Bitcode int this test case is reduced version of compiled code below:
|
|
;extern "C" {
|
|
;#line 1 "/source/dir/foo.h"
|
|
;__device__ void foo() {}
|
|
;#line 2 "/source/dir/bar.cu"
|
|
;__device__ void bar() {}
|
|
;}
|
|
|
|
; CHECK: .file 1 "/source/dir{{/|\\\\}}bar.cu"
|
|
; CHECK: .file 2 "/source/dir{{/|\\\\}}foo.h"
|
|
|
|
; CHECK-LABEL: @foo
|
|
define void @foo() !dbg !4 {
|
|
bb:
|
|
ret void, !dbg !10
|
|
}
|
|
; CHECK: .loc 2 1
|
|
; CHECK: ret
|
|
|
|
; CHECK-LABEL: @bar
|
|
define void @bar() !dbg !7 {
|
|
bb:
|
|
ret void, !dbg !11
|
|
}
|
|
; CHECK: .loc 1 2
|
|
; CHECK: ret
|
|
|
|
!llvm.dbg.cu = !{!0}
|
|
!llvm.module.flags = !{!8, !9}
|
|
|
|
!0 = distinct !DICompileUnit(language: DW_LANG_C_plus_plus, file: !1, producer: "", isOptimized: false, runtimeVersion: 0, emissionKind: LineTablesOnly, enums: !2)
|
|
!1 = !DIFile(filename: "bar.cu", directory: "/source/dir")
|
|
!2 = !{}
|
|
!4 = distinct !DISubprogram(name: "foo", scope: !5, file: !5, line: 1, type: !6, isLocal: false, isDefinition: true, scopeLine: 1, flags: DIFlagPrototyped, isOptimized: false, unit: !0, variables: !2)
|
|
!5 = !DIFile(filename: "foo.h", directory: "/source/dir")
|
|
!6 = !DISubroutineType(types: !2)
|
|
!7 = distinct !DISubprogram(name: "bar", scope: !1, file: !1, line: 2, type: !6, isLocal: false, isDefinition: true, scopeLine: 2, flags: DIFlagPrototyped, isOptimized: false, unit: !0, variables: !2)
|
|
!8 = !{i32 2, !"Dwarf Version", i32 4}
|
|
!9 = !{i32 2, !"Debug Info Version", i32 3}
|
|
!10 = !DILocation(line: 1, column: 31, scope: !4)
|
|
!11 = !DILocation(line: 2, column: 31, scope: !7)
|