X7ROOT File Manager
Current Path:
/opt/golang/1.22.0/src/runtime
opt
/
golang
/
1.22.0
/
src
/
runtime
/
📁
..
📄
HACKING.md
(13.85 KB)
📄
Makefile
(178 B)
📄
abi_test.go
(2.83 KB)
📄
alg.go
(10.99 KB)
📄
align_runtime_test.go
(1.82 KB)
📄
align_test.go
(5.37 KB)
📄
arena.go
(31.66 KB)
📄
arena_test.go
(13.39 KB)
📁
asan
📄
asan.go
(1.55 KB)
📄
asan0.go
(760 B)
📄
asan_amd64.s
(2.45 KB)
📄
asan_arm64.s
(2.14 KB)
📄
asan_loong64.s
(2.12 KB)
📄
asan_ppc64le.s
(2.75 KB)
📄
asan_riscv64.s
(1.92 KB)
📄
asm.s
(719 B)
📄
asm_386.s
(42.54 KB)
📄
asm_amd64.h
(631 B)
📄
asm_amd64.s
(60.09 KB)
📄
asm_arm.s
(31.58 KB)
📄
asm_arm64.s
(43.33 KB)
📄
asm_loong64.s
(27.58 KB)
📄
asm_mips64x.s
(24.34 KB)
📄
asm_mipsx.s
(25.82 KB)
📄
asm_ppc64x.h
(1.93 KB)
📄
asm_ppc64x.s
(45.19 KB)
📄
asm_riscv64.s
(26.97 KB)
📄
asm_s390x.s
(27.55 KB)
📄
asm_wasm.s
(11.82 KB)
📄
atomic_arm64.s
(259 B)
📄
atomic_loong64.s
(245 B)
📄
atomic_mips64x.s
(300 B)
📄
atomic_mipsx.s
(262 B)
📄
atomic_pointer.go
(3.66 KB)
📄
atomic_ppc64x.s
(437 B)
📄
atomic_riscv64.s
(275 B)
📄
auxv_none.go
(298 B)
📄
callers_test.go
(12.13 KB)
📁
cgo
📄
cgo.go
(2.5 KB)
📄
cgo_mmap.go
(2.42 KB)
📄
cgo_ppc64x.go
(418 B)
📄
cgo_sigaction.go
(3.28 KB)
📄
cgocall.go
(23.23 KB)
📄
cgocallback.go
(317 B)
📄
cgocheck.go
(7.97 KB)
📄
chan.go
(23.74 KB)
📄
chan_test.go
(23.44 KB)
📄
chanbarrier_test.go
(1.4 KB)
📄
checkptr.go
(3.29 KB)
📄
checkptr_test.go
(2.86 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)
📄
coro.go
(4.92 KB)
📁
coverage
📄
covercounter.go
(749 B)
📄
covermeta.go
(2.4 KB)
📄
cpuflags.go
(810 B)
📄
cpuflags_amd64.go
(533 B)
📄
cpuflags_arm64.go
(312 B)
📄
cpuprof.go
(7.94 KB)
📄
cputicks.go
(437 B)
📄
crash_cgo_test.go
(23.35 KB)
📄
crash_test.go
(23.12 KB)
📄
crash_unix_test.go
(9.19 KB)
📄
create_file_nounix.go
(305 B)
📄
create_file_unix.go
(368 B)
📁
debug
📄
debug.go
(3.53 KB)
📄
debug_test.go
(7.99 KB)
📄
debugcall.go
(6.75 KB)
📄
debuglog.go
(18.24 KB)
📄
debuglog_off.go
(357 B)
📄
debuglog_on.go
(1.09 KB)
📄
debuglog_test.go
(4.9 KB)
📄
defer_test.go
(11.4 KB)
📄
defs1_linux.go
(845 B)
📄
defs1_netbsd_386.go
(2.91 KB)
📄
defs1_netbsd_amd64.go
(3.14 KB)
📄
defs1_netbsd_arm.go
(3.03 KB)
📄
defs1_netbsd_arm64.go
(3.25 KB)
📄
defs1_solaris_amd64.go
(4.01 KB)
📄
defs2_linux.go
(3.22 KB)
📄
defs3_linux.go
(1.09 KB)
📄
defs_aix.go
(4.17 KB)
📄
defs_aix_ppc64.go
(3.63 KB)
📄
defs_arm_linux.go
(2.67 KB)
📄
defs_darwin.go
(4.18 KB)
📄
defs_darwin_amd64.go
(6.34 KB)
📄
defs_darwin_arm64.go
(4.17 KB)
📄
defs_dragonfly.go
(2.73 KB)
📄
defs_dragonfly_amd64.go
(3.41 KB)
📄
defs_freebsd.go
(3.96 KB)
📄
defs_freebsd_386.go
(4.52 KB)
📄
defs_freebsd_amd64.go
(4.79 KB)
📄
defs_freebsd_arm.go
(3.92 KB)
📄
defs_freebsd_arm64.go
(4.18 KB)
📄
defs_freebsd_riscv64.go
(4.19 KB)
📄
defs_illumos_amd64.go
(285 B)
📄
defs_linux.go
(2.92 KB)
📄
defs_linux_386.go
(4.2 KB)
📄
defs_linux_amd64.go
(4.7 KB)
📄
defs_linux_arm.go
(3.89 KB)
📄
defs_linux_arm64.go
(3.62 KB)
📄
defs_linux_loong64.go
(3.43 KB)
📄
defs_linux_mips64x.go
(3.6 KB)
📄
defs_linux_mipsx.go
(3.6 KB)
📄
defs_linux_ppc64.go
(3.69 KB)
📄
defs_linux_ppc64le.go
(3.69 KB)
📄
defs_linux_riscv64.go
(3.81 KB)
📄
defs_linux_s390x.go
(3.16 KB)
📄
defs_netbsd.go
(2.83 KB)
📄
defs_netbsd_386.go
(855 B)
📄
defs_netbsd_amd64.go
(1.01 KB)
📄
defs_netbsd_arm.go
(764 B)
📄
defs_openbsd.go
(3.06 KB)
📄
defs_openbsd_386.go
(2.91 KB)
📄
defs_openbsd_amd64.go
(3.11 KB)
📄
defs_openbsd_arm.go
(3.03 KB)
📄
defs_openbsd_arm64.go
(2.78 KB)
📄
defs_openbsd_mips64.go
(2.75 KB)
📄
defs_openbsd_ppc64.go
(3 KB)
📄
defs_openbsd_riscv64.go
(2.89 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.32 KB)
📄
defs_solaris_amd64.go
(1004 B)
📄
defs_windows.go
(2.25 KB)
📄
defs_windows_386.go
(2.28 KB)
📄
defs_windows_amd64.go
(3.19 KB)
📄
defs_windows_arm.go
(2.57 KB)
📄
defs_windows_arm64.go
(3.07 KB)
📄
duff_386.s
(8.24 KB)
📄
duff_amd64.s
(5.64 KB)
📄
duff_arm.s
(7.11 KB)
📄
duff_arm64.s
(5.27 KB)
📄
duff_loong64.s
(11.9 KB)
📄
duff_mips64x.s
(11.28 KB)
📄
duff_ppc64x.s
(7.06 KB)
📄
duff_riscv64.s
(11.4 KB)
📄
duff_s390x.s
(507 B)
📄
ehooks_test.go
(2.04 KB)
📄
env_plan9.go
(3 KB)
📄
env_posix.go
(1.56 KB)
📄
env_test.go
(1.16 KB)
📄
error.go
(9.29 KB)
📄
example_test.go
(1.55 KB)
📄
exithook.go
(2.32 KB)
📄
export_aix_test.go
(207 B)
📄
export_arm_test.go
(226 B)
📄
export_darwin_test.go
(207 B)
📄
export_debug_amd64_test.go
(3.6 KB)
📄
export_debug_arm64_test.go
(3.49 KB)
📄
export_debug_ppc64le_test.go
(3.5 KB)
📄
export_debug_test.go
(5.07 KB)
📄
export_debuglog_test.go
(1.27 KB)
📄
export_linux_test.go
(378 B)
📄
export_mmap_test.go
(429 B)
📄
export_pipe2_test.go
(310 B)
📄
export_pipe_test.go
(219 B)
📄
export_test.go
(50.52 KB)
📄
export_unix_test.go
(2.27 KB)
📄
export_windows_test.go
(903 B)
📄
extern.go
(18.58 KB)
📄
fastlog2.go
(1.22 KB)
📄
fastlog2_test.go
(784 B)
📄
fastlog2table.go
(904 B)
📄
fds_nonunix.go
(256 B)
📄
fds_test.go
(1.43 KB)
📄
fds_unix.go
(1.27 KB)
📄
float.go
(1.35 KB)
📄
float_test.go
(699 B)
📄
funcdata.h
(2.53 KB)
📄
gc_test.go
(20.32 KB)
📄
gcinfo_test.go
(5.95 KB)
📄
go_tls.h
(366 B)
📄
hash32.go
(1.58 KB)
📄
hash64.go
(1.95 KB)
📄
hash_test.go
(17.24 KB)
📄
heap_test.go
(529 B)
📄
heapdump.go
(17.88 KB)
📄
histogram.go
(7.3 KB)
📄
histogram_test.go
(3.51 KB)
📄
iface.go
(20.92 KB)
📄
iface_test.go
(7.45 KB)
📄
import_test.go
(1.42 KB)
📄
importx_test.go
(763 B)
📁
internal
📄
lfstack.go
(2.03 KB)
📄
lfstack_test.go
(2.74 KB)
📄
libfuzzer.go
(6.34 KB)
📄
libfuzzer_amd64.s
(5.03 KB)
📄
libfuzzer_arm64.s
(3.15 KB)
📄
lock_futex.go
(5.4 KB)
📄
lock_js.go
(7.28 KB)
📄
lock_sema.go
(6.75 KB)
📄
lock_wasip1.go
(2.01 KB)
📄
lockrank.go
(18.19 KB)
📄
lockrank_off.go
(1.17 KB)
📄
lockrank_on.go
(10.27 KB)
📄
lockrank_test.go
(856 B)
📄
malloc.go
(58.5 KB)
📄
malloc_test.go
(10.64 KB)
📄
map.go
(52.17 KB)
📄
map_benchmark_test.go
(10.59 KB)
📄
map_fast32.go
(12.74 KB)
📄
map_fast64.go
(12.92 KB)
📄
map_faststr.go
(14.32 KB)
📄
map_test.go
(31.75 KB)
📄
mbarrier.go
(13.78 KB)
📄
mbitmap.go
(22.54 KB)
📄
mbitmap_allocheaders.go
(44.67 KB)
📄
mbitmap_noallocheaders.go
(28.95 KB)
📄
mcache.go
(10 KB)
📄
mcentral.go
(8.05 KB)
📄
mcheckmark.go
(2.85 KB)
📄
mem.go
(6.72 KB)
📄
mem_aix.go
(2.01 KB)
📄
mem_bsd.go
(2.21 KB)
📄
mem_darwin.go
(1.96 KB)
📄
mem_js.go
(457 B)
📄
mem_linux.go
(4.98 KB)
📄
mem_plan9.go
(447 B)
📄
mem_sbrk.go
(4.19 KB)
📄
mem_wasip1.go
(392 B)
📄
mem_wasm.go
(488 B)
📄
mem_windows.go
(3.88 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
(843 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.44 KB)
📄
memclr_riscv64.s
(1.71 KB)
📄
memclr_s390x.s
(1.96 KB)
📄
memclr_wasm.s
(485 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.53 KB)
📄
memmove_loong64.s
(1.87 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.91 KB)
📄
memmove_riscv64.s
(5.46 KB)
📄
memmove_s390x.s
(2.92 KB)
📄
memmove_test.go
(21.23 KB)
📄
memmove_wasm.s
(479 B)
📁
metrics
📄
metrics.go
(26.01 KB)
📄
metrics_test.go
(42.46 KB)
📄
mfinal.go
(18.91 KB)
📄
mfinal_test.go
(5.57 KB)
📄
mfixalloc.go
(3.13 KB)
📄
mgc.go
(59.29 KB)
📄
mgclimit.go
(17.28 KB)
📄
mgclimit_test.go
(9.02 KB)
📄
mgcmark.go
(53.07 KB)
📄
mgcpacer.go
(55.36 KB)
📄
mgcpacer_test.go
(39.26 KB)
📄
mgcscavenge.go
(52.32 KB)
📄
mgcscavenge_test.go
(25.2 KB)
📄
mgcstack.go
(10.58 KB)
📄
mgcsweep.go
(32.26 KB)
📄
mgcwork.go
(12.89 KB)
📄
mheap.go
(72.64 KB)
📄
minmax.go
(1.46 KB)
📄
minmax_test.go
(3.31 KB)
📄
mkduff.go
(8.04 KB)
📄
mkfastlog2table.go
(3.08 KB)
📄
mklockrank.go
(9 KB)
📄
mkpreempt.go
(15.33 KB)
📄
mksizeclasses.go
(9.52 KB)
📄
mmap.go
(844 B)
📄
mpagealloc.go
(39.23 KB)
📄
mpagealloc_32bit.go
(4.56 KB)
📄
mpagealloc_64bit.go
(9.34 KB)
📄
mpagealloc_test.go
(32.59 KB)
📄
mpagecache.go
(5.59 KB)
📄
mpagecache_test.go
(10.79 KB)
📄
mpallocbits.go
(12.58 KB)
📄
mpallocbits_test.go
(13.69 KB)
📄
mprof.go
(47.4 KB)
📄
mranges.go
(14.46 KB)
📄
mranges_test.go
(5.68 KB)
📁
msan
📄
msan.go
(1.5 KB)
📄
msan0.go
(725 B)
📄
msan_amd64.s
(2.3 KB)
📄
msan_arm64.s
(1.98 KB)
📄
msan_loong64.s
(1.96 KB)
📄
msize_allocheaders.go
(1.32 KB)
📄
msize_noallocheaders.go
(915 B)
📄
mspanset.go
(13.12 KB)
📄
mstats.go
(33.81 KB)
📄
mwbbuf.go
(8.13 KB)
📄
nbpipe_pipe.go
(405 B)
📄
nbpipe_pipe2.go
(344 B)
📄
nbpipe_pipe_test.go
(706 B)
📄
nbpipe_test.go
(1.99 KB)
📄
net_plan9.go
(645 B)
📄
netpoll.go
(20.55 KB)
📄
netpoll_aix.go
(5.06 KB)
📄
netpoll_epoll.go
(4.4 KB)
📄
netpoll_fake.go
(664 B)
📄
netpoll_kqueue.go
(5.62 KB)
📄
netpoll_os_test.go
(520 B)
📄
netpoll_solaris.go
(11.2 KB)
📄
netpoll_stub.go
(1.48 KB)
📄
netpoll_wasip1.go
(6.08 KB)
📄
netpoll_windows.go
(4.01 KB)
📄
nonwindows_stub.go
(729 B)
📄
norace_linux_test.go
(915 B)
📄
norace_test.go
(983 B)
📄
numcpu_freebsd_test.go
(381 B)
📄
os2_aix.go
(20.88 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.94 KB)
📄
os3_solaris.go
(17.59 KB)
📄
os_aix.go
(8.89 KB)
📄
os_android.go
(463 B)
📄
os_darwin.go
(11.92 KB)
📄
os_darwin_arm64.go
(329 B)
📄
os_dragonfly.go
(7.14 KB)
📄
os_freebsd.go
(11.64 KB)
📄
os_freebsd2.go
(603 B)
📄
os_freebsd_amd64.go
(658 B)
📄
os_freebsd_arm.go
(1.45 KB)
📄
os_freebsd_arm64.go
(320 B)
📄
os_freebsd_noauxv.go
(241 B)
📄
os_freebsd_riscv64.go
(198 B)
📄
os_illumos.go
(3.93 KB)
📄
os_js.go
(767 B)
📄
os_linux.go
(25.71 KB)
📄
os_linux_arm.go
(1.51 KB)
📄
os_linux_arm64.go
(478 B)
📄
os_linux_be64.go
(806 B)
📄
os_linux_generic.go
(870 B)
📄
os_linux_loong64.go
(263 B)
📄
os_linux_mips64x.go
(996 B)
📄
os_linux_mipsx.go
(987 B)
📄
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
(825 B)
📄
os_linux_x86.go
(234 B)
📄
os_netbsd.go
(10.12 KB)
📄
os_netbsd_386.go
(617 B)
📄
os_netbsd_amd64.go
(614 B)
📄
os_netbsd_arm.go
(1.07 KB)
📄
os_netbsd_arm64.go
(769 B)
📄
os_nonopenbsd.go
(437 B)
📄
os_only_solaris.go
(357 B)
📄
os_openbsd.go
(6.23 KB)
📄
os_openbsd_arm.go
(662 B)
📄
os_openbsd_arm64.go
(329 B)
📄
os_openbsd_libc.go
(1.49 KB)
📄
os_openbsd_mips64.go
(329 B)
📄
os_openbsd_syscall.go
(1.36 KB)
📄
os_openbsd_syscall1.go
(441 B)
📄
os_openbsd_syscall2.go
(2.51 KB)
📄
os_plan9.go
(10.18 KB)
📄
os_plan9_arm.go
(375 B)
📄
os_solaris.go
(6.62 KB)
📄
os_unix.go
(436 B)
📄
os_unix_nonlinux.go
(374 B)
📄
os_wasip1.go
(7 KB)
📄
os_wasm.go
(3.15 KB)
📄
os_windows.go
(41.39 KB)
📄
os_windows_arm.go
(511 B)
📄
os_windows_arm64.go
(339 B)
📄
pagetrace_off.go
(550 B)
📄
pagetrace_on.go
(10.36 KB)
📄
panic.go
(41.85 KB)
📄
panic32.go
(4.8 KB)
📄
panic_test.go
(1.71 KB)
📄
panicnil_test.go
(1.25 KB)
📄
pinner.go
(10.98 KB)
📄
pinner_test.go
(11.04 KB)
📄
plugin.go
(4.37 KB)
📁
pprof
📄
preempt.go
(15.03 KB)
📄
preempt_386.s
(824 B)
📄
preempt_amd64.s
(1.67 KB)
📄
preempt_arm.s
(1.49 KB)
📄
preempt_arm64.s
(1.97 KB)
📄
preempt_loong64.s
(2.41 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.92 KB)
📄
proc.go
(204.28 KB)
📄
proc_runtime_test.go
(1.38 KB)
📄
proc_test.go
(25.85 KB)
📄
profbuf.go
(18.26 KB)
📄
profbuf_test.go
(8.54 KB)
📄
proflabel.go
(1.52 KB)
📁
race
📄
race.go
(18.81 KB)
📄
race0.go
(2.79 KB)
📄
race_amd64.s
(13.94 KB)
📄
race_arm64.s
(14.21 KB)
📄
race_ppc64le.s
(15.93 KB)
📄
race_s390x.s
(11.99 KB)
📄
rand.go
(7.11 KB)
📄
rand_test.go
(1.95 KB)
📄
rdebug.go
(550 B)
📄
retry.go
(760 B)
📄
rt0_aix_ppc64.s
(4.09 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_freebsd_riscv64.s
(2.72 KB)
📄
rt0_illumos_amd64.s
(311 B)
📄
rt0_ios_amd64.s
(425 B)
📄
rt0_ios_arm64.s
(425 B)
📄
rt0_js_wasm.s
(1.53 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
(2.01 KB)
📄
rt0_linux_mips64x.s
(1014 B)
📄
rt0_linux_mipsx.s
(797 B)
📄
rt0_linux_ppc64.s
(847 B)
📄
rt0_linux_ppc64le.s
(2.89 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_openbsd_ppc64.s
(370 B)
📄
rt0_openbsd_riscv64.s
(372 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_wasip1_wasm.s
(387 B)
📄
rt0_windows_386.s
(1.28 KB)
📄
rt0_windows_amd64.s
(1.14 KB)
📄
rt0_windows_arm.s
(386 B)
📄
rt0_windows_arm64.s
(733 B)
📄
runtime-gdb.py
(15.44 KB)
📄
runtime-gdb_test.go
(24.04 KB)
📄
runtime-gdb_unix_test.go
(9.4 KB)
📄
runtime-lldb_test.go
(4.95 KB)
📄
runtime-seh_windows_test.go
(4.7 KB)
📄
runtime.go
(7.1 KB)
📄
runtime1.go
(16.66 KB)
📄
runtime2.go
(46.16 KB)
📄
runtime_boring.go
(606 B)
📄
runtime_linux_test.go
(1.77 KB)
📄
runtime_mmap_test.go
(1.77 KB)
📄
runtime_test.go
(11.81 KB)
📄
runtime_unix_test.go
(1.22 KB)
📄
rwmutex.go
(5 KB)
📄
rwmutex_test.go
(4.21 KB)
📄
security_aix.go
(449 B)
📄
security_issetugid.go
(502 B)
📄
security_linux.go
(335 B)
📄
security_nonunix.go
(256 B)
📄
security_test.go
(4.09 KB)
📄
security_unix.go
(818 B)
📄
select.go
(14.82 KB)
📄
sema.go
(18.43 KB)
📄
sema_test.go
(4.21 KB)
📄
semasleep_test.go
(3.46 KB)
📄
sigaction.go
(489 B)
📄
signal_386.go
(1.72 KB)
📄
signal_aix_ppc64.go
(3.54 KB)
📄
signal_amd64.go
(2.73 KB)
📄
signal_arm.go
(2.54 KB)
📄
signal_arm64.go
(3.83 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.24 KB)
📄
signal_freebsd_riscv64.go
(3.08 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.5 KB)
📄
signal_linux_riscv64.go
(2.92 KB)
📄
signal_linux_s390x.go
(4.49 KB)
📄
signal_loong64.go
(3.01 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.39 KB)
📄
signal_openbsd_mips64.go
(3.28 KB)
📄
signal_openbsd_ppc64.go
(3.53 KB)
📄
signal_openbsd_riscv64.go
(3.12 KB)
📄
signal_plan9.go
(1.93 KB)
📄
signal_ppc64x.go
(3.71 KB)
📄
signal_riscv64.go
(2.91 KB)
📄
signal_solaris.go
(4.5 KB)
📄
signal_solaris_amd64.go
(2.47 KB)
📄
signal_unix.go
(44.11 KB)
📄
signal_windows.go
(14.48 KB)
📄
signal_windows_test.go
(8.98 KB)
📄
sigqueue.go
(7.62 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.17 KB)
📄
sizeof_test.go
(1003 B)
📄
slice.go
(11.23 KB)
📄
slice_test.go
(10.32 KB)
📄
softfloat64.go
(11.54 KB)
📄
softfloat64_test.go
(4.04 KB)
📄
stack.go
(40.02 KB)
📄
stack_test.go
(23.14 KB)
📄
start_line_amd64_test.go
(647 B)
📄
start_line_test.go
(2.58 KB)
📄
stkframe.go
(9.88 KB)
📄
string.go
(13.35 KB)
📄
string_test.go
(13.33 KB)
📄
stubs.go
(17.39 KB)
📄
stubs2.go
(1.15 KB)
📄
stubs3.go
(324 B)
📄
stubs_386.go
(708 B)
📄
stubs_amd64.go
(1.38 KB)
📄
stubs_arm.go
(689 B)
📄
stubs_arm64.go
(700 B)
📄
stubs_linux.go
(650 B)
📄
stubs_loong64.go
(638 B)
📄
stubs_mips64x.go
(522 B)
📄
stubs_mipsx.go
(441 B)
📄
stubs_nonlinux.go
(298 B)
📄
stubs_ppc64.go
(302 B)
📄
stubs_ppc64x.go
(688 B)
📄
stubs_riscv64.go
(695 B)
📄
stubs_s390x.go
(414 B)
📄
symtab.go
(34.76 KB)
📄
symtab_test.go
(7.48 KB)
📄
symtabinl.go
(3.81 KB)
📄
symtabinl_test.go
(2.97 KB)
📄
sys_aix_ppc64.s
(7.42 KB)
📄
sys_arm.go
(521 B)
📄
sys_arm64.go
(469 B)
📄
sys_darwin.go
(22.56 KB)
📄
sys_darwin_amd64.s
(19.65 KB)
📄
sys_darwin_arm64.go
(1.74 KB)
📄
sys_darwin_arm64.s
(18.28 KB)
📄
sys_dragonfly_amd64.s
(8.31 KB)
📄
sys_freebsd_386.s
(9.41 KB)
📄
sys_freebsd_amd64.s
(12.67 KB)
📄
sys_freebsd_arm.s
(10.38 KB)
📄
sys_freebsd_arm64.s
(9.49 KB)
📄
sys_freebsd_riscv64.s
(8.92 KB)
📄
sys_libc.go
(1.84 KB)
📄
sys_linux_386.s
(17.89 KB)
📄
sys_linux_amd64.s
(15.74 KB)
📄
sys_linux_arm.s
(13.5 KB)
📄
sys_linux_arm64.s
(16.71 KB)
📄
sys_linux_loong64.s
(14.16 KB)
📄
sys_linux_mips64x.s
(11.96 KB)
📄
sys_linux_mipsx.s
(9.69 KB)
📄
sys_linux_ppc64x.s
(18.09 KB)
📄
sys_linux_riscv64.s
(11.48 KB)
📄
sys_linux_s390x.s
(12.49 KB)
📄
sys_loong64.go
(489 B)
📄
sys_mips64x.go
(500 B)
📄
sys_mipsx.go
(496 B)
📄
sys_netbsd_386.s
(9.61 KB)
📄
sys_netbsd_amd64.s
(9.78 KB)
📄
sys_netbsd_arm.s
(10.58 KB)
📄
sys_netbsd_arm64.s
(9.47 KB)
📄
sys_nonppc64x.go
(245 B)
📄
sys_openbsd.go
(2.59 KB)
📄
sys_openbsd1.go
(1.23 KB)
📄
sys_openbsd2.go
(8.67 KB)
📄
sys_openbsd3.go
(3.37 KB)
📄
sys_openbsd_386.s
(20.4 KB)
📄
sys_openbsd_amd64.s
(15.54 KB)
📄
sys_openbsd_arm.s
(18.46 KB)
📄
sys_openbsd_arm64.s
(15.05 KB)
📄
sys_openbsd_mips64.s
(8.81 KB)
📄
sys_openbsd_ppc64.s
(15.3 KB)
📄
sys_openbsd_riscv64.s
(16.8 KB)
📄
sys_plan9_386.s
(4.48 KB)
📄
sys_plan9_amd64.s
(4.56 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
(758 B)
📄
sys_wasm.s
(1.43 KB)
📄
sys_windows_386.s
(6.46 KB)
📄
sys_windows_amd64.s
(8.41 KB)
📄
sys_windows_arm.s
(7.72 KB)
📄
sys_windows_arm64.s
(6.8 KB)
📄
sys_x86.go
(552 B)
📄
syscall2_solaris.go
(1.85 KB)
📄
syscall_aix.go
(6.33 KB)
📄
syscall_solaris.go
(8.38 KB)
📄
syscall_unix_test.go
(635 B)
📄
syscall_windows.go
(16.57 KB)
📄
syscall_windows_test.go
(32.45 KB)
📄
tagptr.go
(496 B)
📄
tagptr_32bit.go
(927 B)
📄
tagptr_64bit.go
(3.23 KB)
📄
test_amd64.go
(196 B)
📄
test_amd64.s
(316 B)
📄
test_stubs.go
(218 B)
📁
testdata
📄
textflag.h
(1.47 KB)
📄
time.go
(30.57 KB)
📄
time_fake.go
(2.5 KB)
📄
time_linux_amd64.s
(2.02 KB)
📄
time_nofake.go
(709 B)
📄
time_test.go
(2.04 KB)
📄
time_windows.h
(753 B)
📄
time_windows_386.s
(1.71 KB)
📄
time_windows_amd64.s
(786 B)
📄
time_windows_arm.s
(1.97 KB)
📄
time_windows_arm64.s
(906 B)
📄
timeasm.go
(418 B)
📄
timestub.go
(532 B)
📄
timestub2.go
(363 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
(710 B)
📄
tls_ppc64x.s
(1.52 KB)
📄
tls_riscv64.s
(615 B)
📄
tls_s390x.s
(1.55 KB)
📄
tls_stub.go
(260 B)
📄
tls_windows_amd64.go
(294 B)
📁
trace
📄
trace.go
(62.76 KB)
📄
trace2.go
(33.81 KB)
📄
trace2buf.go
(6.58 KB)
📄
trace2cpu.go
(8.87 KB)
📄
trace2event.go
(8.39 KB)
📄
trace2map.go
(4.36 KB)
📄
trace2region.go
(1.68 KB)
📄
trace2runtime.go
(24.2 KB)
📄
trace2stack.go
(9.45 KB)
📄
trace2status.go
(7.24 KB)
📄
trace2string.go
(2.59 KB)
📄
trace2time.go
(3.21 KB)
📄
trace_cgo_test.go
(4.47 KB)
📄
traceback.go
(54.61 KB)
📄
traceback_test.go
(22.95 KB)
📄
tracebackx_test.go
(509 B)
📄
type.go
(12.1 KB)
📄
typekind.go
(743 B)
📄
unsafe.go
(2.97 KB)
📄
unsafepoint_test.go
(3.27 KB)
📄
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
(454 B)
📄
vdso_freebsd_riscv64.go
(429 B)
📄
vdso_freebsd_x86.go
(1.86 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
(659 B)
📄
vdso_test.go
(3.71 KB)
📄
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.06 KB)
📄
zcallback_windows_arm.s
(89.32 KB)
📄
zcallback_windows_arm64.s
(89.32 KB)
Editing: map_test.go
// Copyright 2013 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" "internal/abi" "internal/goarch" "math" "reflect" "runtime" "sort" "strconv" "strings" "sync" "testing" "unsafe" ) func TestHmapSize(t *testing.T) { // The structure of hmap is defined in runtime/map.go // and in cmd/compile/internal/gc/reflect.go and must be in sync. // The size of hmap should be 48 bytes on 64 bit and 28 bytes on 32 bit platforms. var hmapSize = uintptr(8 + 5*goarch.PtrSize) if runtime.RuntimeHmapSize != hmapSize { t.Errorf("sizeof(runtime.hmap{})==%d, want %d", runtime.RuntimeHmapSize, hmapSize) } } // negative zero is a good test because: // 1. 0 and -0 are equal, yet have distinct representations. // 2. 0 is represented as all zeros, -0 isn't. // // I'm not sure the language spec actually requires this behavior, // but it's what the current map implementation does. func TestNegativeZero(t *testing.T) { m := make(map[float64]bool, 0) m[+0.0] = true m[math.Copysign(0.0, -1.0)] = true // should overwrite +0 entry if len(m) != 1 { t.Error("length wrong") } for k := range m { if math.Copysign(1.0, k) > 0 { t.Error("wrong sign") } } m = make(map[float64]bool, 0) m[math.Copysign(0.0, -1.0)] = true m[+0.0] = true // should overwrite -0.0 entry if len(m) != 1 { t.Error("length wrong") } for k := range m { if math.Copysign(1.0, k) < 0 { t.Error("wrong sign") } } } func testMapNan(t *testing.T, m map[float64]int) { if len(m) != 3 { t.Error("length wrong") } s := 0 for k, v := range m { if k == k { t.Error("nan disappeared") } if (v & (v - 1)) != 0 { t.Error("value wrong") } s |= v } if s != 7 { t.Error("values wrong") } } // nan is a good test because nan != nan, and nan has // a randomized hash value. func TestMapAssignmentNan(t *testing.T) { m := make(map[float64]int, 0) nan := math.NaN() // Test assignment. m[nan] = 1 m[nan] = 2 m[nan] = 4 testMapNan(t, m) } // nan is a good test because nan != nan, and nan has // a randomized hash value. func TestMapOperatorAssignmentNan(t *testing.T) { m := make(map[float64]int, 0) nan := math.NaN() // Test assignment operations. m[nan] += 1 m[nan] += 2 m[nan] += 4 testMapNan(t, m) } func TestMapOperatorAssignment(t *testing.T) { m := make(map[int]int, 0) // "m[k] op= x" is rewritten into "m[k] = m[k] op x" // differently when op is / or % than when it isn't. // Simple test to make sure they all work as expected. m[0] = 12345 m[0] += 67890 m[0] /= 123 m[0] %= 456 const want = (12345 + 67890) / 123 % 456 if got := m[0]; got != want { t.Errorf("got %d, want %d", got, want) } } var sinkAppend bool func TestMapAppendAssignment(t *testing.T) { m := make(map[int][]int, 0) m[0] = nil m[0] = append(m[0], 12345) m[0] = append(m[0], 67890) sinkAppend, m[0] = !sinkAppend, append(m[0], 123, 456) a := []int{7, 8, 9, 0} m[0] = append(m[0], a...) want := []int{12345, 67890, 123, 456, 7, 8, 9, 0} if got := m[0]; !reflect.DeepEqual(got, want) { t.Errorf("got %v, want %v", got, want) } } // Maps aren't actually copied on assignment. func TestAlias(t *testing.T) { m := make(map[int]int, 0) m[0] = 5 n := m n[0] = 6 if m[0] != 6 { t.Error("alias didn't work") } } func TestGrowWithNaN(t *testing.T) { m := make(map[float64]int, 4) nan := math.NaN() // Use both assignment and assignment operations as they may // behave differently. m[nan] = 1 m[nan] = 2 m[nan] += 4 cnt := 0 s := 0 growflag := true for k, v := range m { if growflag { // force a hashtable resize for i := 0; i < 50; i++ { m[float64(i)] = i } for i := 50; i < 100; i++ { m[float64(i)] += i } growflag = false } if k != k { cnt++ s |= v } } if cnt != 3 { t.Error("NaN keys lost during grow") } if s != 7 { t.Error("NaN values lost during grow") } } type FloatInt struct { x float64 y int } func TestGrowWithNegativeZero(t *testing.T) { negzero := math.Copysign(0.0, -1.0) m := make(map[FloatInt]int, 4) m[FloatInt{0.0, 0}] = 1 m[FloatInt{0.0, 1}] += 2 m[FloatInt{0.0, 2}] += 4 m[FloatInt{0.0, 3}] = 8 growflag := true s := 0 cnt := 0 negcnt := 0 // The first iteration should return the +0 key. // The subsequent iterations should return the -0 key. // I'm not really sure this is required by the spec, // but it makes sense. // TODO: are we allowed to get the first entry returned again??? for k, v := range m { if v == 0 { continue } // ignore entries added to grow table cnt++ if math.Copysign(1.0, k.x) < 0 { if v&16 == 0 { t.Error("key/value not updated together 1") } negcnt++ s |= v & 15 } else { if v&16 == 16 { t.Error("key/value not updated together 2", k, v) } s |= v } if growflag { // force a hashtable resize for i := 0; i < 100; i++ { m[FloatInt{3.0, i}] = 0 } // then change all the entries // to negative zero m[FloatInt{negzero, 0}] = 1 | 16 m[FloatInt{negzero, 1}] = 2 | 16 m[FloatInt{negzero, 2}] = 4 | 16 m[FloatInt{negzero, 3}] = 8 | 16 growflag = false } } if s != 15 { t.Error("entry missing", s) } if cnt != 4 { t.Error("wrong number of entries returned by iterator", cnt) } if negcnt != 3 { t.Error("update to negzero missed by iteration", negcnt) } } func TestIterGrowAndDelete(t *testing.T) { m := make(map[int]int, 4) for i := 0; i < 100; i++ { m[i] = i } growflag := true for k := range m { if growflag { // grow the table for i := 100; i < 1000; i++ { m[i] = i } // delete all odd keys for i := 1; i < 1000; i += 2 { delete(m, i) } growflag = false } else { if k&1 == 1 { t.Error("odd value returned") } } } } // make sure old bucket arrays don't get GCd while // an iterator is still using them. func TestIterGrowWithGC(t *testing.T) { m := make(map[int]int, 4) for i := 0; i < 8; i++ { m[i] = i } for i := 8; i < 16; i++ { m[i] += i } growflag := true bitmask := 0 for k := range m { if k < 16 { bitmask |= 1 << uint(k) } if growflag { // grow the table for i := 100; i < 1000; i++ { m[i] = i } // trigger a gc runtime.GC() growflag = false } } if bitmask != 1<<16-1 { t.Error("missing key", bitmask) } } func testConcurrentReadsAfterGrowth(t *testing.T, useReflect bool) { t.Parallel() if runtime.GOMAXPROCS(-1) == 1 { defer runtime.GOMAXPROCS(runtime.GOMAXPROCS(16)) } numLoop := 10 numGrowStep := 250 numReader := 16 if testing.Short() { numLoop, numGrowStep = 2, 100 } for i := 0; i < numLoop; i++ { m := make(map[int]int, 0) for gs := 0; gs < numGrowStep; gs++ { m[gs] = gs var wg sync.WaitGroup wg.Add(numReader * 2) for nr := 0; nr < numReader; nr++ { go func() { defer wg.Done() for range m { } }() go func() { defer wg.Done() for key := 0; key < gs; key++ { _ = m[key] } }() if useReflect { wg.Add(1) go func() { defer wg.Done() mv := reflect.ValueOf(m) keys := mv.MapKeys() for _, k := range keys { mv.MapIndex(k) } }() } } wg.Wait() } } } func TestConcurrentReadsAfterGrowth(t *testing.T) { testConcurrentReadsAfterGrowth(t, false) } func TestConcurrentReadsAfterGrowthReflect(t *testing.T) { testConcurrentReadsAfterGrowth(t, true) } func TestBigItems(t *testing.T) { var key [256]string for i := 0; i < 256; i++ { key[i] = "foo" } m := make(map[[256]string][256]string, 4) for i := 0; i < 100; i++ { key[37] = fmt.Sprintf("string%02d", i) m[key] = key } var keys [100]string var values [100]string i := 0 for k, v := range m { keys[i] = k[37] values[i] = v[37] i++ } sort.Strings(keys[:]) sort.Strings(values[:]) for i := 0; i < 100; i++ { if keys[i] != fmt.Sprintf("string%02d", i) { t.Errorf("#%d: missing key: %v", i, keys[i]) } if values[i] != fmt.Sprintf("string%02d", i) { t.Errorf("#%d: missing value: %v", i, values[i]) } } } func TestMapHugeZero(t *testing.T) { type T [4000]byte m := map[int]T{} x := m[0] if x != (T{}) { t.Errorf("map value not zero") } y, ok := m[0] if ok { t.Errorf("map value should be missing") } if y != (T{}) { t.Errorf("map value not zero") } } type empty struct { } func TestEmptyKeyAndValue(t *testing.T) { a := make(map[int]empty, 4) b := make(map[empty]int, 4) c := make(map[empty]empty, 4) a[0] = empty{} b[empty{}] = 0 b[empty{}] = 1 c[empty{}] = empty{} if len(a) != 1 { t.Errorf("empty value insert problem") } if b[empty{}] != 1 { t.Errorf("empty key returned wrong value") } } // Tests a map with a single bucket, with same-lengthed short keys // ("quick keys") as well as long keys. func TestSingleBucketMapStringKeys_DupLen(t *testing.T) { testMapLookups(t, map[string]string{ "x": "x1val", "xx": "x2val", "foo": "fooval", "bar": "barval", // same key length as "foo" "xxxx": "x4val", strings.Repeat("x", 128): "longval1", strings.Repeat("y", 128): "longval2", }) } // Tests a map with a single bucket, with all keys having different lengths. func TestSingleBucketMapStringKeys_NoDupLen(t *testing.T) { testMapLookups(t, map[string]string{ "x": "x1val", "xx": "x2val", "foo": "fooval", "xxxx": "x4val", "xxxxx": "x5val", "xxxxxx": "x6val", strings.Repeat("x", 128): "longval", }) } func testMapLookups(t *testing.T, m map[string]string) { for k, v := range m { if m[k] != v { t.Fatalf("m[%q] = %q; want %q", k, m[k], v) } } } // Tests whether the iterator returns the right elements when // started in the middle of a grow, when the keys are NaNs. func TestMapNanGrowIterator(t *testing.T) { m := make(map[float64]int) nan := math.NaN() const nBuckets = 16 // To fill nBuckets buckets takes LOAD * nBuckets keys. nKeys := int(nBuckets * runtime.HashLoad) // Get map to full point with nan keys. for i := 0; i < nKeys; i++ { m[nan] = i } // Trigger grow m[1.0] = 1 delete(m, 1.0) // Run iterator found := make(map[int]struct{}) for _, v := range m { if v != -1 { if _, repeat := found[v]; repeat { t.Fatalf("repeat of value %d", v) } found[v] = struct{}{} } if len(found) == nKeys/2 { // Halfway through iteration, finish grow. for i := 0; i < nBuckets; i++ { delete(m, 1.0) } } } if len(found) != nKeys { t.Fatalf("missing value") } } func TestMapIterOrder(t *testing.T) { sizes := []int{3, 7, 9, 15} if abi.MapBucketCountBits >= 5 { // it gets flaky (often only one iteration order) at size 3 when abi.MapBucketCountBits >=5. t.Fatalf("This test becomes flaky if abi.MapBucketCountBits(=%d) is 5 or larger", abi.MapBucketCountBits) } for _, n := range sizes { for i := 0; i < 1000; i++ { // Make m be {0: true, 1: true, ..., n-1: true}. m := make(map[int]bool) for i := 0; i < n; i++ { m[i] = true } // Check that iterating over the map produces at least two different orderings. ord := func() []int { var s []int for key := range m { s = append(s, key) } return s } first := ord() ok := false for try := 0; try < 100; try++ { if !reflect.DeepEqual(first, ord()) { ok = true break } } if !ok { t.Errorf("Map with n=%d elements had consistent iteration order: %v", n, first) break } } } } // Issue 8410 func TestMapSparseIterOrder(t *testing.T) { // Run several rounds to increase the probability // of failure. One is not enough. NextRound: for round := 0; round < 10; round++ { m := make(map[int]bool) // Add 1000 items, remove 980. for i := 0; i < 1000; i++ { m[i] = true } for i := 20; i < 1000; i++ { delete(m, i) } var first []int for i := range m { first = append(first, i) } // 800 chances to get a different iteration order. // See bug 8736 for why we need so many tries. for n := 0; n < 800; n++ { idx := 0 for i := range m { if i != first[idx] { // iteration order changed. continue NextRound } idx++ } } t.Fatalf("constant iteration order on round %d: %v", round, first) } } func TestMapStringBytesLookup(t *testing.T) { // Use large string keys to avoid small-allocation coalescing, // which can cause AllocsPerRun to report lower counts than it should. m := map[string]int{ "1000000000000000000000000000000000000000000000000": 1, "2000000000000000000000000000000000000000000000000": 2, } buf := []byte("1000000000000000000000000000000000000000000000000") if x := m[string(buf)]; x != 1 { t.Errorf(`m[string([]byte("1"))] = %d, want 1`, x) } buf[0] = '2' if x := m[string(buf)]; x != 2 { t.Errorf(`m[string([]byte("2"))] = %d, want 2`, x) } var x int n := testing.AllocsPerRun(100, func() { x += m[string(buf)] }) if n != 0 { t.Errorf("AllocsPerRun for m[string(buf)] = %v, want 0", n) } x = 0 n = testing.AllocsPerRun(100, func() { y, ok := m[string(buf)] if !ok { panic("!ok") } x += y }) if n != 0 { t.Errorf("AllocsPerRun for x,ok = m[string(buf)] = %v, want 0", n) } } func TestMapLargeKeyNoPointer(t *testing.T) { const ( I = 1000 N = 64 ) type T [N]int m := make(map[T]int) for i := 0; i < I; i++ { var v T for j := 0; j < N; j++ { v[j] = i + j } m[v] = i } runtime.GC() for i := 0; i < I; i++ { var v T for j := 0; j < N; j++ { v[j] = i + j } if m[v] != i { t.Fatalf("corrupted map: want %+v, got %+v", i, m[v]) } } } func TestMapLargeValNoPointer(t *testing.T) { const ( I = 1000 N = 64 ) type T [N]int m := make(map[int]T) for i := 0; i < I; i++ { var v T for j := 0; j < N; j++ { v[j] = i + j } m[i] = v } runtime.GC() for i := 0; i < I; i++ { var v T for j := 0; j < N; j++ { v[j] = i + j } v1 := m[i] for j := 0; j < N; j++ { if v1[j] != v[j] { t.Fatalf("corrupted map: want %+v, got %+v", v, v1) } } } } // Test that making a map with a large or invalid hint // doesn't panic. (Issue 19926). func TestIgnoreBogusMapHint(t *testing.T) { for _, hint := range []int64{-1, 1 << 62} { _ = make(map[int]int, hint) } } const bs = abi.MapBucketCount // belowOverflow should be a pretty-full pair of buckets; // atOverflow is 1/8 bs larger = 13/8 buckets or two buckets // that are 13/16 full each, which is the overflow boundary. // Adding one to that should ensure overflow to the next higher size. const ( belowOverflow = bs * 3 / 2 // 1.5 bs = 2 buckets @ 75% atOverflow = belowOverflow + bs/8 // 2 buckets at 13/16 fill. ) var mapBucketTests = [...]struct { n int // n is the number of map elements noescape int // number of expected buckets for non-escaping map escape int // number of expected buckets for escaping map }{ {-(1 << 30), 1, 1}, {-1, 1, 1}, {0, 1, 1}, {1, 1, 1}, {bs, 1, 1}, {bs + 1, 2, 2}, {belowOverflow, 2, 2}, // 1.5 bs = 2 buckets @ 75% {atOverflow + 1, 4, 4}, // 13/8 bs + 1 == overflow to 4 {2 * belowOverflow, 4, 4}, // 3 bs = 4 buckets @75% {2*atOverflow + 1, 8, 8}, // 13/4 bs + 1 = overflow to 8 {4 * belowOverflow, 8, 8}, // 6 bs = 8 buckets @ 75% {4*atOverflow + 1, 16, 16}, // 13/2 bs + 1 = overflow to 16 } func TestMapBuckets(t *testing.T) { // Test that maps of different sizes have the right number of buckets. // Non-escaping maps with small buckets (like map[int]int) never // have a nil bucket pointer due to starting with preallocated buckets // on the stack. Escaping maps start with a non-nil bucket pointer if // hint size is above bucketCnt and thereby have more than one bucket. // These tests depend on bucketCnt and loadFactor* in map.go. t.Run("mapliteral", func(t *testing.T) { for _, tt := range mapBucketTests { localMap := map[int]int{} if runtime.MapBucketsPointerIsNil(localMap) { t.Errorf("no escape: buckets pointer is nil for non-escaping map") } for i := 0; i < tt.n; i++ { localMap[i] = i } if got := runtime.MapBucketsCount(localMap); got != tt.noescape { t.Errorf("no escape: n=%d want %d buckets, got %d", tt.n, tt.noescape, got) } escapingMap := runtime.Escape(map[int]int{}) if count := runtime.MapBucketsCount(escapingMap); count > 1 && runtime.MapBucketsPointerIsNil(escapingMap) { t.Errorf("escape: buckets pointer is nil for n=%d buckets", count) } for i := 0; i < tt.n; i++ { escapingMap[i] = i } if got := runtime.MapBucketsCount(escapingMap); got != tt.escape { t.Errorf("escape n=%d want %d buckets, got %d", tt.n, tt.escape, got) } } }) t.Run("nohint", func(t *testing.T) { for _, tt := range mapBucketTests { localMap := make(map[int]int) if runtime.MapBucketsPointerIsNil(localMap) { t.Errorf("no escape: buckets pointer is nil for non-escaping map") } for i := 0; i < tt.n; i++ { localMap[i] = i } if got := runtime.MapBucketsCount(localMap); got != tt.noescape { t.Errorf("no escape: n=%d want %d buckets, got %d", tt.n, tt.noescape, got) } escapingMap := runtime.Escape(make(map[int]int)) if count := runtime.MapBucketsCount(escapingMap); count > 1 && runtime.MapBucketsPointerIsNil(escapingMap) { t.Errorf("escape: buckets pointer is nil for n=%d buckets", count) } for i := 0; i < tt.n; i++ { escapingMap[i] = i } if got := runtime.MapBucketsCount(escapingMap); got != tt.escape { t.Errorf("escape: n=%d want %d buckets, got %d", tt.n, tt.escape, got) } } }) t.Run("makemap", func(t *testing.T) { for _, tt := range mapBucketTests { localMap := make(map[int]int, tt.n) if runtime.MapBucketsPointerIsNil(localMap) { t.Errorf("no escape: buckets pointer is nil for non-escaping map") } for i := 0; i < tt.n; i++ { localMap[i] = i } if got := runtime.MapBucketsCount(localMap); got != tt.noescape { t.Errorf("no escape: n=%d want %d buckets, got %d", tt.n, tt.noescape, got) } escapingMap := runtime.Escape(make(map[int]int, tt.n)) if count := runtime.MapBucketsCount(escapingMap); count > 1 && runtime.MapBucketsPointerIsNil(escapingMap) { t.Errorf("escape: buckets pointer is nil for n=%d buckets", count) } for i := 0; i < tt.n; i++ { escapingMap[i] = i } if got := runtime.MapBucketsCount(escapingMap); got != tt.escape { t.Errorf("escape: n=%d want %d buckets, got %d", tt.n, tt.escape, got) } } }) t.Run("makemap64", func(t *testing.T) { for _, tt := range mapBucketTests { localMap := make(map[int]int, int64(tt.n)) if runtime.MapBucketsPointerIsNil(localMap) { t.Errorf("no escape: buckets pointer is nil for non-escaping map") } for i := 0; i < tt.n; i++ { localMap[i] = i } if got := runtime.MapBucketsCount(localMap); got != tt.noescape { t.Errorf("no escape: n=%d want %d buckets, got %d", tt.n, tt.noescape, got) } escapingMap := runtime.Escape(make(map[int]int, tt.n)) if count := runtime.MapBucketsCount(escapingMap); count > 1 && runtime.MapBucketsPointerIsNil(escapingMap) { t.Errorf("escape: buckets pointer is nil for n=%d buckets", count) } for i := 0; i < tt.n; i++ { escapingMap[i] = i } if got := runtime.MapBucketsCount(escapingMap); got != tt.escape { t.Errorf("escape: n=%d want %d buckets, got %d", tt.n, tt.escape, got) } } }) } func benchmarkMapPop(b *testing.B, n int) { m := map[int]int{} for i := 0; i < b.N; i++ { for j := 0; j < n; j++ { m[j] = j } for j := 0; j < n; j++ { // Use iterator to pop an element. // We want this to be fast, see issue 8412. for k := range m { delete(m, k) break } } } } func BenchmarkMapPop100(b *testing.B) { benchmarkMapPop(b, 100) } func BenchmarkMapPop1000(b *testing.B) { benchmarkMapPop(b, 1000) } func BenchmarkMapPop10000(b *testing.B) { benchmarkMapPop(b, 10000) } var testNonEscapingMapVariable int = 8 func TestNonEscapingMap(t *testing.T) { n := testing.AllocsPerRun(1000, func() { m := map[int]int{} m[0] = 0 }) if n != 0 { t.Fatalf("mapliteral: want 0 allocs, got %v", n) } n = testing.AllocsPerRun(1000, func() { m := make(map[int]int) m[0] = 0 }) if n != 0 { t.Fatalf("no hint: want 0 allocs, got %v", n) } n = testing.AllocsPerRun(1000, func() { m := make(map[int]int, 8) m[0] = 0 }) if n != 0 { t.Fatalf("with small hint: want 0 allocs, got %v", n) } n = testing.AllocsPerRun(1000, func() { m := make(map[int]int, testNonEscapingMapVariable) m[0] = 0 }) if n != 0 { t.Fatalf("with variable hint: want 0 allocs, got %v", n) } } func benchmarkMapAssignInt32(b *testing.B, n int) { a := make(map[int32]int) for i := 0; i < b.N; i++ { a[int32(i&(n-1))] = i } } func benchmarkMapOperatorAssignInt32(b *testing.B, n int) { a := make(map[int32]int) for i := 0; i < b.N; i++ { a[int32(i&(n-1))] += i } } func benchmarkMapAppendAssignInt32(b *testing.B, n int) { a := make(map[int32][]int) b.ReportAllocs() b.ResetTimer() for i := 0; i < b.N; i++ { key := int32(i & (n - 1)) a[key] = append(a[key], i) } } func benchmarkMapDeleteInt32(b *testing.B, n int) { a := make(map[int32]int, n) b.ResetTimer() for i := 0; i < b.N; i++ { if len(a) == 0 { b.StopTimer() for j := i; j < i+n; j++ { a[int32(j)] = j } b.StartTimer() } delete(a, int32(i)) } } func benchmarkMapAssignInt64(b *testing.B, n int) { a := make(map[int64]int) for i := 0; i < b.N; i++ { a[int64(i&(n-1))] = i } } func benchmarkMapOperatorAssignInt64(b *testing.B, n int) { a := make(map[int64]int) for i := 0; i < b.N; i++ { a[int64(i&(n-1))] += i } } func benchmarkMapAppendAssignInt64(b *testing.B, n int) { a := make(map[int64][]int) b.ReportAllocs() b.ResetTimer() for i := 0; i < b.N; i++ { key := int64(i & (n - 1)) a[key] = append(a[key], i) } } func benchmarkMapDeleteInt64(b *testing.B, n int) { a := make(map[int64]int, n) b.ResetTimer() for i := 0; i < b.N; i++ { if len(a) == 0 { b.StopTimer() for j := i; j < i+n; j++ { a[int64(j)] = j } b.StartTimer() } delete(a, int64(i)) } } func benchmarkMapAssignStr(b *testing.B, n int) { k := make([]string, n) for i := 0; i < len(k); i++ { k[i] = strconv.Itoa(i) } b.ResetTimer() a := make(map[string]int) for i := 0; i < b.N; i++ { a[k[i&(n-1)]] = i } } func benchmarkMapOperatorAssignStr(b *testing.B, n int) { k := make([]string, n) for i := 0; i < len(k); i++ { k[i] = strconv.Itoa(i) } b.ResetTimer() a := make(map[string]string) for i := 0; i < b.N; i++ { key := k[i&(n-1)] a[key] += key } } func benchmarkMapAppendAssignStr(b *testing.B, n int) { k := make([]string, n) for i := 0; i < len(k); i++ { k[i] = strconv.Itoa(i) } a := make(map[string][]string) b.ReportAllocs() b.ResetTimer() for i := 0; i < b.N; i++ { key := k[i&(n-1)] a[key] = append(a[key], key) } } func benchmarkMapDeleteStr(b *testing.B, n int) { i2s := make([]string, n) for i := 0; i < n; i++ { i2s[i] = strconv.Itoa(i) } a := make(map[string]int, n) b.ResetTimer() k := 0 for i := 0; i < b.N; i++ { if len(a) == 0 { b.StopTimer() for j := 0; j < n; j++ { a[i2s[j]] = j } k = i b.StartTimer() } delete(a, i2s[i-k]) } } func benchmarkMapDeletePointer(b *testing.B, n int) { i2p := make([]*int, n) for i := 0; i < n; i++ { i2p[i] = new(int) } a := make(map[*int]int, n) b.ResetTimer() k := 0 for i := 0; i < b.N; i++ { if len(a) == 0 { b.StopTimer() for j := 0; j < n; j++ { a[i2p[j]] = j } k = i b.StartTimer() } delete(a, i2p[i-k]) } } func runWith(f func(*testing.B, int), v ...int) func(*testing.B) { return func(b *testing.B) { for _, n := range v { b.Run(strconv.Itoa(n), func(b *testing.B) { f(b, n) }) } } } func BenchmarkMapAssign(b *testing.B) { b.Run("Int32", runWith(benchmarkMapAssignInt32, 1<<8, 1<<16)) b.Run("Int64", runWith(benchmarkMapAssignInt64, 1<<8, 1<<16)) b.Run("Str", runWith(benchmarkMapAssignStr, 1<<8, 1<<16)) } func BenchmarkMapOperatorAssign(b *testing.B) { b.Run("Int32", runWith(benchmarkMapOperatorAssignInt32, 1<<8, 1<<16)) b.Run("Int64", runWith(benchmarkMapOperatorAssignInt64, 1<<8, 1<<16)) b.Run("Str", runWith(benchmarkMapOperatorAssignStr, 1<<8, 1<<16)) } func BenchmarkMapAppendAssign(b *testing.B) { b.Run("Int32", runWith(benchmarkMapAppendAssignInt32, 1<<8, 1<<16)) b.Run("Int64", runWith(benchmarkMapAppendAssignInt64, 1<<8, 1<<16)) b.Run("Str", runWith(benchmarkMapAppendAssignStr, 1<<8, 1<<16)) } func BenchmarkMapDelete(b *testing.B) { b.Run("Int32", runWith(benchmarkMapDeleteInt32, 100, 1000, 10000)) b.Run("Int64", runWith(benchmarkMapDeleteInt64, 100, 1000, 10000)) b.Run("Str", runWith(benchmarkMapDeleteStr, 100, 1000, 10000)) b.Run("Pointer", runWith(benchmarkMapDeletePointer, 100, 1000, 10000)) } func TestDeferDeleteSlow(t *testing.T) { ks := []complex128{0, 1, 2, 3} m := make(map[any]int) for i, k := range ks { m[k] = i } if len(m) != len(ks) { t.Errorf("want %d elements, got %d", len(ks), len(m)) } func() { for _, k := range ks { defer delete(m, k) } }() if len(m) != 0 { t.Errorf("want 0 elements, got %d", len(m)) } } // TestIncrementAfterDeleteValueInt and other test Issue 25936. // Value types int, int32, int64 are affected. Value type string // works as expected. func TestIncrementAfterDeleteValueInt(t *testing.T) { const key1 = 12 const key2 = 13 m := make(map[int]int) m[key1] = 99 delete(m, key1) m[key2]++ if n2 := m[key2]; n2 != 1 { t.Errorf("incremented 0 to %d", n2) } } func TestIncrementAfterDeleteValueInt32(t *testing.T) { const key1 = 12 const key2 = 13 m := make(map[int]int32) m[key1] = 99 delete(m, key1) m[key2]++ if n2 := m[key2]; n2 != 1 { t.Errorf("incremented 0 to %d", n2) } } func TestIncrementAfterDeleteValueInt64(t *testing.T) { const key1 = 12 const key2 = 13 m := make(map[int]int64) m[key1] = 99 delete(m, key1) m[key2]++ if n2 := m[key2]; n2 != 1 { t.Errorf("incremented 0 to %d", n2) } } func TestIncrementAfterDeleteKeyStringValueInt(t *testing.T) { const key1 = "" const key2 = "x" m := make(map[string]int) m[key1] = 99 delete(m, key1) m[key2] += 1 if n2 := m[key2]; n2 != 1 { t.Errorf("incremented 0 to %d", n2) } } func TestIncrementAfterDeleteKeyValueString(t *testing.T) { const key1 = "" const key2 = "x" m := make(map[string]string) m[key1] = "99" delete(m, key1) m[key2] += "1" if n2 := m[key2]; n2 != "1" { t.Errorf("appended '1' to empty (nil) string, got %s", n2) } } // TestIncrementAfterBulkClearKeyStringValueInt tests that map bulk // deletion (mapclear) still works as expected. Note that it was not // affected by Issue 25936. func TestIncrementAfterBulkClearKeyStringValueInt(t *testing.T) { const key1 = "" const key2 = "x" m := make(map[string]int) m[key1] = 99 for k := range m { delete(m, k) } m[key2]++ if n2 := m[key2]; n2 != 1 { t.Errorf("incremented 0 to %d", n2) } } func TestMapTombstones(t *testing.T) { m := map[int]int{} const N = 10000 // Fill a map. for i := 0; i < N; i++ { m[i] = i } runtime.MapTombstoneCheck(m) // Delete half of the entries. for i := 0; i < N; i += 2 { delete(m, i) } runtime.MapTombstoneCheck(m) // Add new entries to fill in holes. for i := N; i < 3*N/2; i++ { m[i] = i } runtime.MapTombstoneCheck(m) // Delete everything. for i := 0; i < 3*N/2; i++ { delete(m, i) } runtime.MapTombstoneCheck(m) } type canString int func (c canString) String() string { return fmt.Sprintf("%d", int(c)) } func TestMapInterfaceKey(t *testing.T) { // Test all the special cases in runtime.typehash. type GrabBag struct { f32 float32 f64 float64 c64 complex64 c128 complex128 s string i0 any i1 interface { String() string } a [4]string } m := map[any]bool{} // Put a bunch of data in m, so that a bad hash is likely to // lead to a bad bucket, which will lead to a missed lookup. for i := 0; i < 1000; i++ { m[i] = true } m[GrabBag{f32: 1.0}] = true if !m[GrabBag{f32: 1.0}] { panic("f32 not found") } m[GrabBag{f64: 1.0}] = true if !m[GrabBag{f64: 1.0}] { panic("f64 not found") } m[GrabBag{c64: 1.0i}] = true if !m[GrabBag{c64: 1.0i}] { panic("c64 not found") } m[GrabBag{c128: 1.0i}] = true if !m[GrabBag{c128: 1.0i}] { panic("c128 not found") } m[GrabBag{s: "foo"}] = true if !m[GrabBag{s: "foo"}] { panic("string not found") } m[GrabBag{i0: "foo"}] = true if !m[GrabBag{i0: "foo"}] { panic("interface{} not found") } m[GrabBag{i1: canString(5)}] = true if !m[GrabBag{i1: canString(5)}] { panic("interface{String() string} not found") } m[GrabBag{a: [4]string{"foo", "bar", "baz", "bop"}}] = true if !m[GrabBag{a: [4]string{"foo", "bar", "baz", "bop"}}] { panic("array not found") } } type panicStructKey struct { sli []int } func (p panicStructKey) String() string { return "panic" } type structKey struct { } func (structKey) String() string { return "structKey" } func TestEmptyMapWithInterfaceKey(t *testing.T) { var ( b bool i int i8 int8 i16 int16 i32 int32 i64 int64 ui uint ui8 uint8 ui16 uint16 ui32 uint32 ui64 uint64 uipt uintptr f32 float32 f64 float64 c64 complex64 c128 complex128 a [4]string s string p *int up unsafe.Pointer ch chan int i0 any i1 interface { String() string } structKey structKey i0Panic any = []int{} i1Panic interface { String() string } = panicStructKey{} panicStructKey = panicStructKey{} sli []int me = map[any]struct{}{} mi = map[interface { String() string }]struct{}{} ) mustNotPanic := func(f func()) { f() } mustPanic := func(f func()) { defer func() { r := recover() if r == nil { t.Errorf("didn't panic") } }() f() } mustNotPanic(func() { _ = me[b] }) mustNotPanic(func() { _ = me[i] }) mustNotPanic(func() { _ = me[i8] }) mustNotPanic(func() { _ = me[i16] }) mustNotPanic(func() { _ = me[i32] }) mustNotPanic(func() { _ = me[i64] }) mustNotPanic(func() { _ = me[ui] }) mustNotPanic(func() { _ = me[ui8] }) mustNotPanic(func() { _ = me[ui16] }) mustNotPanic(func() { _ = me[ui32] }) mustNotPanic(func() { _ = me[ui64] }) mustNotPanic(func() { _ = me[uipt] }) mustNotPanic(func() { _ = me[f32] }) mustNotPanic(func() { _ = me[f64] }) mustNotPanic(func() { _ = me[c64] }) mustNotPanic(func() { _ = me[c128] }) mustNotPanic(func() { _ = me[a] }) mustNotPanic(func() { _ = me[s] }) mustNotPanic(func() { _ = me[p] }) mustNotPanic(func() { _ = me[up] }) mustNotPanic(func() { _ = me[ch] }) mustNotPanic(func() { _ = me[i0] }) mustNotPanic(func() { _ = me[i1] }) mustNotPanic(func() { _ = me[structKey] }) mustPanic(func() { _ = me[i0Panic] }) mustPanic(func() { _ = me[i1Panic] }) mustPanic(func() { _ = me[panicStructKey] }) mustPanic(func() { _ = me[sli] }) mustPanic(func() { _ = me[me] }) mustNotPanic(func() { _ = mi[structKey] }) mustPanic(func() { _ = mi[panicStructKey] }) } func TestLoadFactor(t *testing.T) { for b := uint8(0); b < 20; b++ { count := 13 * (1 << b) / 2 // 6.5 if b == 0 { count = 8 } if runtime.OverLoadFactor(count, b) { t.Errorf("OverLoadFactor(%d,%d)=true, want false", count, b) } if !runtime.OverLoadFactor(count+1, b) { t.Errorf("OverLoadFactor(%d,%d)=false, want true", count+1, b) } } } func TestMapKeys(t *testing.T) { type key struct { s string pad [128]byte // sizeof(key) > abi.MapMaxKeyBytes } m := map[key]int{{s: "a"}: 1, {s: "b"}: 2} keys := make([]key, 0, len(m)) runtime.MapKeys(m, unsafe.Pointer(&keys)) for _, k := range keys { if len(k.s) != 1 { t.Errorf("len(k.s) == %d, want 1", len(k.s)) } } } func TestMapValues(t *testing.T) { type val struct { s string pad [128]byte // sizeof(val) > abi.MapMaxElemBytes } m := map[int]val{1: {s: "a"}, 2: {s: "b"}} vals := make([]val, 0, len(m)) runtime.MapValues(m, unsafe.Pointer(&vals)) for _, v := range vals { if len(v.s) != 1 { t.Errorf("len(v.s) == %d, want 1", len(v.s)) } } }
Upload File
Create Folder