Gecko [ 167.86.127.34 ]

Name	Size	Permission
cgo	[ DIR ]	drwxr-xr-x
debug	[ DIR ]	drwxr-xr-x
internal	[ DIR ]	drwxr-xr-x
msan	[ DIR ]	drwxr-xr-x
pprof	[ DIR ]	drwxr-xr-x
race	[ DIR ]	drwxr-xr-x
testdata	[ DIR ]	drwxr-xr-x
trace	[ DIR ]	drwxr-xr-x
HACKING.md	13.07 KB	-rw-r--r--
Makefile	178 B	-rw-r--r--
alg.go	10.18 KB	-rw-r--r--
asm.s	1.16 KB	-rw-r--r--
asm_386.s	40.2 KB	-rw-r--r--
asm_amd64.s	45.78 KB	-rw-r--r--
asm_arm.s	30.89 KB	-rw-r--r--
asm_arm64.s	33.12 KB	-rw-r--r--
asm_mips64x.s	22.45 KB	-rw-r--r--
asm_mipsx.s	24.72 KB	-rw-r--r--
asm_ppc64x.h	1023 B	-rw-r--r--
asm_ppc64x.s	29.39 KB	-rw-r--r--
asm_riscv64.s	17.38 KB	-rw-r--r--
asm_s390x.s	26.35 KB	-rw-r--r--
asm_wasm.s	9.65 KB	-rw-r--r--
atomic_arm64.s	259 B	-rw-r--r--
atomic_mips64x.s	296 B	-rw-r--r--
atomic_mipsx.s	258 B	-rw-r--r--
atomic_pointer.go	2.62 KB	-rw-r--r--
atomic_ppc64x.s	433 B	-rw-r--r--
atomic_riscv64.s	307 B	-rw-r--r--
auxv_none.go	358 B	-rw-r--r--
callers_test.go	7.7 KB	-rw-r--r--
cgo.go	2.01 KB	-rw-r--r--
cgo_mmap.go	2.38 KB	-rw-r--r--
cgo_ppc64x.go	411 B	-rw-r--r--
cgo_sigaction.go	3.09 KB	-rw-r--r--
cgocall.go	21.38 KB	-rw-r--r--
cgocallback.go	317 B	-rw-r--r--
cgocheck.go	6.8 KB	-rw-r--r--
chan.go	19.71 KB	-rw-r--r--
chan_test.go	21.27 KB	-rw-r--r--
chanbarrier_test.go	1.4 KB	-rw-r--r--
checkptr.go	2.5 KB	-rw-r--r--
checkptr_test.go	1.27 KB	-rw-r--r--
closure_test.go	936 B	-rw-r--r--
compiler.go	413 B	-rw-r--r--
complex.go	1.59 KB	-rw-r--r--
complex_test.go	1.05 KB	-rw-r--r--
cpuflags.go	740 B	-rw-r--r--
cpuflags_amd64.go	533 B	-rw-r--r--
cpuprof.go	6.65 KB	-rw-r--r--
cputicks.go	478 B	-rw-r--r--
crash_cgo_test.go	13.71 KB	-rw-r--r--
crash_nonunix_test.go	385 B	-rw-r--r--
crash_test.go	20.24 KB	-rw-r--r--
crash_unix_test.go	8.89 KB	-rw-r--r--
debug.go	1.63 KB	-rw-r--r--
debug_test.go	6.16 KB	-rw-r--r--
debugcall.go	2.83 KB	-rw-r--r--
debuglog.go	17.08 KB	-rw-r--r--
debuglog_off.go	356 B	-rw-r--r--
debuglog_on.go	1.09 KB	-rw-r--r--
debuglog_test.go	4.56 KB	-rw-r--r--
defer_test.go	9.98 KB	-rw-r--r--
defs1_linux.go	844 B	-rw-r--r--
defs1_netbsd_386.go	2.84 KB	-rw-r--r--
defs1_netbsd_amd64.go	3.07 KB	-rw-r--r--
defs1_netbsd_arm.go	2.96 KB	-rw-r--r--
defs1_netbsd_arm64.go	3.18 KB	-rw-r--r--
defs1_solaris_amd64.go	4.02 KB	-rw-r--r--
defs2_linux.go	3.51 KB	-rw-r--r--
defs3_linux.go	1.09 KB	-rw-r--r--
defs_aix.go	4.16 KB	-rw-r--r--
defs_aix_ppc64.go	3.61 KB	-rw-r--r--
defs_arm_linux.go	2.67 KB	-rw-r--r--
defs_darwin.go	3.84 KB	-rw-r--r--
defs_darwin_386.go	5.98 KB	-rw-r--r--
defs_darwin_amd64.go	6.07 KB	-rw-r--r--
defs_darwin_arm.go	3.78 KB	-rw-r--r--
defs_darwin_arm64.go	3.84 KB	-rw-r--r--
defs_dragonfly.go	2.54 KB	-rw-r--r--
defs_dragonfly_amd64.go	3.25 KB	-rw-r--r--
defs_freebsd.go	3.84 KB	-rw-r--r--
defs_freebsd_386.go	4.35 KB	-rw-r--r--
defs_freebsd_amd64.go	4.62 KB	-rw-r--r--
defs_freebsd_arm.go	3.68 KB	-rw-r--r--
defs_freebsd_arm64.go	4 KB	-rw-r--r--
defs_illumos_amd64.go	285 B	-rw-r--r--
defs_linux.go	3.04 KB	-rw-r--r--
defs_linux_386.go	4.05 KB	-rw-r--r--
defs_linux_amd64.go	4.56 KB	-rw-r--r--
defs_linux_arm.go	3.31 KB	-rw-r--r--
defs_linux_arm64.go	3.23 KB	-rw-r--r--
defs_linux_mips64x.go	3.04 KB	-rw-r--r--
defs_linux_mipsx.go	3.18 KB	-rw-r--r--
defs_linux_ppc64.go	3.28 KB	-rw-r--r--
defs_linux_ppc64le.go	3.28 KB	-rw-r--r--
defs_linux_riscv64.go	3.27 KB	-rw-r--r--
defs_linux_s390x.go	2.76 KB	-rw-r--r--
defs_netbsd.go	2.74 KB	-rw-r--r--
defs_netbsd_386.go	854 B	-rw-r--r--
defs_netbsd_amd64.go	1.01 KB	-rw-r--r--
defs_netbsd_arm.go	763 B	-rw-r--r--
defs_openbsd.go	2.6 KB	-rw-r--r--
defs_openbsd_386.go	2.63 KB	-rw-r--r--
defs_openbsd_amd64.go	2.83 KB	-rw-r--r--
defs_openbsd_arm.go	2.74 KB	-rw-r--r--
defs_openbsd_arm64.go	2.34 KB	-rw-r--r--
defs_plan9_386.go	1.47 KB	-rw-r--r--
defs_plan9_amd64.go	1.66 KB	-rw-r--r--
defs_plan9_arm.go	1.73 KB	-rw-r--r--
defs_solaris.go	3.33 KB	-rw-r--r--
defs_solaris_amd64.go	1003 B	-rw-r--r--
defs_windows.go	2.07 KB	-rw-r--r--
defs_windows_386.go	3.75 KB	-rw-r--r--
defs_windows_amd64.go	4.51 KB	-rw-r--r--
defs_windows_arm.go	3.59 KB	-rw-r--r--
duff_386.s	8.24 KB	-rw-r--r--
duff_amd64.s	5.53 KB	-rw-r--r--
duff_arm.s	7.11 KB	-rw-r--r--
duff_arm64.s	5.25 KB	-rw-r--r--
duff_mips64x.s	11.28 KB	-rw-r--r--
duff_ppc64x.s	2.45 KB	-rw-r--r--
duff_s390x.s	507 B	-rw-r--r--
env_plan9.go	855 B	-rw-r--r--
env_posix.go	1.82 KB	-rw-r--r--
env_test.go	1.28 KB	-rw-r--r--
error.go	7.26 KB	-rw-r--r--
example_test.go	1.34 KB	-rw-r--r--
export_aix_test.go	204 B	-rw-r--r--
export_arm_test.go	226 B	-rw-r--r--
export_darwin_test.go	351 B	-rw-r--r--
export_debug_test.go	5.28 KB	-rw-r--r--
export_debuglog_test.go	1.27 KB	-rw-r--r--
export_futex_test.go	529 B	-rw-r--r--
export_linux_test.go	429 B	-rw-r--r--
export_mmap_test.go	481 B	-rw-r--r--
export_solaris_test.go	282 B	-rw-r--r--
export_test.go	23.58 KB	-rw-r--r--
export_unix_test.go	2.28 KB	-rw-r--r--
export_windows_test.go	652 B	-rw-r--r--
extern.go	11.6 KB	-rw-r--r--
fastlog2.go	1.22 KB	-rw-r--r--
fastlog2_test.go	784 B	-rw-r--r--
fastlog2table.go	904 B	-rw-r--r--
float.go	1.35 KB	-rw-r--r--
funcdata.h	2.44 KB	-rw-r--r--
futex_test.go	2.1 KB	-rw-r--r--
gc_test.go	13.22 KB	-rw-r--r--
gcinfo_test.go	6.18 KB	-rw-r--r--
go_tls.h	366 B	-rw-r--r--
hash32.go	2.51 KB	-rw-r--r--
hash64.go	2.6 KB	-rw-r--r--
hash_test.go	17.54 KB	-rw-r--r--
heapdump.go	17.1 KB	-rw-r--r--
iface.go	15.78 KB	-rw-r--r--
iface_test.go	6.81 KB	-rw-r--r--
lfstack.go	1.77 KB	-rw-r--r--
lfstack_32bit.go	522 B	-rw-r--r--
lfstack_64bit.go	2.15 KB	-rw-r--r--
lfstack_test.go	2.78 KB	-rw-r--r--
libfuzzer.go	2.58 KB	-rw-r--r--
libfuzzer_amd64.s	940 B	-rw-r--r--
libfuzzer_arm64.s	751 B	-rw-r--r--
lock_futex.go	5.06 KB	-rw-r--r--
lock_js.go	5.45 KB	-rw-r--r--
lock_sema.go	6.6 KB	-rw-r--r--
malloc.go	48.32 KB	-rw-r--r--
malloc_test.go	9.37 KB	-rw-r--r--
map.go	42.13 KB	-rw-r--r--
map_benchmark_test.go	10.16 KB	-rw-r--r--
map_fast32.go	12.18 KB	-rw-r--r--
map_fast64.go	12.37 KB	-rw-r--r--
map_faststr.go	13.82 KB	-rw-r--r--
map_test.go	27.11 KB	-rw-r--r--
mbarrier.go	12.14 KB	-rw-r--r--
mbitmap.go	67.53 KB	-rw-r--r--
mcache.go	5.61 KB	-rw-r--r--
mcentral.go	7.14 KB	-rw-r--r--
mem_aix.go	1.93 KB	-rw-r--r--
mem_bsd.go	2.05 KB	-rw-r--r--
mem_darwin.go	1.88 KB	-rw-r--r--
mem_js.go	2.32 KB	-rw-r--r--
mem_linux.go	5.58 KB	-rw-r--r--
mem_plan9.go	4.53 KB	-rw-r--r--
mem_windows.go	3.86 KB	-rw-r--r--
memclr_386.s	2.4 KB	-rw-r--r--
memclr_amd64.s	3.65 KB	-rw-r--r--
memclr_arm.s	2.44 KB	-rw-r--r--
memclr_arm64.s	3.48 KB	-rw-r--r--
memclr_mips64x.s	785 B	-rw-r--r--
memclr_mipsx.s	1.24 KB	-rw-r--r--
memclr_plan9_386.s	905 B	-rw-r--r--
memclr_plan9_amd64.s	433 B	-rw-r--r--
memclr_ppc64x.s	4.2 KB	-rw-r--r--
memclr_riscv64.s	848 B	-rwxr-xr-x
memclr_s390x.s	1.89 KB	-rw-r--r--
memclr_wasm.s	544 B	-rw-r--r--
memmove_386.s	4.45 KB	-rw-r--r--
memmove_amd64.s	12.33 KB	-rw-r--r--
memmove_arm.s	5.9 KB	-rw-r--r--
memmove_arm64.s	3.56 KB	-rw-r--r--
memmove_linux_amd64_test.go	1.61 KB	-rw-r--r--
memmove_mips64x.s	1.82 KB	-rw-r--r--
memmove_mipsx.s	4.39 KB	-rw-r--r--
memmove_plan9_386.s	3.06 KB	-rw-r--r--
memmove_plan9_amd64.s	3.04 KB	-rw-r--r--
memmove_ppc64x.s	3.33 KB	-rw-r--r--
memmove_riscv64.s	1.81 KB	-rwxr-xr-x
memmove_s390x.s	2.92 KB	-rw-r--r--
memmove_test.go	10.97 KB	-rw-r--r--
memmove_wasm.s	1.74 KB	-rw-r--r--
mfinal.go	14.8 KB	-rw-r--r--
mfinal_test.go	5.85 KB	-rw-r--r--
mfixalloc.go	2.72 KB	-rw-r--r--
mgc.go	74.87 KB	-rw-r--r--
mgcmark.go	46.5 KB	-rw-r--r--
mgcscavenge.go	30.95 KB	-rw-r--r--
mgcscavenge_test.go	12.34 KB	-rw-r--r--
mgcstack.go	10.55 KB	-rw-r--r--
mgcsweep.go	14.79 KB	-rw-r--r--
mgcsweepbuf.go	5.98 KB	-rw-r--r--
mgcwork.go	14.24 KB	-rw-r--r--
mheap.go	61.5 KB	-rw-r--r--
mkduff.go	6.23 KB	-rw-r--r--
mkfastlog2table.go	1.32 KB	-rw-r--r--
mkpreempt.go	13.33 KB	-rw-r--r--
mksizeclasses.go	8.62 KB	-rw-r--r--
mmap.go	847 B	-rw-r--r--
mpagealloc.go	35.25 KB	-rw-r--r--
mpagealloc_32bit.go	3.75 KB	-rw-r--r--
mpagealloc_64bit.go	6.51 KB	-rw-r--r--
mpagealloc_test.go	28.88 KB	-rw-r--r--
mpagecache.go	5.03 KB	-rw-r--r--
mpagecache_test.go	9.93 KB	-rw-r--r--
mpallocbits.go	10.69 KB	-rw-r--r--
mpallocbits_test.go	12.93 KB	-rw-r--r--
mprof.go	24.06 KB	-rw-r--r--
mranges.go	5.41 KB	-rw-r--r--
msan.go	1.39 KB	-rw-r--r--
msan0.go	647 B	-rw-r--r--
msan_amd64.s	2.03 KB	-rw-r--r--
msan_arm64.s	1.69 KB	-rw-r--r--
msize.go	785 B	-rw-r--r--
mstats.go	22.62 KB	-rw-r--r--
mwbbuf.go	10.07 KB	-rw-r--r--
nbpipe_fcntl_libc_test.go	463 B	-rw-r--r--
nbpipe_fcntl_unix_test.go	445 B	-rw-r--r--
nbpipe_pipe.go	411 B	-rw-r--r--
nbpipe_pipe2.go	509 B	-rw-r--r--
nbpipe_test.go	2.17 KB	-rw-r--r--
net_plan9.go	645 B	-rw-r--r--
netpoll.go	14.46 KB	-rw-r--r--
netpoll_aix.go	4.64 KB	-rw-r--r--
netpoll_epoll.go	4 KB	-rw-r--r--
netpoll_fake.go	648 B	-rw-r--r--
netpoll_kqueue.go	4.39 KB	-rw-r--r--
netpoll_solaris.go	10.56 KB	-rw-r--r--
netpoll_stub.go	1.3 KB	-rw-r--r--
netpoll_windows.go	4.51 KB	-rw-r--r--
norace_linux_test.go	888 B	-rw-r--r--
norace_test.go	979 B	-rw-r--r--
numcpu_freebsd_test.go	381 B	-rw-r--r--
os2_aix.go	20.67 KB	-rw-r--r--
os2_freebsd.go	302 B	-rw-r--r--
os2_openbsd.go	296 B	-rw-r--r--
os2_plan9.go	1.48 KB	-rw-r--r--
os2_solaris.go	320 B	-rw-r--r--
os3_plan9.go	3.99 KB	-rw-r--r--
os3_solaris.go	16.92 KB	-rw-r--r--
os_aix.go	8.29 KB	-rw-r--r--
os_android.go	463 B	-rw-r--r--
os_darwin.go	10.59 KB	-rw-r--r--
os_darwin_arm.go	749 B	-rw-r--r--
os_darwin_arm64.go	416 B	-rw-r--r--
os_dragonfly.go	6.2 KB	-rw-r--r--
os_freebsd.go	10.97 KB	-rw-r--r--
os_freebsd2.go	478 B	-rw-r--r--
os_freebsd_amd64.go	529 B	-rw-r--r--
os_freebsd_arm.go	1.32 KB	-rw-r--r--
os_freebsd_arm64.go	2.97 KB	-rw-r--r--
os_freebsd_noauxv.go	254 B	-rw-r--r--
os_illumos.go	3.93 KB	-rw-r--r--
os_js.go	2.93 KB	-rw-r--r--
os_linux.go	13.16 KB	-rw-r--r--
os_linux_arm.go	1.35 KB	-rw-r--r--
os_linux_arm64.go	1.02 KB	-rw-r--r--
os_linux_be64.go	816 B	-rw-r--r--
os_linux_generic.go	916 B	-rw-r--r--
os_linux_mips64x.go	999 B	-rw-r--r--
os_linux_mipsx.go	1.05 KB	-rw-r--r--
os_linux_noauxv.go	307 B	-rw-r--r--
os_linux_novdso.go	298 B	-rw-r--r--
os_linux_ppc64x.go	527 B	-rw-r--r--
os_linux_riscv64.go	198 B	-rw-r--r--
os_linux_s390x.go	455 B	-rw-r--r--
os_linux_x86.go	2.69 KB	-rw-r--r--
os_netbsd.go	8.49 KB	-rw-r--r--
os_netbsd_386.go	588 B	-rw-r--r--
os_netbsd_amd64.go	585 B	-rw-r--r--
os_netbsd_arm.go	1.13 KB	-rw-r--r--
os_netbsd_arm64.go	827 B	-rw-r--r--
os_nonopenbsd.go	436 B	-rw-r--r--
os_only_solaris.go	356 B	-rw-r--r--
os_openbsd.go	7.81 KB	-rw-r--r--
os_openbsd_arm.go	749 B	-rw-r--r--
os_openbsd_arm64.go	714 B	-rw-r--r--
os_plan9.go	9.3 KB	-rw-r--r--
os_plan9_arm.go	462 B	-rw-r--r--
os_solaris.go	6.49 KB	-rw-r--r--
os_windows.go	37.01 KB	-rw-r--r--
os_windows_arm.go	511 B	-rw-r--r--
panic.go	42.23 KB	-rw-r--r--
panic32.go	4.79 KB	-rw-r--r--
plugin.go	4.16 KB	-rw-r--r--
preempt.go	14.72 KB	-rw-r--r--
preempt_386.s	983 B	-rw-r--r--
preempt_amd64.s	1.62 KB	-rw-r--r--
preempt_arm.s	1.48 KB	-rw-r--r--
preempt_arm64.s	2.8 KB	-rw-r--r--
preempt_mips64x.s	2.71 KB	-rw-r--r--
preempt_mipsx.s	2.68 KB	-rw-r--r--
preempt_nonwindows.go	289 B	-rw-r--r--
preempt_ppc64x.s	2.71 KB	-rw-r--r--
preempt_riscv64.s	197 B	-rw-r--r--
preempt_s390x.s	1.01 KB	-rw-r--r--
preempt_wasm.s	176 B	-rw-r--r--
print.go	5.98 KB	-rw-r--r--
proc.go	149.75 KB	-rw-r--r--
proc_runtime_test.go	820 B	-rw-r--r--
proc_test.go	22.89 KB	-rw-r--r--
profbuf.go	18.26 KB	-rw-r--r--
profbuf_test.go	8.65 KB	-rw-r--r--
proflabel.go	1.52 KB	-rw-r--r--
race.go	18.11 KB	-rw-r--r--
race0.go	2.61 KB	-rw-r--r--
race_amd64.s	13.59 KB	-rw-r--r--
race_arm64.s	13.53 KB	-rw-r--r--
race_ppc64le.s	17.93 KB	-rw-r--r--
rand_test.go	783 B	-rw-r--r--
rdebug.go	553 B	-rw-r--r--
relax_stub.go	597 B	-rw-r--r--
rt0_aix_ppc64.s	4.33 KB	-rw-r--r--
rt0_android_386.s	822 B	-rw-r--r--
rt0_android_amd64.s	754 B	-rw-r--r--
rt0_android_arm.s	843 B	-rw-r--r--
rt0_android_arm64.s	941 B	-rw-r--r--
rt0_darwin_386.s	452 B	-rw-r--r--
rt0_darwin_amd64.s	399 B	-rw-r--r--
rt0_darwin_arm.s	290 B	-rw-r--r--
rt0_darwin_arm64.s	2.32 KB	-rw-r--r--
rt0_dragonfly_amd64.s	448 B	-rw-r--r--
rt0_freebsd_386.s	454 B	-rw-r--r--
rt0_freebsd_amd64.s	442 B	-rw-r--r--
rt0_freebsd_arm.s	298 B	-rw-r--r--
rt0_freebsd_arm64.s	2.46 KB	-rw-r--r--
rt0_illumos_amd64.s	311 B	-rw-r--r--
rt0_js_wasm.s	2.3 KB	-rw-r--r--
rt0_linux_386.s	450 B	-rw-r--r--
rt0_linux_amd64.s	307 B	-rw-r--r--
rt0_linux_arm.s	1007 B	-rw-r--r--
rt0_linux_arm64.s	2.39 KB	-rw-r--r--
rt0_linux_mips64x.s	1015 B	-rw-r--r--
rt0_linux_mipsx.s	798 B	-rw-r--r--
rt0_linux_ppc64.s	705 B	-rw-r--r--
rt0_linux_ppc64le.s	3.72 KB	-rw-r--r--
rt0_linux_riscv64.s	370 B	-rw-r--r--
rt0_linux_s390x.s	676 B	-rw-r--r--
rt0_netbsd_386.s	452 B	-rw-r--r--
rt0_netbsd_amd64.s	309 B	-rw-r--r--
rt0_netbsd_arm.s	296 B	-rw-r--r--
rt0_netbsd_arm64.s	2.39 KB	-rw-r--r--
rt0_openbsd_386.s	454 B	-rw-r--r--
rt0_openbsd_amd64.s	311 B	-rw-r--r--
rt0_openbsd_arm.s	298 B	-rw-r--r--
rt0_openbsd_arm64.s	2.42 KB	-rw-r--r--
rt0_plan9_386.s	523 B	-rw-r--r--
rt0_plan9_amd64.s	481 B	-rw-r--r--
rt0_plan9_arm.s	397 B	-rw-r--r--
rt0_solaris_amd64.s	311 B	-rw-r--r--
rt0_windows_386.s	1.28 KB	-rw-r--r--
rt0_windows_amd64.s	1.15 KB	-rw-r--r--
rt0_windows_arm.s	386 B	-rw-r--r--
runtime-gdb.py	14.83 KB	-rw-r--r--
runtime-gdb_test.go	16.85 KB	-rw-r--r--
runtime-lldb_test.go	5.09 KB	-rw-r--r--
runtime.go	1.42 KB	-rw-r--r--
runtime1.go	11.97 KB	-rw-r--r--
runtime2.go	37.85 KB	-rw-r--r--
runtime_linux_test.go	1.46 KB	-rw-r--r--
runtime_mmap_test.go	1.82 KB	-rw-r--r--
runtime_test.go	7.81 KB	-rw-r--r--
runtime_unix_test.go	1.2 KB	-rw-r--r--
rwmutex.go	3.4 KB	-rw-r--r--
rwmutex_test.go	4.03 KB	-rw-r--r--
select.go	13.24 KB	-rw-r--r--
sema.go	15.95 KB	-rw-r--r--
sema_test.go	2.41 KB	-rw-r--r--
semasleep_test.go	1.62 KB	-rw-r--r--
sigaction.go	460 B	-rw-r--r--
signal_386.go	2.14 KB	-rw-r--r--
signal_aix_ppc64.go	3.55 KB	-rw-r--r--
signal_amd64.go	2.56 KB	-rw-r--r--
signal_arm.go	2.63 KB	-rw-r--r--
signal_arm64.go	3.12 KB	-rw-r--r--
signal_darwin.go	2.13 KB	-rw-r--r--
signal_darwin_386.go	2.33 KB	-rw-r--r--
signal_darwin_amd64.go	3.85 KB	-rw-r--r--
signal_darwin_arm.go	2.71 KB	-rw-r--r--
signal_darwin_arm64.go	3.6 KB	-rw-r--r--
signal_dragonfly.go	2.17 KB	-rw-r--r--
signal_dragonfly_amd64.go	2.01 KB	-rw-r--r--
signal_freebsd.go	2.2 KB	-rw-r--r--
signal_freebsd_386.go	1.55 KB	-rw-r--r--
signal_freebsd_amd64.go	2.03 KB	-rw-r--r--
signal_freebsd_arm.go	2.18 KB	-rw-r--r--
signal_freebsd_arm64.go	3.23 KB	-rw-r--r--
signal_linux_386.go	1.59 KB	-rw-r--r--
signal_linux_amd64.go	2.05 KB	-rw-r--r--
signal_linux_arm.go	2.13 KB	-rw-r--r--
signal_linux_arm64.go	2.95 KB	-rw-r--r--
signal_linux_mips64x.go	3.35 KB	-rw-r--r--
signal_linux_mipsx.go	3.67 KB	-rw-r--r--
signal_linux_ppc64x.go	3.42 KB	-rw-r--r--
signal_linux_riscv64.go	2.92 KB	-rw-r--r--
signal_linux_s390x.go	4.45 KB	-rw-r--r--
signal_mips64x.go	3.16 KB	-rw-r--r--
signal_mipsx.go	3.05 KB	-rw-r--r--
signal_netbsd.go	2.18 KB	-rw-r--r--
signal_netbsd_386.go	1.76 KB	-rw-r--r--
signal_netbsd_amd64.go	2.33 KB	-rw-r--r--
signal_netbsd_arm.go	2.3 KB	-rw-r--r--
signal_netbsd_arm64.go	3.4 KB	-rw-r--r--
signal_openbsd.go	2.15 KB	-rw-r--r--
signal_openbsd_386.go	1.58 KB	-rw-r--r--
signal_openbsd_amd64.go	2.04 KB	-rw-r--r--
signal_openbsd_arm.go	2.12 KB	-rw-r--r--
signal_openbsd_arm64.go	3.38 KB	-rw-r--r--
signal_plan9.go	1.93 KB	-rw-r--r--
signal_ppc64x.go	3.61 KB	-rw-r--r--
signal_riscv64.go	2.45 KB	-rw-r--r--
signal_solaris.go	4.5 KB	-rw-r--r--
signal_solaris_amd64.go	2.47 KB	-rw-r--r--
signal_unix.go	35.95 KB	-rw-r--r--
signal_windows.go	8.54 KB	-rw-r--r--
signal_windows_test.go	1.6 KB	-rw-r--r--
sigqueue.go	7.69 KB	-rw-r--r--
sigqueue_note.go	654 B	-rw-r--r--
sigqueue_plan9.go	3.31 KB	-rw-r--r--
sigtab_aix.go	11.3 KB	-rw-r--r--
sigtab_linux_generic.go	3.49 KB	-rw-r--r--
sigtab_linux_mipsx.go	5.89 KB	-rw-r--r--
sizeclasses.go	7.9 KB	-rw-r--r--
sizeof_test.go	839 B	-rw-r--r--
slice.go	6.88 KB	-rw-r--r--
slice_test.go	8.78 KB	-rw-r--r--
softfloat64.go	10.7 KB	-rw-r--r--
softfloat64_test.go	4.05 KB	-rw-r--r--
stack.go	39.14 KB	-rw-r--r--
stack_test.go	19.9 KB	-rw-r--r--
string.go	11.52 KB	-rw-r--r--
string_test.go	10.35 KB	-rw-r--r--
stubs.go	13.08 KB	-rw-r--r--
stubs2.go	1.04 KB	-rw-r--r--
stubs3.go	289 B	-rw-r--r--
stubs32.go	393 B	-rw-r--r--
stubs_386.go	490 B	-rw-r--r--
stubs_amd64.go	348 B	-rw-r--r--
stubs_arm.go	454 B	-rw-r--r--
stubs_arm64.go	256 B	-rw-r--r--
stubs_linux.go	646 B	-rw-r--r--
stubs_mips64x.go	283 B	-rw-r--r--
stubs_mipsx.go	279 B	-rw-r--r--
stubs_nonlinux.go	297 B	-rw-r--r--
stubs_ppc64x.go	296 B	-rw-r--r--
stubs_s390x.go	256 B	-rw-r--r--
symtab.go	28.32 KB	-rw-r--r--
symtab_test.go	4.1 KB	-rw-r--r--
sys_aix_ppc64.s	7.17 KB	-rw-r--r--
sys_arm.go	521 B	-rw-r--r--
sys_arm64.go	469 B	-rw-r--r--
sys_darwin.go	15.96 KB	-rw-r--r--
sys_darwin_32.go	533 B	-rw-r--r--
sys_darwin_386.s	18.55 KB	-rw-r--r--
sys_darwin_64.go	513 B	-rw-r--r--
sys_darwin_amd64.s	18.07 KB	-rw-r--r--
sys_darwin_arm.s	13.7 KB	-rw-r--r--
sys_darwin_arm64.s	15.84 KB	-rw-r--r--
sys_dragonfly_amd64.s	8.32 KB	-rw-r--r--
sys_freebsd_386.s	8.92 KB	-rw-r--r--
sys_freebsd_amd64.s	10.72 KB	-rw-r--r--
sys_freebsd_arm.s	10.64 KB	-rw-r--r--
sys_freebsd_arm64.s	10.75 KB	-rw-r--r--
sys_linux_386.s	17.57 KB	-rw-r--r--
sys_linux_amd64.s	17.07 KB	-rw-r--r--
sys_linux_arm.s	14.9 KB	-rw-r--r--
sys_linux_arm64.s	14.32 KB	-rw-r--r--
sys_linux_mips64x.s	12 KB	-rw-r--r--
sys_linux_mipsx.s	11.13 KB	-rw-r--r--
sys_linux_ppc64x.s	14.71 KB	-rw-r--r--
sys_linux_riscv64.s	10.38 KB	-rw-r--r--

