X7ROOT File Manager
Current Path:
/opt/golang/1.17.2/src/runtime
opt
/
golang
/
1.17.2
/
src
/
runtime
/
📁
..
📄
HACKING.md
(13.07 KB)
📄
Makefile
(178 B)
📄
abi_test.go
(2.88 KB)
📄
alg.go
(9.45 KB)
📄
asm.s
(715 B)
📄
asm_386.s
(40.27 KB)
📄
asm_amd64.s
(56.93 KB)
📄
asm_arm.s
(30.23 KB)
📄
asm_arm64.s
(33 KB)
📄
asm_mips64x.s
(22.43 KB)
📄
asm_mipsx.s
(24.39 KB)
📄
asm_ppc64x.h
(1023 B)
📄
asm_ppc64x.s
(29.16 KB)
📄
asm_riscv64.s
(22.43 KB)
📄
asm_s390x.s
(26.04 KB)
📄
asm_wasm.s
(9.8 KB)
📄
atomic_arm64.s
(259 B)
📄
atomic_mips64x.s
(326 B)
📄
atomic_mipsx.s
(284 B)
📄
atomic_pointer.go
(2.62 KB)
📄
atomic_ppc64x.s
(461 B)
📄
atomic_riscv64.s
(275 B)
📄
auxv_none.go
(360 B)
📄
callers_test.go
(7.72 KB)
📁
cgo
📄
cgo.go
(2.01 KB)
📄
cgo_mmap.go
(2.42 KB)
📄
cgo_ppc64x.go
(439 B)
📄
cgo_sigaction.go
(3.17 KB)
📄
cgocall.go
(18.88 KB)
📄
cgocallback.go
(317 B)
📄
cgocheck.go
(6.83 KB)
📄
chan.go
(23.54 KB)
📄
chan_test.go
(23.01 KB)
📄
chanbarrier_test.go
(1.4 KB)
📄
checkptr.go
(3.29 KB)
📄
checkptr_test.go
(1.62 KB)
📄
closure_test.go
(937 B)
📄
compiler.go
(413 B)
📄
complex.go
(1.59 KB)
📄
complex_test.go
(1.05 KB)
📄
conv_wasm_test.go
(2.96 KB)
📄
cpuflags.go
(800 B)
📄
cpuflags_amd64.go
(533 B)
📄
cpuflags_arm64.go
(334 B)
📄
cpuprof.go
(6.92 KB)
📄
cputicks.go
(497 B)
📄
crash_cgo_test.go
(16.17 KB)
📄
crash_nonunix_test.go
(429 B)
📄
crash_test.go
(20.96 KB)
📄
crash_unix_test.go
(8.52 KB)
📁
debug
📄
debug.go
(1.63 KB)
📄
debug_test.go
(6.82 KB)
📄
debugcall.go
(6.21 KB)
📄
debuglog.go
(17.49 KB)
📄
debuglog_off.go
(377 B)
📄
debuglog_on.go
(1.11 KB)
📄
debuglog_test.go
(4.56 KB)
📄
defer_test.go
(10.32 KB)
📄
defs1_linux.go
(862 B)
📄
defs1_netbsd_386.go
(2.84 KB)
📄
defs1_netbsd_amd64.go
(3.07 KB)
📄
defs1_netbsd_arm.go
(2.96 KB)
📄
defs1_netbsd_arm64.go
(3.18 KB)
📄
defs1_solaris_amd64.go
(4.02 KB)
📄
defs2_linux.go
(3.52 KB)
📄
defs3_linux.go
(1.11 KB)
📄
defs_aix.go
(4.18 KB)
📄
defs_aix_ppc64.go
(3.63 KB)
📄
defs_arm_linux.go
(2.69 KB)
📄
defs_darwin.go
(3.79 KB)
📄
defs_darwin_amd64.go
(6.07 KB)
📄
defs_darwin_arm64.go
(3.89 KB)
📄
defs_dragonfly.go
(2.63 KB)
📄
defs_dragonfly_amd64.go
(3.31 KB)
📄
defs_freebsd.go
(3.86 KB)
📄
defs_freebsd_386.go
(4.38 KB)
📄
defs_freebsd_amd64.go
(4.65 KB)
📄
defs_freebsd_arm.go
(3.71 KB)
📄
defs_freebsd_arm64.go
(4.03 KB)
📄
defs_illumos_amd64.go
(285 B)
📄
defs_linux.go
(3.05 KB)
📄
defs_linux_386.go
(3.77 KB)
📄
defs_linux_amd64.go
(4.28 KB)
📄
defs_linux_arm.go
(3.45 KB)
📄
defs_linux_arm64.go
(3.21 KB)
📄
defs_linux_mips64x.go
(3.24 KB)
📄
defs_linux_mipsx.go
(3.21 KB)
📄
defs_linux_ppc64.go
(3.28 KB)
📄
defs_linux_ppc64le.go
(3.28 KB)
📄
defs_linux_riscv64.go
(3.27 KB)
📄
defs_linux_s390x.go
(2.76 KB)
📄
defs_netbsd.go
(2.76 KB)
📄
defs_netbsd_386.go
(872 B)
📄
defs_netbsd_amd64.go
(1.03 KB)
📄
defs_netbsd_arm.go
(781 B)
📄
defs_openbsd.go
(3.1 KB)
📄
defs_openbsd_386.go
(2.89 KB)
📄
defs_openbsd_amd64.go
(3.09 KB)
📄
defs_openbsd_arm.go
(3 KB)
📄
defs_openbsd_arm64.go
(2.76 KB)
📄
defs_openbsd_mips64.go
(2.66 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.35 KB)
📄
defs_solaris_amd64.go
(1021 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.25 KB)
📄
duff_mips64x.s
(11.31 KB)
📄
duff_ppc64x.s
(2.43 KB)
📄
duff_riscv64.s
(11.38 KB)
📄
duff_s390x.s
(507 B)
📄
env_plan9.go
(2.99 KB)
📄
env_posix.go
(1.95 KB)
📄
env_test.go
(1.16 KB)
📄
error.go
(9.23 KB)
📄
example_test.go
(1.55 KB)
📄
export_aix_test.go
(204 B)
📄
export_arm_test.go
(226 B)
📄
export_darwin_test.go
(351 B)
📄
export_debug_regabiargs_off_test.go
(416 B)
📄
export_debug_regabiargs_on_test.go
(1.39 KB)
📄
export_debug_test.go
(5.86 KB)
📄
export_debuglog_test.go
(1.27 KB)
📄
export_futex_test.go
(570 B)
📄
export_linux_test.go
(429 B)
📄
export_mmap_test.go
(571 B)
📄
export_pipe2_test.go
(436 B)
📄
export_pipe_test.go
(240 B)
📄
export_solaris_test.go
(282 B)
📄
export_test.go
(30.12 KB)
📄
export_unix_test.go
(2.35 KB)
📄
export_windows_test.go
(652 B)
📄
extern.go
(12.58 KB)
📄
fastlog2.go
(1.22 KB)
📄
fastlog2_test.go
(784 B)
📄
fastlog2table.go
(904 B)
📄
float.go
(1.35 KB)
📄
funcdata.h
(2.47 KB)
📄
futex_test.go
(2.15 KB)
📄
gc_test.go
(19.21 KB)
📄
gcinfo_test.go
(5.69 KB)
📄
go_tls.h
(366 B)
📄
hash32.go
(1.61 KB)
📄
hash64.go
(2.01 KB)
📄
hash_test.go
(16.5 KB)
📄
heapdump.go
(17.74 KB)
📄
histogram.go
(6.42 KB)
📄
histogram_test.go
(1.85 KB)
📄
iface.go
(16.13 KB)
📄
iface_test.go
(7.51 KB)
📁
internal
📄
lfstack.go
(1.77 KB)
📄
lfstack_32bit.go
(562 B)
📄
lfstack_64bit.go
(2.24 KB)
📄
lfstack_test.go
(2.78 KB)
📄
libfuzzer.go
(2.6 KB)
📄
libfuzzer_amd64.s
(961 B)
📄
libfuzzer_arm64.s
(772 B)
📄
lock_futex.go
(5.22 KB)
📄
lock_js.go
(5.81 KB)
📄
lock_sema.go
(6.8 KB)
📄
lockrank.go
(11.62 KB)
📄
lockrank_off.go
(1.17 KB)
📄
lockrank_on.go
(9.84 KB)
📄
lockrank_test.go
(1.15 KB)
📄
malloc.go
(52.33 KB)
📄
malloc_test.go
(10.83 KB)
📄
map.go
(42.47 KB)
📄
map_benchmark_test.go
(10.51 KB)
📄
map_fast32.go
(12.63 KB)
📄
map_fast64.go
(12.82 KB)
📄
map_faststr.go
(14.15 KB)
📄
map_test.go
(27.52 KB)
📄
mbarrier.go
(12.2 KB)
📄
mbitmap.go
(65.27 KB)
📄
mcache.go
(9.68 KB)
📄
mcentral.go
(7.8 KB)
📄
mcheckmark.go
(2.81 KB)
📄
mem_aix.go
(1.94 KB)
📄
mem_bsd.go
(2.12 KB)
📄
mem_darwin.go
(1.88 KB)
📄
mem_js.go
(2.35 KB)
📄
mem_linux.go
(5.59 KB)
📄
mem_plan9.go
(4.53 KB)
📄
mem_windows.go
(3.87 KB)
📄
memclr_386.s
(2.42 KB)
📄
memclr_amd64.s
(3.89 KB)
📄
memclr_arm.s
(2.6 KB)
📄
memclr_arm64.s
(3.65 KB)
📄
memclr_mips64x.s
(1.75 KB)
📄
memclr_mipsx.s
(1.35 KB)
📄
memclr_plan9_386.s
(983 B)
📄
memclr_plan9_amd64.s
(511 B)
📄
memclr_ppc64x.s
(4.31 KB)
📄
memclr_riscv64.s
(926 B)
📄
memclr_s390x.s
(1.96 KB)
📄
memclr_wasm.s
(622 B)
📄
memmove_386.s
(4.46 KB)
📄
memmove_amd64.s
(12.66 KB)
📄
memmove_arm.s
(5.9 KB)
📄
memmove_arm64.s
(6 KB)
📄
memmove_linux_amd64_test.go
(1.6 KB)
📄
memmove_mips64x.s
(1.85 KB)
📄
memmove_mipsx.s
(4.42 KB)
📄
memmove_plan9_386.s
(3.06 KB)
📄
memmove_plan9_amd64.s
(3.04 KB)
📄
memmove_ppc64x.s
(4.11 KB)
📄
memmove_riscv64.s
(1.81 KB)
📄
memmove_s390x.s
(2.92 KB)
📄
memmove_test.go
(12.04 KB)
📄
memmove_wasm.s
(1.74 KB)
📁
metrics
📄
metrics.go
(17.69 KB)
📄
metrics_test.go
(12.48 KB)
📄
mfinal.go
(15.76 KB)
📄
mfinal_test.go
(5.85 KB)
📄
mfixalloc.go
(2.73 KB)
📄
mgc.go
(55.18 KB)
📄
mgcmark.go
(45.54 KB)
📄
mgcpacer.go
(29.56 KB)
📄
mgcscavenge.go
(35.05 KB)
📄
mgcscavenge_test.go
(12.74 KB)
📄
mgcstack.go
(10.58 KB)
📄
mgcsweep.go
(23.56 KB)
📄
mgcwork.go
(12.82 KB)
📄
mheap.go
(66.31 KB)
📄
mkduff.go
(7.19 KB)
📄
mkfastlog2table.go
(1.32 KB)
📄
mkpreempt.go
(14.17 KB)
📄
mksizeclasses.go
(9.31 KB)
📄
mmap.go
(990 B)
📄
mpagealloc.go
(36.77 KB)
📄
mpagealloc_32bit.go
(3.81 KB)
📄
mpagealloc_64bit.go
(6.65 KB)
📄
mpagealloc_test.go
(32.38 KB)
📄
mpagecache.go
(5.28 KB)
📄
mpagecache_test.go
(9.93 KB)
📄
mpallocbits.go
(12.01 KB)
📄
mpallocbits_test.go
(13.69 KB)
📄
mprof.go
(25.82 KB)
📄
mranges.go
(11.84 KB)
📄
mranges_test.go
(5.68 KB)
📁
msan
📄
msan.go
(1.51 KB)
📄
msan0.go
(741 B)
📄
msan_amd64.s
(2.32 KB)
📄
msan_arm64.s
(2.01 KB)
📄
msize.go
(777 B)
📄
mspanset.go
(12.2 KB)
📄
mstats.go
(30.65 KB)
📄
mwbbuf.go
(9.3 KB)
📄
nbpipe_fcntl_libc_test.go
(499 B)
📄
nbpipe_fcntl_unix_test.go
(507 B)
📄
nbpipe_pipe.go
(426 B)
📄
nbpipe_pipe2.go
(592 B)
📄
nbpipe_test.go
(2.26 KB)
📄
net_plan9.go
(645 B)
📄
netpoll.go
(16.24 KB)
📄
netpoll_aix.go
(4.87 KB)
📄
netpoll_epoll.go
(4.21 KB)
📄
netpoll_fake.go
(670 B)
📄
netpoll_kqueue.go
(4.64 KB)
📄
netpoll_os_test.go
(360 B)
📄
netpoll_solaris.go
(10.75 KB)
📄
netpoll_stub.go
(1.42 KB)
📄
netpoll_windows.go
(3.75 KB)
📄
norace_linux_test.go
(905 B)
📄
norace_test.go
(996 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.88 KB)
📄
os3_solaris.go
(17.02 KB)
📄
os_aix.go
(8.06 KB)
📄
os_android.go
(463 B)
📄
os_darwin.go
(11.54 KB)
📄
os_darwin_arm64.go
(416 B)
📄
os_dragonfly.go
(6.46 KB)
📄
os_freebsd.go
(11.2 KB)
📄
os_freebsd2.go
(507 B)
📄
os_freebsd_amd64.go
(529 B)
📄
os_freebsd_arm.go
(1.32 KB)
📄
os_freebsd_arm64.go
(398 B)
📄
os_freebsd_noauxv.go
(264 B)
📄
os_illumos.go
(3.93 KB)
📄
os_js.go
(3.26 KB)
📄
os_linux.go
(13.47 KB)
📄
os_linux_arm.go
(1.35 KB)
📄
os_linux_arm64.go
(572 B)
📄
os_linux_be64.go
(862 B)
📄
os_linux_generic.go
(950 B)
📄
os_linux_mips64x.go
(1.11 KB)
📄
os_linux_mipsx.go
(1.09 KB)
📄
os_linux_noauxv.go
(408 B)
📄
os_linux_novdso.go
(387 B)
📄
os_linux_ppc64x.go
(566 B)
📄
os_linux_riscv64.go
(198 B)
📄
os_linux_s390x.go
(316 B)
📄
os_linux_x86.go
(270 B)
📄
os_netbsd.go
(9.09 KB)
📄
os_netbsd_386.go
(588 B)
📄
os_netbsd_amd64.go
(585 B)
📄
os_netbsd_arm.go
(1.13 KB)
📄
os_netbsd_arm64.go
(827 B)
📄
os_nonopenbsd.go
(456 B)
📄
os_only_solaris.go
(376 B)
📄
os_openbsd.go
(6.01 KB)
📄
os_openbsd_arm.go
(749 B)
📄
os_openbsd_arm64.go
(416 B)
📄
os_openbsd_libc.go
(1.7 KB)
📄
os_openbsd_mips64.go
(416 B)
📄
os_openbsd_syscall.go
(1.27 KB)
📄
os_openbsd_syscall1.go
(466 B)
📄
os_openbsd_syscall2.go
(2.5 KB)
📄
os_plan9.go
(10.2 KB)
📄
os_plan9_arm.go
(462 B)
📄
os_solaris.go
(6.49 KB)
📄
os_windows.go
(43.68 KB)
📄
os_windows_arm.go
(511 B)
📄
os_windows_arm64.go
(339 B)
📄
panic.go
(44.28 KB)
📄
panic32.go
(4.83 KB)
📄
panic_test.go
(1.71 KB)
📄
plugin.go
(4.27 KB)
📁
pprof
📄
preempt.go
(15.4 KB)
📄
preempt_386.s
(1.07 KB)
📄
preempt_amd64.s
(1.81 KB)
📄
preempt_arm.s
(1.66 KB)
📄
preempt_arm64.s
(2.99 KB)
📄
preempt_mips64x.s
(2.93 KB)
📄
preempt_mipsx.s
(2.89 KB)
📄
preempt_nonwindows.go
(309 B)
📄
preempt_ppc64x.s
(2.92 KB)
📄
preempt_riscv64.s
(2.48 KB)
📄
preempt_s390x.s
(1.19 KB)
📄
preempt_wasm.s
(365 B)
📄
print.go
(5.95 KB)
📄
proc.go
(181.46 KB)
📄
proc_runtime_test.go
(820 B)
📄
proc_test.go
(25.02 KB)
📄
profbuf.go
(18.26 KB)
📄
profbuf_test.go
(8.65 KB)
📄
proflabel.go
(1.52 KB)
📁
race
📄
race.go
(18.56 KB)
📄
race0.go
(2.81 KB)
📄
race_amd64.s
(14.46 KB)
📄
race_arm64.s
(13.71 KB)
📄
race_ppc64le.s
(17.72 KB)
📄
rand_test.go
(783 B)
📄
rdebug.go
(553 B)
📄
relax_stub.go
(617 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
(2.27 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
(2.46 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
(2.39 KB)
📄
rt0_linux_mips64x.s
(1.03 KB)
📄
rt0_linux_mipsx.s
(835 B)
📄
rt0_linux_ppc64.s
(865 B)
📄
rt0_linux_ppc64le.s
(3.88 KB)
📄
rt0_linux_riscv64.s
(370 B)
📄
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
(2.38 KB)
📄
rt0_openbsd_386.s
(454 B)
📄
rt0_openbsd_amd64.s
(311 B)
📄
rt0_openbsd_arm.s
(298 B)
📄
rt0_openbsd_arm64.s
(2.54 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.02 KB)
📄
runtime-gdb_test.go
(20.19 KB)
📄
runtime-lldb_test.go
(4.95 KB)
📄
runtime.go
(1.42 KB)
📄
runtime1.go
(12.63 KB)
📄
runtime2.go
(42.27 KB)
📄
runtime_linux_test.go
(1.46 KB)
📄
runtime_mmap_test.go
(1.91 KB)
📄
runtime_test.go
(7.81 KB)
📄
runtime_unix_test.go
(1.29 KB)
📄
rwmutex.go
(3.53 KB)
📄
rwmutex_test.go
(4.03 KB)
📄
select.go
(14.45 KB)
📄
sema.go
(16.08 KB)
📄
sema_test.go
(2.5 KB)
📄
semasleep_test.go
(1.65 KB)
📄
sigaction.go
(543 B)
📄
signal_386.go
(1.72 KB)
📄
signal_aix_ppc64.go
(3.56 KB)
📄
signal_amd64.go
(2.71 KB)
📄
signal_arm.go
(2.56 KB)
📄
signal_arm64.go
(3.16 KB)
📄
signal_darwin.go
(2.13 KB)
📄
signal_darwin_amd64.go
(3.85 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.13 KB)
📄
signal_linux_arm64.go
(2.95 KB)
📄
signal_linux_mips64x.go
(3.39 KB)
📄
signal_linux_mipsx.go
(3.7 KB)
📄
signal_linux_ppc64x.go
(3.46 KB)
📄
signal_linux_riscv64.go
(2.92 KB)
📄
signal_linux_s390x.go
(4.43 KB)
📄
signal_mips64x.go
(3.2 KB)
📄
signal_mipsx.go
(3.07 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.88 KB)
📄
signal_solaris.go
(4.5 KB)
📄
signal_solaris_amd64.go
(2.47 KB)
📄
signal_unix.go
(37.82 KB)
📄
signal_windows.go
(9.2 KB)
📄
signal_windows_test.go
(5.73 KB)
📄
sigqueue.go
(8.76 KB)
📄
sigqueue_note.go
(673 B)
📄
sigqueue_plan9.go
(3.39 KB)
📄
sigtab_aix.go
(11.3 KB)
📄
sigtab_linux_generic.go
(3.56 KB)
📄
sigtab_linux_mipsx.go
(6.01 KB)
📄
sizeclasses.go
(9.14 KB)
📄
sizeof_test.go
(905 B)
📄
slice.go
(8.94 KB)
📄
slice_test.go
(10.32 KB)
📄
softfloat64.go
(10.78 KB)
📄
softfloat64_test.go
(4.05 KB)
📄
stack.go
(41.92 KB)
📄
stack_test.go
(21.05 KB)
📄
string.go
(10.85 KB)
📄
string_test.go
(9.62 KB)
📄
stubs.go
(18.17 KB)
📄
stubs2.go
(1.14 KB)
📄
stubs3.go
(331 B)
📄
stubs_386.go
(550 B)
📄
stubs_amd64.go
(1.2 KB)
📄
stubs_arm.go
(531 B)
📄
stubs_arm64.go
(351 B)
📄
stubs_linux.go
(663 B)
📄
stubs_mips64x.go
(390 B)
📄
stubs_mipsx.go
(305 B)
📄
stubs_nonlinux.go
(315 B)
📄
stubs_ppc64.go
(383 B)
📄
stubs_ppc64le.go
(271 B)
📄
stubs_s390x.go
(256 B)
📄
symtab.go
(32.29 KB)
📄
symtab_test.go
(6.78 KB)
📄
sys_aix_ppc64.s
(7.13 KB)
📄
sys_arm.go
(521 B)
📄
sys_arm64.go
(469 B)
📄
sys_darwin.go
(15.91 KB)
📄
sys_darwin_amd64.s
(18.52 KB)
📄
sys_darwin_arm64.go
(1.68 KB)
📄
sys_darwin_arm64.s
(17.23 KB)
📄
sys_dragonfly_amd64.s
(8.42 KB)
📄
sys_freebsd_386.s
(8.98 KB)
📄
sys_freebsd_amd64.s
(10.55 KB)
📄
sys_freebsd_arm.s
(10.69 KB)
📄
sys_freebsd_arm64.s
(10.33 KB)
📄
sys_libc.go
(1.87 KB)
📄
sys_linux_386.s
(18.17 KB)
📄
sys_linux_amd64.s
(16.25 KB)
📄
sys_linux_arm.s
(15.84 KB)
📄
sys_linux_arm64.s
(15.26 KB)
📄
sys_linux_mips64x.s
(13.4 KB)
📄
sys_linux_mipsx.s
(11.16 KB)
📄
sys_linux_ppc64x.s
(21.48 KB)
📄
sys_linux_riscv64.s
(10.35 KB)
📄
sys_linux_s390x.s
(10.52 KB)
📄
sys_mips64x.go
(526 B)
📄
sys_mipsx.go
(518 B)
📄
sys_netbsd_386.s
(10.13 KB)
📄
sys_netbsd_amd64.s
(9.91 KB)
📄
sys_netbsd_arm.s
(10.94 KB)
📄
sys_netbsd_arm64.s
(10.42 KB)
📄
sys_nonppc64x.go
(271 B)
📄
sys_openbsd.go
(2.3 KB)
📄
sys_openbsd1.go
(1.16 KB)
📄
sys_openbsd2.go
(7.31 KB)
📄
sys_openbsd3.go
(3.29 KB)
📄
sys_openbsd_386.s
(19.97 KB)
📄
sys_openbsd_amd64.s
(16.44 KB)
📄
sys_openbsd_arm.s
(18.09 KB)
📄
sys_openbsd_arm64.s
(15.92 KB)
📄
sys_openbsd_mips64.s
(9.22 KB)
📄
sys_plan9_386.s
(4.4 KB)
📄
sys_plan9_amd64.s
(4.47 KB)
📄
sys_plan9_arm.s
(7.03 KB)
📄
sys_ppc64x.go
(556 B)
📄
sys_riscv64.go
(469 B)
📄
sys_s390x.go
(469 B)
📄
sys_solaris_amd64.s
(6.69 KB)
📄
sys_wasm.go
(732 B)
📄
sys_wasm.s
(2.65 KB)
📄
sys_windows_386.s
(7.74 KB)
📄
sys_windows_amd64.s
(9.16 KB)
📄
sys_windows_arm.s
(12.02 KB)
📄
sys_windows_arm64.s
(12.51 KB)
📄
sys_x86.go
(574 B)
📄
syscall2_solaris.go
(1.65 KB)
📄
syscall_aix.go
(5.99 KB)
📄
syscall_solaris.go
(8.26 KB)
📄
syscall_windows.go
(16.48 KB)
📄
syscall_windows_test.go
(32.53 KB)
📁
testdata
📄
textflag.h
(1.52 KB)
📄
time.go
(30.56 KB)
📄
time_fake.go
(2.38 KB)
📄
time_linux_amd64.s
(2.18 KB)
📄
time_nofake.go
(587 B)
📄
time_test.go
(2.03 KB)
📄
time_windows.h
(694 B)
📄
time_windows_386.s
(1.81 KB)
📄
time_windows_amd64.s
(1.07 KB)
📄
time_windows_arm.s
(2.07 KB)
📄
time_windows_arm64.s
(1.33 KB)
📄
timeasm.go
(468 B)
📄
timestub.go
(595 B)
📄
timestub2.go
(447 B)
📄
tls_arm.s
(3.33 KB)
📄
tls_arm64.h
(1.22 KB)
📄
tls_arm64.s
(1.2 KB)
📄
tls_mips64x.s
(759 B)
📄
tls_mipsx.s
(731 B)
📄
tls_ppc64x.s
(1.52 KB)
📄
tls_riscv64.s
(726 B)
📄
tls_s390x.s
(1.55 KB)
📄
tls_stub.go
(294 B)
📄
tls_windows_amd64.go
(294 B)
📁
trace
📄
trace.go
(38.36 KB)
📄
traceback.go
(46.51 KB)
📄
traceback_test.go
(8.04 KB)
📄
type.go
(18.59 KB)
📄
typekind.go
(742 B)
📄
utf8.go
(3.39 KB)
📄
vdso_elf32.go
(2.79 KB)
📄
vdso_elf64.go
(2.87 KB)
📄
vdso_freebsd.go
(2.46 KB)
📄
vdso_freebsd_arm.go
(454 B)
📄
vdso_freebsd_arm64.go
(443 B)
📄
vdso_freebsd_x86.go
(1.89 KB)
📄
vdso_in_none.go
(490 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_mips64x.go
(892 B)
📄
vdso_linux_ppc64x.go
(712 B)
📄
vlop_386.s
(2.02 KB)
📄
vlop_arm.s
(7.06 KB)
📄
vlop_arm_test.go
(3.75 KB)
📄
vlrt.go
(5.91 KB)
📄
wincallback.go
(3.52 KB)
📄
write_err.go
(310 B)
📄
write_err_android.go
(4.65 KB)
📄
zcallback_windows.go
(155 B)
📄
zcallback_windows.s
(63.05 KB)
📄
zcallback_windows_arm.s
(89.34 KB)
📄
zcallback_windows_arm64.s
(89.34 KB)
Editing: mgcscavenge_test.go
// Copyright 2019 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 ( "fmt" "math/rand" . "runtime" "testing" ) // makePallocData produces an initialized PallocData by setting // the ranges of described in alloc and scavenge. func makePallocData(alloc, scavenged []BitRange) *PallocData { b := new(PallocData) for _, v := range alloc { if v.N == 0 { // Skip N==0. It's harmless and allocRange doesn't // handle this case. continue } b.AllocRange(v.I, v.N) } for _, v := range scavenged { if v.N == 0 { // See the previous loop. continue } b.ScavengedSetRange(v.I, v.N) } return b } func TestFillAligned(t *testing.T) { fillAlignedSlow := func(x uint64, m uint) uint64 { if m == 1 { return x } out := uint64(0) for i := uint(0); i < 64; i += m { for j := uint(0); j < m; j++ { if x&(uint64(1)<<(i+j)) != 0 { out |= ((uint64(1) << m) - 1) << i break } } } return out } check := func(x uint64, m uint) { want := fillAlignedSlow(x, m) if got := FillAligned(x, m); got != want { t.Logf("got: %064b", got) t.Logf("want: %064b", want) t.Errorf("bad fillAligned(%016x, %d)", x, m) } } for m := uint(1); m <= 64; m *= 2 { tests := []uint64{ 0x0000000000000000, 0x00000000ffffffff, 0xffffffff00000000, 0x8000000000000001, 0xf00000000000000f, 0xf00000010050000f, 0xffffffffffffffff, 0x0000000000000001, 0x0000000000000002, 0x0000000000000008, uint64(1) << (m - 1), uint64(1) << m, // Try a few fixed arbitrary examples. 0xb02b9effcf137016, 0x3975a076a9fbff18, 0x0f8c88ec3b81506e, 0x60f14d80ef2fa0e6, } for _, test := range tests { check(test, m) } for i := 0; i < 1000; i++ { // Try a pseudo-random numbers. check(rand.Uint64(), m) if m > 1 { // For m != 1, let's construct a slightly more interesting // random test. Generate a bitmap which is either 0 or // randomly set bits for each m-aligned group of m bits. val := uint64(0) for n := uint(0); n < 64; n += m { // For each group of m bits, flip a coin: // * Leave them as zero. // * Set them randomly. if rand.Uint64()%2 == 0 { val |= (rand.Uint64() & ((1 << m) - 1)) << n } } check(val, m) } } } } func TestPallocDataFindScavengeCandidate(t *testing.T) { type test struct { alloc, scavenged []BitRange min, max uintptr want BitRange } tests := map[string]test{ "MixedMin1": { alloc: []BitRange{{0, 40}, {42, PallocChunkPages - 42}}, scavenged: []BitRange{{0, 41}, {42, PallocChunkPages - 42}}, min: 1, max: PallocChunkPages, want: BitRange{41, 1}, }, "MultiMin1": { alloc: []BitRange{{0, 63}, {65, 20}, {87, PallocChunkPages - 87}}, scavenged: []BitRange{{86, 1}}, min: 1, max: PallocChunkPages, want: BitRange{85, 1}, }, } // Try out different page minimums. for m := uintptr(1); m <= 64; m *= 2 { suffix := fmt.Sprintf("Min%d", m) tests["AllFree"+suffix] = test{ min: m, max: PallocChunkPages, want: BitRange{0, PallocChunkPages}, } tests["AllScavenged"+suffix] = test{ scavenged: []BitRange{{0, PallocChunkPages}}, min: m, max: PallocChunkPages, want: BitRange{0, 0}, } tests["NoneFree"+suffix] = test{ alloc: []BitRange{{0, PallocChunkPages}}, scavenged: []BitRange{{PallocChunkPages / 2, PallocChunkPages / 2}}, min: m, max: PallocChunkPages, want: BitRange{0, 0}, } tests["StartFree"+suffix] = test{ alloc: []BitRange{{uint(m), PallocChunkPages - uint(m)}}, min: m, max: PallocChunkPages, want: BitRange{0, uint(m)}, } tests["EndFree"+suffix] = test{ alloc: []BitRange{{0, PallocChunkPages - uint(m)}}, min: m, max: PallocChunkPages, want: BitRange{PallocChunkPages - uint(m), uint(m)}, } tests["Straddle64"+suffix] = test{ alloc: []BitRange{{0, 64 - uint(m)}, {64 + uint(m), PallocChunkPages - (64 + uint(m))}}, min: m, max: 2 * m, want: BitRange{64 - uint(m), 2 * uint(m)}, } tests["BottomEdge64WithFull"+suffix] = test{ alloc: []BitRange{{64, 64}, {128 + 3*uint(m), PallocChunkPages - (128 + 3*uint(m))}}, scavenged: []BitRange{{1, 10}}, min: m, max: 3 * m, want: BitRange{128, 3 * uint(m)}, } tests["BottomEdge64WithPocket"+suffix] = test{ alloc: []BitRange{{64, 62}, {127, 1}, {128 + 3*uint(m), PallocChunkPages - (128 + 3*uint(m))}}, scavenged: []BitRange{{1, 10}}, min: m, max: 3 * m, want: BitRange{128, 3 * uint(m)}, } tests["Max0"+suffix] = test{ scavenged: []BitRange{{0, PallocChunkPages - uint(m)}}, min: m, max: 0, want: BitRange{PallocChunkPages - uint(m), uint(m)}, } if m <= 8 { tests["OneFree"] = test{ alloc: []BitRange{{0, 40}, {40 + uint(m), PallocChunkPages - (40 + uint(m))}}, min: m, max: PallocChunkPages, want: BitRange{40, uint(m)}, } tests["OneScavenged"] = test{ alloc: []BitRange{{0, 40}, {40 + uint(m), PallocChunkPages - (40 + uint(m))}}, scavenged: []BitRange{{40, 1}}, min: m, max: PallocChunkPages, want: BitRange{0, 0}, } } if m > 1 { tests["MaxUnaligned"+suffix] = test{ scavenged: []BitRange{{0, PallocChunkPages - uint(m*2-1)}}, min: m, max: m - 2, want: BitRange{PallocChunkPages - uint(m), uint(m)}, } tests["SkipSmall"+suffix] = test{ alloc: []BitRange{{0, 64 - uint(m)}, {64, 5}, {70, 11}, {82, PallocChunkPages - 82}}, min: m, max: m, want: BitRange{64 - uint(m), uint(m)}, } tests["SkipMisaligned"+suffix] = test{ alloc: []BitRange{{0, 64 - uint(m)}, {64, 63}, {127 + uint(m), PallocChunkPages - (127 + uint(m))}}, min: m, max: m, want: BitRange{64 - uint(m), uint(m)}, } tests["MaxLessThan"+suffix] = test{ scavenged: []BitRange{{0, PallocChunkPages - uint(m)}}, min: m, max: 1, want: BitRange{PallocChunkPages - uint(m), uint(m)}, } } } if PhysHugePageSize > uintptr(PageSize) { // Check hugepage preserving behavior. bits := uint(PhysHugePageSize / uintptr(PageSize)) if bits < PallocChunkPages { tests["PreserveHugePageBottom"] = test{ alloc: []BitRange{{bits + 2, PallocChunkPages - (bits + 2)}}, min: 1, max: 3, // Make it so that max would have us try to break the huge page. want: BitRange{0, bits + 2}, } if 3*bits < PallocChunkPages { // We need at least 3 huge pages in a chunk for this test to make sense. tests["PreserveHugePageMiddle"] = test{ alloc: []BitRange{{0, bits - 10}, {2*bits + 10, PallocChunkPages - (2*bits + 10)}}, min: 1, max: 12, // Make it so that max would have us try to break the huge page. want: BitRange{bits, bits + 10}, } } tests["PreserveHugePageTop"] = test{ alloc: []BitRange{{0, PallocChunkPages - bits}}, min: 1, max: 1, // Even one page would break a huge page in this case. want: BitRange{PallocChunkPages - bits, bits}, } } else if bits == PallocChunkPages { tests["PreserveHugePageAll"] = test{ min: 1, max: 1, // Even one page would break a huge page in this case. want: BitRange{0, PallocChunkPages}, } } else { // The huge page size is greater than pallocChunkPages, so it should // be effectively disabled. There's no way we can possible scavenge // a huge page out of this bitmap chunk. tests["PreserveHugePageNone"] = test{ min: 1, max: 1, want: BitRange{PallocChunkPages - 1, 1}, } } } for name, v := range tests { v := v t.Run(name, func(t *testing.T) { b := makePallocData(v.alloc, v.scavenged) start, size := b.FindScavengeCandidate(PallocChunkPages-1, v.min, v.max) got := BitRange{start, size} if !(got.N == 0 && v.want.N == 0) && got != v.want { t.Fatalf("candidate mismatch: got %v, want %v", got, v.want) } }) } } // Tests end-to-end scavenging on a pageAlloc. func TestPageAllocScavenge(t *testing.T) { if GOOS == "openbsd" && testing.Short() { t.Skip("skipping because virtual memory is limited; see #36210") } type test struct { request, expect uintptr } minPages := PhysPageSize / PageSize if minPages < 1 { minPages = 1 } type setup struct { beforeAlloc map[ChunkIdx][]BitRange beforeScav map[ChunkIdx][]BitRange expect []test afterScav map[ChunkIdx][]BitRange } tests := map[string]setup{ "AllFreeUnscavExhaust": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 1: {}, BaseChunkIdx + 2: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 1: {}, BaseChunkIdx + 2: {}, }, expect: []test{ {^uintptr(0), 3 * PallocChunkPages * PageSize}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, BaseChunkIdx + 1: {{0, PallocChunkPages}}, BaseChunkIdx + 2: {{0, PallocChunkPages}}, }, }, "NoneFreeUnscavExhaust": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, BaseChunkIdx + 1: {}, BaseChunkIdx + 2: {{0, PallocChunkPages}}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 1: {{0, PallocChunkPages}}, BaseChunkIdx + 2: {}, }, expect: []test{ {^uintptr(0), 0}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 1: {{0, PallocChunkPages}}, BaseChunkIdx + 2: {}, }, }, "ScavHighestPageFirst": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{uint(minPages), PallocChunkPages - uint(2*minPages)}}, }, expect: []test{ {1, minPages * PageSize}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{uint(minPages), PallocChunkPages - uint(minPages)}}, }, }, "ScavMultiple": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{uint(minPages), PallocChunkPages - uint(2*minPages)}}, }, expect: []test{ {minPages * PageSize, minPages * PageSize}, {minPages * PageSize, minPages * PageSize}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, }, }, "ScavMultiple2": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 1: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{uint(minPages), PallocChunkPages - uint(2*minPages)}}, BaseChunkIdx + 1: {{0, PallocChunkPages - uint(2*minPages)}}, }, expect: []test{ {2 * minPages * PageSize, 2 * minPages * PageSize}, {minPages * PageSize, minPages * PageSize}, {minPages * PageSize, minPages * PageSize}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, BaseChunkIdx + 1: {{0, PallocChunkPages}}, }, }, "ScavDiscontiguous": { beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 0xe: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{uint(minPages), PallocChunkPages - uint(2*minPages)}}, BaseChunkIdx + 0xe: {{uint(2 * minPages), PallocChunkPages - uint(2*minPages)}}, }, expect: []test{ {2 * minPages * PageSize, 2 * minPages * PageSize}, {^uintptr(0), 2 * minPages * PageSize}, {^uintptr(0), 0}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, BaseChunkIdx + 0xe: {{0, PallocChunkPages}}, }, }, } if PageAlloc64Bit != 0 { tests["ScavAllVeryDiscontiguous"] = setup{ beforeAlloc: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 0x1000: {}, }, beforeScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {}, BaseChunkIdx + 0x1000: {}, }, expect: []test{ {^uintptr(0), 2 * PallocChunkPages * PageSize}, {^uintptr(0), 0}, }, afterScav: map[ChunkIdx][]BitRange{ BaseChunkIdx: {{0, PallocChunkPages}}, BaseChunkIdx + 0x1000: {{0, PallocChunkPages}}, }, } } for name, v := range tests { v := v runTest := func(t *testing.T, mayUnlock bool) { b := NewPageAlloc(v.beforeAlloc, v.beforeScav) defer FreePageAlloc(b) for iter, h := range v.expect { if got := b.Scavenge(h.request, mayUnlock); got != h.expect { t.Fatalf("bad scavenge #%d: want %d, got %d", iter+1, h.expect, got) } } want := NewPageAlloc(v.beforeAlloc, v.afterScav) defer FreePageAlloc(want) checkPageAlloc(t, want, b) } t.Run(name, func(t *testing.T) { runTest(t, false) }) t.Run(name+"MayUnlock", func(t *testing.T) { runTest(t, true) }) } }
Upload File
Create Folder