X7ROOT File Manager
Current Path:
/opt/golang/1.19.4/src/runtime
opt
/
golang
/
1.19.4
/
src
/
runtime
/
📁
..
📄
HACKING.md
(15.29 KB)
📄
Makefile
(178 B)
📄
abi_test.go
(2.83 KB)
📄
alg.go
(9.45 KB)
📄
align_runtime_test.go
(2.73 KB)
📄
align_test.go
(5.26 KB)
📁
asan
📄
asan.go
(1.55 KB)
📄
asan0.go
(761 B)
📄
asan_amd64.s
(2.46 KB)
📄
asan_arm64.s
(2.15 KB)
📄
asan_riscv64.s
(1.92 KB)
📄
asm.s
(278 B)
📄
asm_386.s
(40.43 KB)
📄
asm_amd64.h
(411 B)
📄
asm_amd64.s
(57.44 KB)
📄
asm_arm.s
(30.2 KB)
📄
asm_arm64.s
(41.41 KB)
📄
asm_loong64.s
(21.79 KB)
📄
asm_mips64x.s
(22.43 KB)
📄
asm_mipsx.s
(24.41 KB)
📄
asm_ppc64x.h
(1023 B)
📄
asm_ppc64x.s
(35.21 KB)
📄
asm_riscv64.s
(26.43 KB)
📄
asm_s390x.s
(26.08 KB)
📄
asm_wasm.s
(9.38 KB)
📄
atomic_arm64.s
(259 B)
📄
atomic_loong64.s
(245 B)
📄
atomic_mips64x.s
(300 B)
📄
atomic_mipsx.s
(262 B)
📄
atomic_pointer.go
(2.62 KB)
📄
atomic_ppc64x.s
(437 B)
📄
atomic_riscv64.s
(275 B)
📄
auxv_none.go
(298 B)
📄
callers_test.go
(8.44 KB)
📁
cgo
📄
cgo.go
(2 KB)
📄
cgo_mmap.go
(2.4 KB)
📄
cgo_ppc64x.go
(418 B)
📄
cgo_sigaction.go
(3.28 KB)
📄
cgocall.go
(19.12 KB)
📄
cgocallback.go
(317 B)
📄
cgocheck.go
(6.86 KB)
📄
chan.go
(23.73 KB)
📄
chan_test.go
(23.37 KB)
📄
chanbarrier_test.go
(1.4 KB)
📄
checkptr.go
(3.29 KB)
📄
checkptr_test.go
(2.73 KB)
📄
closure_test.go
(937 B)
📄
compiler.go
(410 B)
📄
complex.go
(1.59 KB)
📄
complex_test.go
(1.05 KB)
📄
conv_wasm_test.go
(2.96 KB)
📄
cpuflags.go
(810 B)
📄
cpuflags_amd64.go
(533 B)
📄
cpuflags_arm64.go
(334 B)
📄
cpuprof.go
(7.78 KB)
📄
cputicks.go
(449 B)
📄
crash_cgo_test.go
(18.14 KB)
📄
crash_test.go
(21.77 KB)
📄
crash_unix_test.go
(8.39 KB)
📁
debug
📄
debug.go
(3.23 KB)
📄
debug_test.go
(7.98 KB)
📄
debugcall.go
(6.19 KB)
📄
debuglog.go
(17.87 KB)
📄
debuglog_off.go
(357 B)
📄
debuglog_on.go
(1.09 KB)
📄
debuglog_test.go
(4.56 KB)
📄
defer_test.go
(11.56 KB)
📄
defs1_linux.go
(845 B)
📄
defs1_netbsd_386.go
(2.83 KB)
📄
defs1_netbsd_amd64.go
(3.06 KB)
📄
defs1_netbsd_arm.go
(2.94 KB)
📄
defs1_netbsd_arm64.go
(3.17 KB)
📄
defs1_solaris_amd64.go
(4 KB)
📄
defs2_linux.go
(3.51 KB)
📄
defs3_linux.go
(1.09 KB)
📄
defs_aix.go
(4.16 KB)
📄
defs_aix_ppc64.go
(3.61 KB)
📄
defs_arm_linux.go
(2.67 KB)
📄
defs_darwin.go
(3.78 KB)
📄
defs_darwin_amd64.go
(6.07 KB)
📄
defs_darwin_arm64.go
(3.89 KB)
📄
defs_dragonfly.go
(2.59 KB)
📄
defs_dragonfly_amd64.go
(3.29 KB)
📄
defs_freebsd.go
(3.82 KB)
📄
defs_freebsd_386.go
(4.36 KB)
📄
defs_freebsd_amd64.go
(4.63 KB)
📄
defs_freebsd_arm.go
(3.69 KB)
📄
defs_freebsd_arm64.go
(4.01 KB)
📄
defs_illumos_amd64.go
(285 B)
📄
defs_linux.go
(3.25 KB)
📄
defs_linux_386.go
(4.42 KB)
📄
defs_linux_amd64.go
(4.93 KB)
📄
defs_linux_arm.go
(4.11 KB)
📄
defs_linux_arm64.go
(3.86 KB)
📄
defs_linux_loong64.go
(3.68 KB)
📄
defs_linux_mips64x.go
(3.85 KB)
📄
defs_linux_mipsx.go
(3.83 KB)
📄
defs_linux_ppc64.go
(3.93 KB)
📄
defs_linux_ppc64le.go
(3.93 KB)
📄
defs_linux_riscv64.go
(4.06 KB)
📄
defs_linux_s390x.go
(3.41 KB)
📄
defs_netbsd.go
(2.72 KB)
📄
defs_netbsd_386.go
(855 B)
📄
defs_netbsd_amd64.go
(1.01 KB)
📄
defs_netbsd_arm.go
(764 B)
📄
defs_openbsd.go
(3.09 KB)
📄
defs_openbsd_386.go
(2.87 KB)
📄
defs_openbsd_amd64.go
(3.07 KB)
📄
defs_openbsd_arm.go
(2.99 KB)
📄
defs_openbsd_arm64.go
(2.74 KB)
📄
defs_openbsd_mips64.go
(2.64 KB)
📄
defs_plan9_386.go
(1.63 KB)
📄
defs_plan9_amd64.go
(1.82 KB)
📄
defs_plan9_arm.go
(1.73 KB)
📄
defs_solaris.go
(3.31 KB)
📄
defs_solaris_amd64.go
(1004 B)
📄
defs_windows.go
(2.09 KB)
📄
defs_windows_386.go
(1.98 KB)
📄
defs_windows_amd64.go
(2.71 KB)
📄
defs_windows_arm.go
(2.11 KB)
📄
defs_windows_arm64.go
(2.63 KB)
📄
duff_386.s
(8.24 KB)
📄
duff_amd64.s
(5.62 KB)
📄
duff_arm.s
(7.11 KB)
📄
duff_arm64.s
(5.27 KB)
📄
duff_loong64.s
(12 KB)
📄
duff_mips64x.s
(11.28 KB)
📄
duff_ppc64x.s
(7.06 KB)
📄
duff_riscv64.s
(11.4 KB)
📄
duff_s390x.s
(507 B)
📄
env_plan9.go
(3 KB)
📄
env_posix.go
(1.79 KB)
📄
env_test.go
(1.16 KB)
📄
error.go
(9.21 KB)
📄
example_test.go
(1.55 KB)
📄
export_aix_test.go
(234 B)
📄
export_arm_test.go
(226 B)
📄
export_darwin_test.go
(382 B)
📄
export_debug_amd64_test.go
(3.6 KB)
📄
export_debug_arm64_test.go
(3.49 KB)
📄
export_debug_test.go
(5.05 KB)
📄
export_debuglog_test.go
(1.24 KB)
📄
export_linux_test.go
(550 B)
📄
export_mmap_test.go
(429 B)
📄
export_pipe2_test.go
(310 B)
📄
export_pipe_test.go
(219 B)
📄
export_solaris_test.go
(282 B)
📄
export_test.go
(38.87 KB)
📄
export_unix_test.go
(2.18 KB)
📄
export_windows_test.go
(677 B)
📄
extern.go
(13.62 KB)
📄
fastlog2.go
(1.22 KB)
📄
fastlog2_test.go
(784 B)
📄
fastlog2table.go
(904 B)
📄
float.go
(1.35 KB)
📄
float_test.go
(699 B)
📄
funcdata.h
(2.55 KB)
📄
gc_test.go
(20.04 KB)
📄
gcinfo_test.go
(5.59 KB)
📄
go_tls.h
(366 B)
📄
hash32.go
(1.58 KB)
📄
hash64.go
(1.95 KB)
📄
hash_test.go
(16.77 KB)
📄
heapdump.go
(17.65 KB)
📄
histogram.go
(6.19 KB)
📄
histogram_test.go
(3.42 KB)
📄
iface.go
(15.66 KB)
📄
iface_test.go
(7.45 KB)
📁
internal
📄
lfstack.go
(1.77 KB)
📄
lfstack_32bit.go
(532 B)
📄
lfstack_64bit.go
(2.18 KB)
📄
lfstack_test.go
(2.77 KB)
📄
libfuzzer.go
(6.5 KB)
📄
libfuzzer_amd64.s
(5.01 KB)
📄
libfuzzer_arm64.s
(3.15 KB)
📄
lock_futex.go
(5.19 KB)
📄
lock_js.go
(6.14 KB)
📄
lock_sema.go
(6.74 KB)
📄
lockrank.go
(13.26 KB)
📄
lockrank_off.go
(1.14 KB)
📄
lockrank_on.go
(9.83 KB)
📄
lockrank_test.go
(1.15 KB)
📄
malloc.go
(51.01 KB)
📄
malloc_test.go
(10.78 KB)
📄
map.go
(43.52 KB)
📄
map_benchmark_test.go
(10.48 KB)
📄
map_fast32.go
(12.72 KB)
📄
map_fast64.go
(12.91 KB)
📄
map_faststr.go
(14.3 KB)
📄
map_test.go
(27.44 KB)
📄
mbarrier.go
(12.43 KB)
📄
mbitmap.go
(66.08 KB)
📄
mcache.go
(10 KB)
📄
mcentral.go
(7.9 KB)
📄
mcheckmark.go
(2.81 KB)
📄
mem.go
(6.23 KB)
📄
mem_aix.go
(1.9 KB)
📄
mem_bsd.go
(2.03 KB)
📄
mem_darwin.go
(1.84 KB)
📄
mem_js.go
(2.25 KB)
📄
mem_linux.go
(6.15 KB)
📄
mem_plan9.go
(4.32 KB)
📄
mem_windows.go
(3.76 KB)
📄
memclr_386.s
(2.38 KB)
📄
memclr_amd64.s
(4.91 KB)
📄
memclr_arm.s
(2.6 KB)
📄
memclr_arm64.s
(3.62 KB)
📄
memclr_loong64.s
(778 B)
📄
memclr_mips64x.s
(1.72 KB)
📄
memclr_mipsx.s
(1.32 KB)
📄
memclr_plan9_386.s
(983 B)
📄
memclr_plan9_amd64.s
(511 B)
📄
memclr_ppc64x.s
(4.23 KB)
📄
memclr_riscv64.s
(978 B)
📄
memclr_s390x.s
(1.96 KB)
📄
memclr_wasm.s
(622 B)
📄
memmove_386.s
(4.42 KB)
📄
memmove_amd64.s
(12.48 KB)
📄
memmove_arm.s
(5.9 KB)
📄
memmove_arm64.s
(5.96 KB)
📄
memmove_linux_amd64_test.go
(1.6 KB)
📄
memmove_loong64.s
(1.8 KB)
📄
memmove_mips64x.s
(1.83 KB)
📄
memmove_mipsx.s
(4.4 KB)
📄
memmove_plan9_386.s
(3.06 KB)
📄
memmove_plan9_amd64.s
(3.04 KB)
📄
memmove_ppc64x.s
(4.58 KB)
📄
memmove_riscv64.s
(1.86 KB)
📄
memmove_s390x.s
(2.92 KB)
📄
memmove_test.go
(14.03 KB)
📄
memmove_wasm.s
(1.74 KB)
📁
metrics
📄
metrics.go
(18.71 KB)
📄
metrics_test.go
(14.74 KB)
📄
mfinal.go
(16.34 KB)
📄
mfinal_test.go
(6.19 KB)
📄
mfixalloc.go
(3.07 KB)
📄
mgc.go
(56.37 KB)
📄
mgclimit.go
(17.26 KB)
📄
mgclimit_test.go
(9.02 KB)
📄
mgcmark.go
(47.47 KB)
📄
mgcpacer.go
(60.12 KB)
📄
mgcpacer_test.go
(40.43 KB)
📄
mgcscavenge.go
(41.29 KB)
📄
mgcscavenge_test.go
(20.33 KB)
📄
mgcstack.go
(10.58 KB)
📄
mgcsweep.go
(27.89 KB)
📄
mgcwork.go
(12.86 KB)
📄
mheap.go
(69.14 KB)
📄
mkduff.go
(8.01 KB)
📄
mkfastlog2table.go
(3.08 KB)
📄
mkpreempt.go
(15.12 KB)
📄
mksizeclasses.go
(9.3 KB)
📄
mmap.go
(821 B)
📄
mpagealloc.go
(36.84 KB)
📄
mpagealloc_32bit.go
(3.81 KB)
📄
mpagealloc_64bit.go
(9.44 KB)
📄
mpagealloc_test.go
(32.59 KB)
📄
mpagecache.go
(5.46 KB)
📄
mpagecache_test.go
(10.79 KB)
📄
mpallocbits.go
(12.6 KB)
📄
mpallocbits_test.go
(13.69 KB)
📄
mprof.go
(38.51 KB)
📄
mranges.go
(13.64 KB)
📄
mranges_test.go
(5.68 KB)
📁
msan
📄
msan.go
(1.5 KB)
📄
msan0.go
(725 B)
📄
msan_amd64.s
(2.31 KB)
📄
msan_arm64.s
(1.99 KB)
📄
msize.go
(777 B)
📄
mspanset.go
(12.21 KB)
📄
mstats.go
(30.07 KB)
📄
mwbbuf.go
(9.28 KB)
📄
nbpipe_fcntl_libc_test.go
(470 B)
📄
nbpipe_fcntl_unix_test.go
(458 B)
📄
nbpipe_pipe.go
(405 B)
📄
nbpipe_pipe2.go
(344 B)
📄
nbpipe_pipe_test.go
(706 B)
📄
nbpipe_test.go
(1.68 KB)
📄
net_plan9.go
(645 B)
📄
netpoll.go
(18.27 KB)
📄
netpoll_aix.go
(4.83 KB)
📄
netpoll_epoll.go
(4.16 KB)
📄
netpoll_fake.go
(652 B)
📄
netpoll_kqueue.go
(4.56 KB)
📄
netpoll_os_test.go
(360 B)
📄
netpoll_solaris.go
(10.76 KB)
📄
netpoll_stub.go
(1.41 KB)
📄
netpoll_windows.go
(3.75 KB)
📄
norace_linux_test.go
(915 B)
📄
norace_test.go
(983 B)
📄
numcpu_freebsd_test.go
(381 B)
📄
os2_aix.go
(20.45 KB)
📄
os2_freebsd.go
(302 B)
📄
os2_openbsd.go
(296 B)
📄
os2_plan9.go
(1.48 KB)
📄
os2_solaris.go
(320 B)
📄
os3_plan9.go
(3.93 KB)
📄
os3_solaris.go
(17.22 KB)
📄
os_aix.go
(8.61 KB)
📄
os_android.go
(463 B)
📄
os_darwin.go
(12 KB)
📄
os_darwin_arm64.go
(416 B)
📄
os_dragonfly.go
(6.96 KB)
📄
os_freebsd.go
(11.61 KB)
📄
os_freebsd2.go
(603 B)
📄
os_freebsd_amd64.go
(658 B)
📄
os_freebsd_arm.go
(1.32 KB)
📄
os_freebsd_arm64.go
(398 B)
📄
os_freebsd_noauxv.go
(241 B)
📄
os_illumos.go
(3.93 KB)
📄
os_js.go
(3.28 KB)
📄
os_linux.go
(26.14 KB)
📄
os_linux_arm.go
(1.35 KB)
📄
os_linux_arm64.go
(556 B)
📄
os_linux_be64.go
(824 B)
📄
os_linux_generic.go
(888 B)
📄
os_linux_loong64.go
(485 B)
📄
os_linux_mips64x.go
(1.07 KB)
📄
os_linux_mipsx.go
(1.06 KB)
📄
os_linux_noauxv.go
(337 B)
📄
os_linux_novdso.go
(347 B)
📄
os_linux_ppc64x.go
(526 B)
📄
os_linux_riscv64.go
(198 B)
📄
os_linux_s390x.go
(316 B)
📄
os_linux_x86.go
(234 B)
📄
os_netbsd.go
(9.8 KB)
📄
os_netbsd_386.go
(617 B)
📄
os_netbsd_amd64.go
(614 B)
📄
os_netbsd_arm.go
(1.16 KB)
📄
os_netbsd_arm64.go
(856 B)
📄
os_nonopenbsd.go
(437 B)
📄
os_only_solaris.go
(357 B)
📄
os_openbsd.go
(6.55 KB)
📄
os_openbsd_arm.go
(749 B)
📄
os_openbsd_arm64.go
(416 B)
📄
os_openbsd_libc.go
(1.71 KB)
📄
os_openbsd_mips64.go
(416 B)
📄
os_openbsd_syscall.go
(1.27 KB)
📄
os_openbsd_syscall1.go
(441 B)
📄
os_openbsd_syscall2.go
(2.46 KB)
📄
os_plan9.go
(10.3 KB)
📄
os_plan9_arm.go
(462 B)
📄
os_solaris.go
(6.55 KB)
📄
os_windows.go
(44.43 KB)
📄
os_windows_arm.go
(511 B)
📄
os_windows_arm64.go
(339 B)
📄
panic.go
(40.25 KB)
📄
panic32.go
(4.8 KB)
📄
panic_test.go
(1.71 KB)
📄
plugin.go
(4.26 KB)
📁
pprof
📄
preempt.go
(15.21 KB)
📄
preempt_386.s
(824 B)
📄
preempt_amd64.s
(1.62 KB)
📄
preempt_arm.s
(1.48 KB)
📄
preempt_arm64.s
(1.97 KB)
📄
preempt_loong64.s
(2.35 KB)
📄
preempt_mips64x.s
(2.72 KB)
📄
preempt_mipsx.s
(2.68 KB)
📄
preempt_nonwindows.go
(290 B)
📄
preempt_ppc64x.s
(2.72 KB)
📄
preempt_riscv64.s
(2.26 KB)
📄
preempt_s390x.s
(1.01 KB)
📄
preempt_wasm.s
(176 B)
📄
print.go
(5.95 KB)
📄
proc.go
(176.84 KB)
📄
proc_runtime_test.go
(1.38 KB)
📄
proc_test.go
(25.66 KB)
📄
profbuf.go
(18.26 KB)
📄
profbuf_test.go
(8.65 KB)
📄
proflabel.go
(1.52 KB)
📁
race
📄
race.go
(18.58 KB)
📄
race0.go
(2.79 KB)
📄
race_amd64.s
(13.82 KB)
📄
race_arm64.s
(14.21 KB)
📄
race_ppc64le.s
(17.89 KB)
📄
race_s390x.s
(12 KB)
📄
rand_test.go
(907 B)
📄
rdebug.go
(553 B)
📄
relax_stub.go
(598 B)
📄
rt0_aix_ppc64.s
(4.33 KB)
📄
rt0_android_386.s
(822 B)
📄
rt0_android_amd64.s
(754 B)
📄
rt0_android_arm.s
(843 B)
📄
rt0_android_arm64.s
(941 B)
📄
rt0_darwin_amd64.s
(399 B)
📄
rt0_darwin_arm64.s
(1.69 KB)
📄
rt0_dragonfly_amd64.s
(448 B)
📄
rt0_freebsd_386.s
(454 B)
📄
rt0_freebsd_amd64.s
(442 B)
📄
rt0_freebsd_arm.s
(298 B)
📄
rt0_freebsd_arm64.s
(1.88 KB)
📄
rt0_illumos_amd64.s
(311 B)
📄
rt0_ios_amd64.s
(425 B)
📄
rt0_ios_arm64.s
(425 B)
📄
rt0_js_wasm.s
(2.3 KB)
📄
rt0_linux_386.s
(450 B)
📄
rt0_linux_amd64.s
(307 B)
📄
rt0_linux_arm.s
(1007 B)
📄
rt0_linux_arm64.s
(1.81 KB)
📄
rt0_linux_loong64.s
(716 B)
📄
rt0_linux_mips64x.s
(1014 B)
📄
rt0_linux_mipsx.s
(797 B)
📄
rt0_linux_ppc64.s
(928 B)
📄
rt0_linux_ppc64le.s
(4.35 KB)
📄
rt0_linux_riscv64.s
(2.65 KB)
📄
rt0_linux_s390x.s
(676 B)
📄
rt0_netbsd_386.s
(452 B)
📄
rt0_netbsd_amd64.s
(309 B)
📄
rt0_netbsd_arm.s
(296 B)
📄
rt0_netbsd_arm64.s
(1.8 KB)
📄
rt0_openbsd_386.s
(454 B)
📄
rt0_openbsd_amd64.s
(311 B)
📄
rt0_openbsd_arm.s
(298 B)
📄
rt0_openbsd_arm64.s
(1.96 KB)
📄
rt0_openbsd_mips64.s
(976 B)
📄
rt0_plan9_386.s
(523 B)
📄
rt0_plan9_amd64.s
(481 B)
📄
rt0_plan9_arm.s
(397 B)
📄
rt0_solaris_amd64.s
(311 B)
📄
rt0_windows_386.s
(1.28 KB)
📄
rt0_windows_amd64.s
(986 B)
📄
rt0_windows_arm.s
(386 B)
📄
rt0_windows_arm64.s
(725 B)
📄
runtime-gdb.py
(15.33 KB)
📄
runtime-gdb_test.go
(20.93 KB)
📄
runtime-lldb_test.go
(4.95 KB)
📄
runtime.go
(1.45 KB)
📄
runtime1.go
(13.06 KB)
📄
runtime2.go
(43.07 KB)
📄
runtime_boring.go
(606 B)
📄
runtime_linux_test.go
(1.95 KB)
📄
runtime_mmap_test.go
(1.77 KB)
📄
runtime_test.go
(11.79 KB)
📄
runtime_unix_test.go
(1.22 KB)
📄
rwmutex.go
(3.53 KB)
📄
rwmutex_test.go
(4.19 KB)
📄
select.go
(14.84 KB)
📄
sema.go
(16.16 KB)
📄
sema_test.go
(4.21 KB)
📄
semasleep_test.go
(3.05 KB)
📄
sigaction.go
(489 B)
📄
signal_386.go
(1.72 KB)
📄
signal_aix_ppc64.go
(3.55 KB)
📄
signal_amd64.go
(2.73 KB)
📄
signal_arm.go
(2.54 KB)
📄
signal_arm64.go
(3.21 KB)
📄
signal_darwin.go
(2.13 KB)
📄
signal_darwin_amd64.go
(4 KB)
📄
signal_darwin_arm64.go
(3.6 KB)
📄
signal_dragonfly.go
(2.17 KB)
📄
signal_dragonfly_amd64.go
(2.01 KB)
📄
signal_freebsd.go
(2.2 KB)
📄
signal_freebsd_386.go
(1.55 KB)
📄
signal_freebsd_amd64.go
(2.03 KB)
📄
signal_freebsd_arm.go
(2.18 KB)
📄
signal_freebsd_arm64.go
(3.23 KB)
📄
signal_linux_386.go
(1.59 KB)
📄
signal_linux_amd64.go
(2.05 KB)
📄
signal_linux_arm.go
(2.12 KB)
📄
signal_linux_arm64.go
(2.95 KB)
📄
signal_linux_loong64.go
(3.22 KB)
📄
signal_linux_mips64x.go
(3.35 KB)
📄
signal_linux_mipsx.go
(3.67 KB)
📄
signal_linux_ppc64x.go
(3.42 KB)
📄
signal_linux_riscv64.go
(2.92 KB)
📄
signal_linux_s390x.go
(4.49 KB)
📄
signal_loong64.go
(3.09 KB)
📄
signal_mips64x.go
(3.18 KB)
📄
signal_mipsx.go
(3.06 KB)
📄
signal_netbsd.go
(2.18 KB)
📄
signal_netbsd_386.go
(1.76 KB)
📄
signal_netbsd_amd64.go
(2.33 KB)
📄
signal_netbsd_arm.go
(2.3 KB)
📄
signal_netbsd_arm64.go
(3.4 KB)
📄
signal_openbsd.go
(2.18 KB)
📄
signal_openbsd_386.go
(1.58 KB)
📄
signal_openbsd_amd64.go
(2.04 KB)
📄
signal_openbsd_arm.go
(2.12 KB)
📄
signal_openbsd_arm64.go
(3.38 KB)
📄
signal_openbsd_mips64.go
(3.28 KB)
📄
signal_plan9.go
(1.93 KB)
📄
signal_ppc64x.go
(3.64 KB)
📄
signal_riscv64.go
(2.89 KB)
📄
signal_solaris.go
(4.5 KB)
📄
signal_solaris_amd64.go
(2.47 KB)
📄
signal_unix.go
(41.88 KB)
📄
signal_windows.go
(9.27 KB)
📄
signal_windows_test.go
(5.29 KB)
📄
sigqueue.go
(7.66 KB)
📄
sigqueue_note.go
(648 B)
📄
sigqueue_plan9.go
(3.25 KB)
📄
sigtab_aix.go
(11.3 KB)
📄
sigtab_linux_generic.go
(3.52 KB)
📄
sigtab_linux_mipsx.go
(5.95 KB)
📄
sizeclasses.go
(9.14 KB)
📄
sizeof_test.go
(893 B)
📄
slice.go
(9.87 KB)
📄
slice_test.go
(10.32 KB)
📄
softfloat64.go
(11.54 KB)
📄
softfloat64_test.go
(4.04 KB)
📄
stack.go
(45.05 KB)
📄
stack_test.go
(22.39 KB)
📄
string.go
(13.18 KB)
📄
string_test.go
(12.61 KB)
📄
stubs.go
(19.37 KB)
📄
stubs2.go
(1.13 KB)
📄
stubs3.go
(274 B)
📄
stubs_386.go
(550 B)
📄
stubs_amd64.go
(1.2 KB)
📄
stubs_arm.go
(531 B)
📄
stubs_arm64.go
(555 B)
📄
stubs_linux.go
(650 B)
📄
stubs_loong64.go
(276 B)
📄
stubs_mips64x.go
(364 B)
📄
stubs_mipsx.go
(283 B)
📄
stubs_nonlinux.go
(298 B)
📄
stubs_ppc64.go
(301 B)
📄
stubs_ppc64x.go
(453 B)
📄
stubs_riscv64.go
(460 B)
📄
stubs_s390x.go
(256 B)
📄
symtab.go
(35.81 KB)
📄
symtab_test.go
(7.48 KB)
📄
sys_aix_ppc64.s
(7.42 KB)
📄
sys_arm.go
(521 B)
📄
sys_arm64.go
(469 B)
📄
sys_darwin.go
(17.92 KB)
📄
sys_darwin_amd64.s
(19.12 KB)
📄
sys_darwin_arm64.go
(1.74 KB)
📄
sys_darwin_arm64.s
(15.95 KB)
📄
sys_dragonfly_amd64.s
(8.03 KB)
📄
sys_freebsd_386.s
(8.41 KB)
📄
sys_freebsd_amd64.s
(10.7 KB)
📄
sys_freebsd_arm.s
(10.12 KB)
📄
sys_freebsd_arm64.s
(9.4 KB)
📄
sys_libc.go
(1.84 KB)
📄
sys_linux_386.s
(18.31 KB)
📄
sys_linux_amd64.s
(16.57 KB)
📄
sys_linux_arm.s
(16.12 KB)
📄
sys_linux_arm64.s
(18.09 KB)
📄
sys_linux_loong64.s
(12.15 KB)
📄
sys_linux_mips64x.s
(13.5 KB)
📄
sys_linux_mipsx.s
(11.09 KB)
📄
sys_linux_ppc64x.s
(22.1 KB)
📄
sys_linux_riscv64.s
(12.59 KB)
📄
sys_linux_s390x.s
(13.78 KB)
📄
sys_loong64.go
(489 B)
📄
sys_mips64x.go
(500 B)
📄
sys_mipsx.go
(496 B)
📄
sys_netbsd_386.s
(9.55 KB)
📄
sys_netbsd_amd64.s
(9.51 KB)
📄
sys_netbsd_arm.s
(10.41 KB)
📄
sys_netbsd_arm64.s
(9.38 KB)
📄
sys_nonppc64x.go
(245 B)
📄
sys_openbsd.go
(2.59 KB)
📄
sys_openbsd1.go
(1.23 KB)
📄
sys_openbsd2.go
(8.36 KB)
📄
sys_openbsd3.go
(3.37 KB)
📄
sys_openbsd_386.s
(20.03 KB)
📄
sys_openbsd_amd64.s
(16.64 KB)
📄
sys_openbsd_arm.s
(18.15 KB)
📄
sys_openbsd_arm64.s
(14.84 KB)
📄
sys_openbsd_mips64.s
(8.6 KB)
📄
sys_plan9_386.s
(4.48 KB)
📄
sys_plan9_amd64.s
(4.55 KB)
📄
sys_plan9_arm.s
(7.03 KB)
📄
sys_ppc64x.go
(532 B)
📄
sys_riscv64.go
(469 B)
📄
sys_s390x.go
(469 B)
📄
sys_solaris_amd64.s
(6.42 KB)
📄
sys_wasm.go
(754 B)
📄
sys_wasm.s
(2.65 KB)
📄
sys_windows_386.s
(7.65 KB)
📄
sys_windows_amd64.s
(8.88 KB)
📄
sys_windows_arm.s
(11.97 KB)
📄
sys_windows_arm64.s
(11.45 KB)
📄
sys_x86.go
(552 B)
📄
syscall2_solaris.go
(1.65 KB)
📄
syscall_aix.go
(6 KB)
📄
syscall_solaris.go
(8.01 KB)
📄
syscall_windows.go
(16.95 KB)
📄
syscall_windows_test.go
(32.96 KB)
📁
testdata
📄
textflag.h
(1.52 KB)
📄
time.go
(30.75 KB)
📄
time_fake.go
(2.5 KB)
📄
time_linux_amd64.s
(2.02 KB)
📄
time_nofake.go
(709 B)
📄
time_test.go
(2.03 KB)
📄
time_windows.h
(753 B)
📄
time_windows_386.s
(1.79 KB)
📄
time_windows_amd64.s
(871 B)
📄
time_windows_arm.s
(2.1 KB)
📄
time_windows_arm64.s
(1021 B)
📄
timeasm.go
(418 B)
📄
timestub.go
(532 B)
📄
timestub2.go
(314 B)
📄
tls_arm.s
(3.45 KB)
📄
tls_arm64.h
(1.1 KB)
📄
tls_arm64.s
(1.2 KB)
📄
tls_loong64.s
(589 B)
📄
tls_mips64x.s
(733 B)
📄
tls_mipsx.s
(709 B)
📄
tls_ppc64x.s
(1.5 KB)
📄
tls_riscv64.s
(726 B)
📄
tls_s390x.s
(1.55 KB)
📄
tls_stub.go
(260 B)
📄
tls_windows_amd64.go
(294 B)
📁
trace
📄
trace.go
(45.8 KB)
📄
traceback.go
(48.18 KB)
📄
traceback_test.go
(11.64 KB)
📄
type.go
(17.43 KB)
📄
typekind.go
(742 B)
📄
utf8.go
(3.39 KB)
📄
vdso_elf32.go
(2.76 KB)
📄
vdso_elf64.go
(2.84 KB)
📄
vdso_freebsd.go
(2.44 KB)
📄
vdso_freebsd_arm.go
(454 B)
📄
vdso_freebsd_arm64.go
(443 B)
📄
vdso_freebsd_x86.go
(1.85 KB)
📄
vdso_in_none.go
(443 B)
📄
vdso_linux.go
(7.77 KB)
📄
vdso_linux_386.go
(669 B)
📄
vdso_linux_amd64.go
(685 B)
📄
vdso_linux_arm.go
(669 B)
📄
vdso_linux_arm64.go
(670 B)
📄
vdso_linux_loong64.go
(793 B)
📄
vdso_linux_mips64x.go
(850 B)
📄
vdso_linux_ppc64x.go
(672 B)
📄
vdso_linux_riscv64.go
(666 B)
📄
vdso_linux_s390x.go
(681 B)
📄
vlop_386.s
(2.02 KB)
📄
vlop_arm.s
(7.06 KB)
📄
vlop_arm_test.go
(3.75 KB)
📄
vlrt.go
(6.71 KB)
📄
wincallback.go
(3.45 KB)
📄
write_err.go
(291 B)
📄
write_err_android.go
(4.65 KB)
📄
zcallback_windows.go
(155 B)
📄
zcallback_windows.s
(63.02 KB)
📄
zcallback_windows_arm.s
(89.32 KB)
📄
zcallback_windows_arm64.s
(89.32 KB)
Editing: traceback_test.go
// Copyright 2021 The Go Authors. All rights reserved. // Use of this source code is governed by a BSD-style // license that can be found in the LICENSE file. package runtime_test import ( "bytes" "internal/abi" "internal/testenv" "runtime" "strings" "testing" ) var testTracebackArgsBuf [1000]byte func TestTracebackArgs(t *testing.T) { if *flagQuick { t.Skip("-quick") } optimized := !strings.HasSuffix(testenv.Builder(), "-noopt") abiSel := func(x, y string) string { // select expected output based on ABI // In noopt build we always spill arguments so the output is the same as stack ABI. if optimized && abi.IntArgRegs > 0 { return x } return y } tests := []struct { fn func() int expect string }{ // simple ints { func() int { return testTracebackArgs1(1, 2, 3, 4, 5) }, "testTracebackArgs1(0x1, 0x2, 0x3, 0x4, 0x5)", }, // some aggregates { func() int { return testTracebackArgs2(false, struct { a, b, c int x [2]int }{1, 2, 3, [2]int{4, 5}}, [0]int{}, [3]byte{6, 7, 8}) }, "testTracebackArgs2(0x0, {0x1, 0x2, 0x3, {0x4, 0x5}}, {}, {0x6, 0x7, 0x8})", }, { func() int { return testTracebackArgs3([3]byte{1, 2, 3}, 4, 5, 6, [3]byte{7, 8, 9}) }, "testTracebackArgs3({0x1, 0x2, 0x3}, 0x4, 0x5, 0x6, {0x7, 0x8, 0x9})", }, // too deeply nested type { func() int { return testTracebackArgs4(false, [1][1][1][1][1][1][1][1][1][1]int{}) }, "testTracebackArgs4(0x0, {{{{{...}}}}})", }, // a lot of zero-sized type { func() int { z := [0]int{} return testTracebackArgs5(false, struct { x int y [0]int z [2][0]int }{1, z, [2][0]int{}}, z, z, z, z, z, z, z, z, z, z, z, z) }, "testTracebackArgs5(0x0, {0x1, {}, {{}, {}}}, {}, {}, {}, {}, {}, ...)", }, // edge cases for ... // no ... for 10 args { func() int { return testTracebackArgs6a(1, 2, 3, 4, 5, 6, 7, 8, 9, 10) }, "testTracebackArgs6a(0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa)", }, // has ... for 11 args { func() int { return testTracebackArgs6b(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11) }, "testTracebackArgs6b(0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa, ...)", }, // no ... for aggregates with 10 words { func() int { return testTracebackArgs7a([10]int{1, 2, 3, 4, 5, 6, 7, 8, 9, 10}) }, "testTracebackArgs7a({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa})", }, // has ... for aggregates with 11 words { func() int { return testTracebackArgs7b([11]int{1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11}) }, "testTracebackArgs7b({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa, ...})", }, // no ... for aggregates, but with more args { func() int { return testTracebackArgs7c([10]int{1, 2, 3, 4, 5, 6, 7, 8, 9, 10}, 11) }, "testTracebackArgs7c({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa}, ...)", }, // has ... for aggregates and also for more args { func() int { return testTracebackArgs7d([11]int{1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11}, 12) }, "testTracebackArgs7d({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, 0x9, 0xa, ...}, ...)", }, // nested aggregates, no ... { func() int { return testTracebackArgs8a(testArgsType8a{1, 2, 3, 4, 5, 6, 7, 8, [2]int{9, 10}}) }, "testTracebackArgs8a({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, {0x9, 0xa}})", }, // nested aggregates, ... in inner but not outer { func() int { return testTracebackArgs8b(testArgsType8b{1, 2, 3, 4, 5, 6, 7, 8, [3]int{9, 10, 11}}) }, "testTracebackArgs8b({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, {0x9, 0xa, ...}})", }, // nested aggregates, ... in outer but not inner { func() int { return testTracebackArgs8c(testArgsType8c{1, 2, 3, 4, 5, 6, 7, 8, [2]int{9, 10}, 11}) }, "testTracebackArgs8c({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, {0x9, 0xa}, ...})", }, // nested aggregates, ... in both inner and outer { func() int { return testTracebackArgs8d(testArgsType8d{1, 2, 3, 4, 5, 6, 7, 8, [3]int{9, 10, 11}, 12}) }, "testTracebackArgs8d({0x1, 0x2, 0x3, 0x4, 0x5, 0x6, 0x7, 0x8, {0x9, 0xa, ...}, ...})", }, // Register argument liveness. // 1, 3 are used and live, 2, 4 are dead (in register ABI). // Address-taken (7) and stack ({5, 6}) args are always live. { func() int { poisonStack() // poison arg area to make output deterministic return testTracebackArgs9(1, 2, 3, 4, [2]int{5, 6}, 7) }, abiSel( "testTracebackArgs9(0x1, 0xffffffff?, 0x3, 0xff?, {0x5, 0x6}, 0x7)", "testTracebackArgs9(0x1, 0x2, 0x3, 0x4, {0x5, 0x6}, 0x7)"), }, // No live. // (Note: this assume at least 5 int registers if register ABI is used.) { func() int { poisonStack() // poison arg area to make output deterministic return testTracebackArgs10(1, 2, 3, 4, 5) }, abiSel( "testTracebackArgs10(0xffffffff?, 0xffffffff?, 0xffffffff?, 0xffffffff?, 0xffffffff?)", "testTracebackArgs10(0x1, 0x2, 0x3, 0x4, 0x5)"), }, // Conditional spills. // Spill in conditional, not executed. { func() int { poisonStack() // poison arg area to make output deterministic return testTracebackArgs11a(1, 2, 3) }, abiSel( "testTracebackArgs11a(0xffffffff?, 0xffffffff?, 0xffffffff?)", "testTracebackArgs11a(0x1, 0x2, 0x3)"), }, // 2 spills in conditional, not executed; 3 spills in conditional, executed, but not statically known. // So print 0x3?. { func() int { poisonStack() // poison arg area to make output deterministic return testTracebackArgs11b(1, 2, 3, 4) }, abiSel( "testTracebackArgs11b(0xffffffff?, 0xffffffff?, 0x3?, 0x4)", "testTracebackArgs11b(0x1, 0x2, 0x3, 0x4)"), }, } for _, test := range tests { n := test.fn() got := testTracebackArgsBuf[:n] if !bytes.Contains(got, []byte(test.expect)) { t.Errorf("traceback does not contain expected string: want %q, got\n%s", test.expect, got) } } } //go:noinline func testTracebackArgs1(a, b, c, d, e int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a < 0 { // use in-reg args to keep them alive return a + b + c + d + e } return n } //go:noinline func testTracebackArgs2(a bool, b struct { a, b, c int x [2]int }, _ [0]int, d [3]byte) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a { // use in-reg args to keep them alive return b.a + b.b + b.c + b.x[0] + b.x[1] + int(d[0]) + int(d[1]) + int(d[2]) } return n } //go:noinline //go:registerparams func testTracebackArgs3(x [3]byte, a, b, c int, y [3]byte) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a < 0 { // use in-reg args to keep them alive return int(x[0]) + int(x[1]) + int(x[2]) + a + b + c + int(y[0]) + int(y[1]) + int(y[2]) } return n } //go:noinline func testTracebackArgs4(a bool, x [1][1][1][1][1][1][1][1][1][1]int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a { panic(x) // use args to keep them alive } return n } //go:noinline func testTracebackArgs5(a bool, x struct { x int y [0]int z [2][0]int }, _, _, _, _, _, _, _, _, _, _, _, _ [0]int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a { panic(x) // use args to keep them alive } return n } //go:noinline func testTracebackArgs6a(a, b, c, d, e, f, g, h, i, j int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a < 0 { // use in-reg args to keep them alive return a + b + c + d + e + f + g + h + i + j } return n } //go:noinline func testTracebackArgs6b(a, b, c, d, e, f, g, h, i, j, k int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a < 0 { // use in-reg args to keep them alive return a + b + c + d + e + f + g + h + i + j + k } return n } //go:noinline func testTracebackArgs7a(a [10]int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a[0] < 0 { // use in-reg args to keep them alive return a[1] + a[2] + a[3] + a[4] + a[5] + a[6] + a[7] + a[8] + a[9] } return n } //go:noinline func testTracebackArgs7b(a [11]int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a[0] < 0 { // use in-reg args to keep them alive return a[1] + a[2] + a[3] + a[4] + a[5] + a[6] + a[7] + a[8] + a[9] + a[10] } return n } //go:noinline func testTracebackArgs7c(a [10]int, b int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a[0] < 0 { // use in-reg args to keep them alive return a[1] + a[2] + a[3] + a[4] + a[5] + a[6] + a[7] + a[8] + a[9] + b } return n } //go:noinline func testTracebackArgs7d(a [11]int, b int) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a[0] < 0 { // use in-reg args to keep them alive return a[1] + a[2] + a[3] + a[4] + a[5] + a[6] + a[7] + a[8] + a[9] + a[10] + b } return n } type testArgsType8a struct { a, b, c, d, e, f, g, h int i [2]int } type testArgsType8b struct { a, b, c, d, e, f, g, h int i [3]int } type testArgsType8c struct { a, b, c, d, e, f, g, h int i [2]int j int } type testArgsType8d struct { a, b, c, d, e, f, g, h int i [3]int j int } //go:noinline func testTracebackArgs8a(a testArgsType8a) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a.a < 0 { // use in-reg args to keep them alive return a.b + a.c + a.d + a.e + a.f + a.g + a.h + a.i[0] + a.i[1] } return n } //go:noinline func testTracebackArgs8b(a testArgsType8b) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a.a < 0 { // use in-reg args to keep them alive return a.b + a.c + a.d + a.e + a.f + a.g + a.h + a.i[0] + a.i[1] + a.i[2] } return n } //go:noinline func testTracebackArgs8c(a testArgsType8c) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a.a < 0 { // use in-reg args to keep them alive return a.b + a.c + a.d + a.e + a.f + a.g + a.h + a.i[0] + a.i[1] + a.j } return n } //go:noinline func testTracebackArgs8d(a testArgsType8d) int { n := runtime.Stack(testTracebackArgsBuf[:], false) if a.a < 0 { // use in-reg args to keep them alive return a.b + a.c + a.d + a.e + a.f + a.g + a.h + a.i[0] + a.i[1] + a.i[2] + a.j } return n } // nosplit to avoid preemption or morestack spilling registers. // //go:nosplit //go:noinline func testTracebackArgs9(a int64, b int32, c int16, d int8, x [2]int, y int) int { if a < 0 { println(&y) // take address, make y live, even if no longer used at traceback } n := runtime.Stack(testTracebackArgsBuf[:], false) if a < 0 { // use half of in-reg args to keep them alive, the other half are dead return int(a) + int(c) } return n } // nosplit to avoid preemption or morestack spilling registers. // //go:nosplit //go:noinline func testTracebackArgs10(a, b, c, d, e int32) int { // no use of any args return runtime.Stack(testTracebackArgsBuf[:], false) } // norace to avoid race instrumentation changing spill locations. // nosplit to avoid preemption or morestack spilling registers. // //go:norace //go:nosplit //go:noinline func testTracebackArgs11a(a, b, c int32) int { if a < 0 { println(a, b, c) // spill in a conditional, may not execute } if b < 0 { return int(a + b + c) } return runtime.Stack(testTracebackArgsBuf[:], false) } // norace to avoid race instrumentation changing spill locations. // nosplit to avoid preemption or morestack spilling registers. // //go:norace //go:nosplit //go:noinline func testTracebackArgs11b(a, b, c, d int32) int { var x int32 if a < 0 { print() // spill b in a conditional x = b } else { print() // spill c in a conditional x = c } if d < 0 { // d is always needed return int(x + d) } return runtime.Stack(testTracebackArgsBuf[:], false) } // Poison the arg area with deterministic values. // //go:noinline func poisonStack() [20]int { return [20]int{-1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1, -1} }
Upload File
Create Folder