Code Editor : mstats.go

// Copyright 2009 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.

// Memory statistics

package runtime

import (
	"runtime/internal/atomic"
	"runtime/internal/sys"
	"unsafe"
)

// Statistics.
// If you edit this structure, also edit type MemStats below.
// Their layouts must match exactly.
//
// For detailed descriptions see the documentation for MemStats.
// Fields that differ from MemStats are further documented here.
//
// Many of these fields are updated on the fly, while others are only
// updated when updatememstats is called.
type mstats struct {
	// General statistics.
	alloc       uint64 // bytes allocated and not yet freed
	total_alloc uint64 // bytes allocated (even if freed)
	sys         uint64 // bytes obtained from system (should be sum of xxx_sys below, no locking, approximate)
	nlookup     uint64 // number of pointer lookups (unused)
	nmalloc     uint64 // number of mallocs
	nfree       uint64 // number of frees

// Statistics about malloc heap.
	// Updated atomically, or with the world stopped.
	//
	// Like MemStats, heap_sys and heap_inuse do not count memory
	// in manually-managed spans.
	heap_alloc    uint64 // bytes allocated and not yet freed (same as alloc above)
	heap_sys      uint64 // virtual address space obtained from system for GC'd heap
	heap_idle     uint64 // bytes in idle spans
	heap_inuse    uint64 // bytes in mSpanInUse spans
	heap_released uint64 // bytes released to the os

// heap_objects is not used by the runtime directly and instead
	// computed on the fly by updatememstats.
	heap_objects uint64 // total number of allocated objects

// Statistics about allocation of low-level fixed-size structures.
	// Protected by FixAlloc locks.
	stacks_inuse uint64 // bytes in manually-managed stack spans; updated atomically or during STW
	stacks_sys   uint64 // only counts newosproc0 stack in mstats; differs from MemStats.StackSys
	mspan_inuse  uint64 // mspan structures
	mspan_sys    uint64
	mcache_inuse uint64 // mcache structures
	mcache_sys   uint64
	buckhash_sys uint64 // profiling bucket hash table
	gc_sys       uint64 // updated atomically or during STW
	other_sys    uint64 // updated atomically or during STW

// Statistics about garbage collector.
	// Protected by mheap or stopping the world during GC.
	next_gc         uint64 // goal heap_live for when next GC ends; ^0 if disabled
	last_gc_unix    uint64 // last gc (in unix time)
	pause_total_ns  uint64
	pause_ns        [256]uint64 // circular buffer of recent gc pause lengths
	pause_end       [256]uint64 // circular buffer of recent gc end times (nanoseconds since 1970)
	numgc           uint32
	numforcedgc     uint32  // number of user-forced GCs
	gc_cpu_fraction float64 // fraction of CPU time used by GC
	enablegc        bool
	debuggc         bool

// Statistics about allocation size classes.

by_size [_NumSizeClasses]struct {
		size    uint32
		nmalloc uint64
		nfree   uint64
	}

// Statistics below here are not exported to MemStats directly.

last_gc_nanotime uint64 // last gc (monotonic time)
	tinyallocs       uint64 // number of tiny allocations that didn't cause actual allocation; not exported to go directly
	last_next_gc     uint64 // next_gc for the previous GC
	last_heap_inuse  uint64 // heap_inuse at mark termination of the previous GC

// triggerRatio is the heap growth ratio that triggers marking.
	//
	// E.g., if this is 0.6, then GC should start when the live
	// heap has reached 1.6 times the heap size marked by the
	// previous cycle. This should be ≤ GOGC/100 so the trigger
	// heap size is less than the goal heap size. This is set
	// during mark termination for the next cycle's trigger.
	triggerRatio float64

// gc_trigger is the heap size that triggers marking.
	//
	// When heap_live ≥ gc_trigger, the mark phase will start.
	// This is also the heap size by which proportional sweeping
	// must be complete.
	//
	// This is computed from triggerRatio during mark termination
	// for the next cycle's trigger.
	gc_trigger uint64

// heap_live is the number of bytes considered live by the GC.
	// That is: retained by the most recent GC plus allocated
	// since then. heap_live <= heap_alloc, since heap_alloc
	// includes unmarked objects that have not yet been swept (and
	// hence goes up as we allocate and down as we sweep) while
	// heap_live excludes these objects (and hence only goes up
	// between GCs).
	//
	// This is updated atomically without locking. To reduce
	// contention, this is updated only when obtaining a span from
	// an mcentral and at this point it counts all of the
	// unallocated slots in that span (which will be allocated
	// before that mcache obtains another span from that
	// mcentral). Hence, it slightly overestimates the "true" live
	// heap size. It's better to overestimate than to
	// underestimate because 1) this triggers the GC earlier than
	// necessary rather than potentially too late and 2) this
	// leads to a conservative GC rate rather than a GC rate that
	// is potentially too low.
	//
	// Reads should likewise be atomic (or during STW).
	//
	// Whenever this is updated, call traceHeapAlloc() and
	// gcController.revise().
	heap_live uint64

// heap_scan is the number of bytes of "scannable" heap. This
	// is the live heap (as counted by heap_live), but omitting
	// no-scan objects and no-scan tails of objects.
	//
	// Whenever this is updated, call gcController.revise().
	heap_scan uint64

// heap_marked is the number of bytes marked by the previous
	// GC. After mark termination, heap_live == heap_marked, but
	// unlike heap_live, heap_marked does not change until the
	// next mark termination.
	heap_marked uint64
}

var memstats mstats

// A MemStats records statistics about the memory allocator.
type MemStats struct {
	// General statistics.

// Alloc is bytes of allocated heap objects.
	//
	// This is the same as HeapAlloc (see below).
	Alloc uint64

// TotalAlloc is cumulative bytes allocated for heap objects.
	//
	// TotalAlloc increases as heap objects are allocated, but
	// unlike Alloc and HeapAlloc, it does not decrease when
	// objects are freed.
	TotalAlloc uint64

// Sys is the total bytes of memory obtained from the OS.
	//
	// Sys is the sum of the XSys fields below. Sys measures the
	// virtual address space reserved by the Go runtime for the
	// heap, stacks, and other internal data structures. It's
	// likely that not all of the virtual address space is backed
	// by physical memory at any given moment, though in general
	// it all was at some point.
	Sys uint64

// Lookups is the number of pointer lookups performed by the
	// runtime.
	//
	// This is primarily useful for debugging runtime internals.
	Lookups uint64

// Mallocs is the cumulative count of heap objects allocated.
	// The number of live objects is Mallocs - Frees.
	Mallocs uint64

// Frees is the cumulative count of heap objects freed.
	Frees uint64

// Heap memory statistics.
	//
	// Interpreting the heap statistics requires some knowledge of
	// how Go organizes memory. Go divides the virtual address
	// space of the heap into "spans", which are contiguous
	// regions of memory 8K or larger. A span may be in one of
	// three states:
	//
	// An "idle" span contains no objects or other data. The
	// physical memory backing an idle span can be released back
	// to the OS (but the virtual address space never is), or it
	// can be converted into an "in use" or "stack" span.
	//
	// An "in use" span contains at least one heap object and may
	// have free space available to allocate more heap objects.
	//
	// A "stack" span is used for goroutine stacks. Stack spans
	// are not considered part of the heap. A span can change
	// between heap and stack memory; it is never used for both
	// simultaneously.

// HeapAlloc is bytes of allocated heap objects.
	//
	// "Allocated" heap objects include all reachable objects, as
	// well as unreachable objects that the garbage collector has
	// not yet freed. Specifically, HeapAlloc increases as heap
	// objects are allocated and decreases as the heap is swept
	// and unreachable objects are freed. Sweeping occurs
	// incrementally between GC cycles, so these two processes
	// occur simultaneously, and as a result HeapAlloc tends to
	// change smoothly (in contrast with the sawtooth that is
	// typical of stop-the-world garbage collectors).
	HeapAlloc uint64

// HeapSys is bytes of heap memory obtained from the OS.
	//
	// HeapSys measures the amount of virtual address space
	// reserved for the heap. This includes virtual address space
	// that has been reserved but not yet used, which consumes no
	// physical memory, but tends to be small, as well as virtual
	// address space for which the physical memory has been
	// returned to the OS after it became unused (see HeapReleased
	// for a measure of the latter).
	//
	// HeapSys estimates the largest size the heap has had.
	HeapSys uint64

// HeapIdle is bytes in idle (unused) spans.
	//
	// Idle spans have no objects in them. These spans could be
	// (and may already have been) returned to the OS, or they can
	// be reused for heap allocations, or they can be reused as
	// stack memory.
	//
	// HeapIdle minus HeapReleased estimates the amount of memory
	// that could be returned to the OS, but is being retained by
	// the runtime so it can grow the heap without requesting more
	// memory from the OS. If this difference is significantly
	// larger than the heap size, it indicates there was a recent
	// transient spike in live heap size.
	HeapIdle uint64

// HeapInuse is bytes in in-use spans.
	//
	// In-use spans have at least one object in them. These spans
	// can only be used for other objects of roughly the same
	// size.
	//
	// HeapInuse minus HeapAlloc estimates the amount of memory
	// that has been dedicated to particular size classes, but is
	// not currently being used. This is an upper bound on
	// fragmentation, but in general this memory can be reused
	// efficiently.
	HeapInuse uint64

// HeapReleased is bytes of physical memory returned to the OS.
	//
	// This counts heap memory from idle spans that was returned
	// to the OS and has not yet been reacquired for the heap.
	HeapReleased uint64

// HeapObjects is the number of allocated heap objects.
	//
	// Like HeapAlloc, this increases as objects are allocated and
	// decreases as the heap is swept and unreachable objects are
	// freed.
	HeapObjects uint64

// Stack memory statistics.
	//
	// Stacks are not considered part of the heap, but the runtime
	// can reuse a span of heap memory for stack memory, and
	// vice-versa.

// StackInuse is bytes in stack spans.
	//
	// In-use stack spans have at least one stack in them. These
	// spans can only be used for other stacks of the same size.
	//
	// There is no StackIdle because unused stack spans are
	// returned to the heap (and hence counted toward HeapIdle).
	StackInuse uint64

// StackSys is bytes of stack memory obtained from the OS.
	//
	// StackSys is StackInuse, plus any memory obtained directly
	// from the OS for OS thread stacks (which should be minimal).
	StackSys uint64

// Off-heap memory statistics.
	//
	// The following statistics measure runtime-internal
	// structures that are not allocated from heap memory (usually
	// because they are part of implementing the heap). Unlike
	// heap or stack memory, any memory allocated to these
	// structures is dedicated to these structures.
	//
	// These are primarily useful for debugging runtime memory
	// overheads.

// MSpanInuse is bytes of allocated mspan structures.
	MSpanInuse uint64

// MSpanSys is bytes of memory obtained from the OS for mspan
	// structures.
	MSpanSys uint64

// MCacheInuse is bytes of allocated mcache structures.
	MCacheInuse uint64

// MCacheSys is bytes of memory obtained from the OS for
	// mcache structures.
	MCacheSys uint64

// BuckHashSys is bytes of memory in profiling bucket hash tables.
	BuckHashSys uint64

// GCSys is bytes of memory in garbage collection metadata.
	GCSys uint64

// OtherSys is bytes of memory in miscellaneous off-heap
	// runtime allocations.
	OtherSys uint64

// Garbage collector statistics.

// NextGC is the target heap size of the next GC cycle.
	//
	// The garbage collector's goal is to keep HeapAlloc ≤ NextGC.
	// At the end of each GC cycle, the target for the next cycle
	// is computed based on the amount of reachable data and the
	// value of GOGC.
	NextGC uint64

// LastGC is the time the last garbage collection finished, as
	// nanoseconds since 1970 (the UNIX epoch).
	LastGC uint64

// PauseTotalNs is the cumulative nanoseconds in GC
	// stop-the-world pauses since the program started.
	//
	// During a stop-the-world pause, all goroutines are paused
	// and only the garbage collector can run.
	PauseTotalNs uint64

// PauseNs is a circular buffer of recent GC stop-the-world
	// pause times in nanoseconds.
	//
	// The most recent pause is at PauseNs[(NumGC+255)%256]. In
	// general, PauseNs[N%256] records the time paused in the most
	// recent N%256th GC cycle. There may be multiple pauses per
	// GC cycle; this is the sum of all pauses during a cycle.
	PauseNs [256]uint64

// PauseEnd is a circular buffer of recent GC pause end times,
	// as nanoseconds since 1970 (the UNIX epoch).
	//
	// This buffer is filled the same way as PauseNs. There may be
	// multiple pauses per GC cycle; this records the end of the
	// last pause in a cycle.
	PauseEnd [256]uint64

// NumGC is the number of completed GC cycles.
	NumGC uint32

// NumForcedGC is the number of GC cycles that were forced by
	// the application calling the GC function.
	NumForcedGC uint32

// GCCPUFraction is the fraction of this program's available
	// CPU time used by the GC since the program started.
	//
	// GCCPUFraction is expressed as a number between 0 and 1,
	// where 0 means GC has consumed none of this program's CPU. A
	// program's available CPU time is defined as the integral of
	// GOMAXPROCS since the program started. That is, if
	// GOMAXPROCS is 2 and a program has been running for 10
	// seconds, its "available CPU" is 20 seconds. GCCPUFraction
	// does not include CPU time used for write barrier activity.
	//
	// This is the same as the fraction of CPU reported by
	// GODEBUG=gctrace=1.
	GCCPUFraction float64

// EnableGC indicates that GC is enabled. It is always true,
	// even if GOGC=off.
	EnableGC bool

// DebugGC is currently unused.
	DebugGC bool

// BySize reports per-size class allocation statistics.
	//
	// BySize[N] gives statistics for allocations of size S where
	// BySize[N-1].Size < S ≤ BySize[N].Size.
	//
	// This does not report allocations larger than BySize[60].Size.
	BySize [61]struct {
		// Size is the maximum byte size of an object in this
		// size class.
		Size uint32

// Mallocs is the cumulative count of heap objects
		// allocated in this size class. The cumulative bytes
		// of allocation is Size*Mallocs. The number of live
		// objects in this size class is Mallocs - Frees.
		Mallocs uint64

// Frees is the cumulative count of heap objects freed
		// in this size class.
		Frees uint64
	}
}

// Size of the trailing by_size array differs between mstats and MemStats,
// and all data after by_size is local to runtime, not exported.
// NumSizeClasses was changed, but we cannot change MemStats because of backward compatibility.
// sizeof_C_MStats is the size of the prefix of mstats that
// corresponds to MemStats. It should match Sizeof(MemStats{}).
var sizeof_C_MStats = unsafe.Offsetof(memstats.by_size) + 61*unsafe.Sizeof(memstats.by_size[0])

func init() {
	var memStats MemStats
	if sizeof_C_MStats != unsafe.Sizeof(memStats) {
		println(sizeof_C_MStats, unsafe.Sizeof(memStats))
		throw("MStats vs MemStatsType size mismatch")
	}

if unsafe.Offsetof(memstats.heap_live)%8 != 0 {
		println(unsafe.Offsetof(memstats.heap_live))
		throw("memstats.heap_live not aligned to 8 bytes")
	}
}

// ReadMemStats populates m with memory allocator statistics.
//
// The returned memory allocator statistics are up to date as of the
// call to ReadMemStats. This is in contrast with a heap profile,
// which is a snapshot as of the most recently completed garbage
// collection cycle.
func ReadMemStats(m *MemStats) {
	stopTheWorld("read mem stats")

systemstack(func() {
		readmemstats_m(m)
	})

startTheWorld()
}

func readmemstats_m(stats *MemStats) {
	updatememstats()

// The size of the trailing by_size array differs between
	// mstats and MemStats. NumSizeClasses was changed, but we
	// cannot change MemStats because of backward compatibility.
	memmove(unsafe.Pointer(stats), unsafe.Pointer(&memstats), sizeof_C_MStats)

// memstats.stacks_sys is only memory mapped directly for OS stacks.
	// Add in heap-allocated stack memory for user consumption.
	stats.StackSys += stats.StackInuse
}

//go:linkname readGCStats runtime/debug.readGCStats
func readGCStats(pauses *[]uint64) {
	systemstack(func() {
		readGCStats_m(pauses)
	})
}

// readGCStats_m must be called on the system stack because it acquires the heap
// lock. See mheap for details.
//go:systemstack
func readGCStats_m(pauses *[]uint64) {
	p := *pauses
	// Calling code in runtime/debug should make the slice large enough.
	if cap(p) < len(memstats.pause_ns)+3 {
		throw("short slice passed to readGCStats")
	}

// Pass back: pauses, pause ends, last gc (absolute time), number of gc, total pause ns.
	lock(&mheap_.lock)

n := memstats.numgc
	if n > uint32(len(memstats.pause_ns)) {
		n = uint32(len(memstats.pause_ns))
	}

// The pause buffer is circular. The most recent pause is at
	// pause_ns[(numgc-1)%len(pause_ns)], and then backward
	// from there to go back farther in time. We deliver the times
	// most recent first (in p[0]).
	p = p[:cap(p)]
	for i := uint32(0); i < n; i++ {
		j := (memstats.numgc - 1 - i) % uint32(len(memstats.pause_ns))
		p[i] = memstats.pause_ns[j]
		p[n+i] = memstats.pause_end[j]
	}

p[n+n] = memstats.last_gc_unix
	p[n+n+1] = uint64(memstats.numgc)
	p[n+n+2] = memstats.pause_total_ns
	unlock(&mheap_.lock)
	*pauses = p[:n+n+3]
}

//go:nowritebarrier
func updatememstats() {
	memstats.mcache_inuse = uint64(mheap_.cachealloc.inuse)
	memstats.mspan_inuse = uint64(mheap_.spanalloc.inuse)
	memstats.sys = memstats.heap_sys + memstats.stacks_sys + memstats.mspan_sys +
		memstats.mcache_sys + memstats.buckhash_sys + memstats.gc_sys + memstats.other_sys

// We also count stacks_inuse as sys memory.
	memstats.sys += memstats.stacks_inuse

// Calculate memory allocator stats.
	// During program execution we only count number of frees and amount of freed memory.
	// Current number of alive object in the heap and amount of alive heap memory
	// are calculated by scanning all spans.
	// Total number of mallocs is calculated as number of frees plus number of alive objects.
	// Similarly, total amount of allocated memory is calculated as amount of freed memory
	// plus amount of alive heap memory.
	memstats.alloc = 0
	memstats.total_alloc = 0
	memstats.nmalloc = 0
	memstats.nfree = 0
	for i := 0; i < len(memstats.by_size); i++ {
		memstats.by_size[i].nmalloc = 0
		memstats.by_size[i].nfree = 0
	}

// Flush mcache's to mcentral.
	systemstack(flushallmcaches)

// Aggregate local stats.
	cachestats()

// Collect allocation stats. This is safe and consistent
	// because the world is stopped.
	var smallFree, totalAlloc, totalFree uint64
	// Collect per-spanclass stats.
	for spc := range mheap_.central {
		// The mcaches are now empty, so mcentral stats are
		// up-to-date.
		c := &mheap_.central[spc].mcentral
		memstats.nmalloc += c.nmalloc
		i := spanClass(spc).sizeclass()
		memstats.by_size[i].nmalloc += c.nmalloc
		totalAlloc += c.nmalloc * uint64(class_to_size[i])
	}
	// Collect per-sizeclass stats.
	for i := 0; i < _NumSizeClasses; i++ {
		if i == 0 {
			memstats.nmalloc += mheap_.nlargealloc
			totalAlloc += mheap_.largealloc
			totalFree += mheap_.largefree
			memstats.nfree += mheap_.nlargefree
			continue
		}

// The mcache stats have been flushed to mheap_.
		memstats.nfree += mheap_.nsmallfree[i]
		memstats.by_size[i].nfree = mheap_.nsmallfree[i]
		smallFree += mheap_.nsmallfree[i] * uint64(class_to_size[i])
	}
	totalFree += smallFree

memstats.nfree += memstats.tinyallocs
	memstats.nmalloc += memstats.tinyallocs

// Calculate derived stats.
	memstats.total_alloc = totalAlloc
	memstats.alloc = totalAlloc - totalFree
	memstats.heap_alloc = memstats.alloc
	memstats.heap_objects = memstats.nmalloc - memstats.nfree
}

// cachestats flushes all mcache stats.
//
// The world must be stopped.
//
//go:nowritebarrier
func cachestats() {
	for _, p := range allp {
		c := p.mcache
		if c == nil {
			continue
		}
		purgecachedstats(c)
	}
}

// flushmcache flushes the mcache of allp[i].
//
// The world must be stopped.
//
//go:nowritebarrier
func flushmcache(i int) {
	p := allp[i]
	c := p.mcache
	if c == nil {
		return
	}
	c.releaseAll()
	stackcache_clear(c)
}

// flushallmcaches flushes the mcaches of all Ps.
//
// The world must be stopped.
//
//go:nowritebarrier
func flushallmcaches() {
	for i := 0; i < int(gomaxprocs); i++ {
		flushmcache(i)
	}
}

//go:nosplit
func purgecachedstats(c *mcache) {
	// Protected by either heap or GC lock.
	h := &mheap_
	memstats.heap_scan += uint64(c.local_scan)
	c.local_scan = 0
	memstats.tinyallocs += uint64(c.local_tinyallocs)
	c.local_tinyallocs = 0
	h.largefree += uint64(c.local_largefree)
	c.local_largefree = 0
	h.nlargefree += uint64(c.local_nlargefree)
	c.local_nlargefree = 0
	for i := 0; i < len(c.local_nsmallfree); i++ {
		h.nsmallfree[i] += uint64(c.local_nsmallfree[i])
		c.local_nsmallfree[i] = 0
	}
}

// Atomically increases a given *system* memory stat. We are counting on this
// stat never overflowing a uintptr, so this function must only be used for
// system memory stats.
//
// The current implementation for little endian architectures is based on
// xadduintptr(), which is less than ideal: xadd64() should really be used.
// Using xadduintptr() is a stop-gap solution until arm supports xadd64() that
// doesn't use locks.  (Locks are a problem as they require a valid G, which
// restricts their useability.)
//
// A side-effect of using xadduintptr() is that we need to check for
// overflow errors.
//go:nosplit
func mSysStatInc(sysStat *uint64, n uintptr) {
	if sysStat == nil {
		return
	}
	if sys.BigEndian {
		atomic.Xadd64(sysStat, int64(n))
		return
	}
	if val := atomic.Xadduintptr((*uintptr)(unsafe.Pointer(sysStat)), n); val < n {
		print("runtime: stat overflow: val ", val, ", n ", n, "\n")
		exit(2)
	}
}

// Atomically decreases a given *system* memory stat. Same comments as
// mSysStatInc apply.
//go:nosplit
func mSysStatDec(sysStat *uint64, n uintptr) {
	if sysStat == nil {
		return
	}
	if sys.BigEndian {
		atomic.Xadd64(sysStat, -int64(n))
		return
	}
	if val := atomic.Xadduintptr((*uintptr)(unsafe.Pointer(sysStat)), uintptr(-int64(n))); val+n < n {
		print("runtime: stat underflow: val ", val, ", n ", n, "\n")
		exit(2)
	}
}

${this.title}

Code Editor : mstats.go