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 : syscall_windows_test.go

// Copyright 2010 The Go Authors. All rights reserved.
// Use of this source code is governed by a BSD-style
// license that can be found in the LICENSE file.

package runtime_test

import (
	"bytes"
	"fmt"
	"internal/syscall/windows/sysdll"
	"internal/testenv"
	"io/ioutil"
	"math"
	"os"
	"os/exec"
	"path/filepath"
	"runtime"
	"strconv"
	"strings"
	"syscall"
	"testing"
	"unsafe"
)

type DLL struct {
	*syscall.DLL
	t *testing.T
}

func GetDLL(t *testing.T, name string) *DLL {
	d, e := syscall.LoadDLL(name)
	if e != nil {
		t.Fatal(e)
	}
	return &DLL{DLL: d, t: t}
}

func (d *DLL) Proc(name string) *syscall.Proc {
	p, e := d.FindProc(name)
	if e != nil {
		d.t.Fatal(e)
	}
	return p
}

func TestStdCall(t *testing.T) {
	type Rect struct {
		left, top, right, bottom int32
	}
	res := Rect{}
	expected := Rect{1, 1, 40, 60}
	a, _, _ := GetDLL(t, "user32.dll").Proc("UnionRect").Call(
		uintptr(unsafe.Pointer(&res)),
		uintptr(unsafe.Pointer(&Rect{10, 1, 14, 60})),
		uintptr(unsafe.Pointer(&Rect{1, 2, 40, 50})))
	if a != 1 || res.left != expected.left ||
		res.top != expected.top ||
		res.right != expected.right ||
		res.bottom != expected.bottom {
		t.Error("stdcall USER32.UnionRect returns", a, "res=", res)
	}
}

func Test64BitReturnStdCall(t *testing.T) {

const (
		VER_BUILDNUMBER      = 0x0000004
		VER_MAJORVERSION     = 0x0000002
		VER_MINORVERSION     = 0x0000001
		VER_PLATFORMID       = 0x0000008
		VER_PRODUCT_TYPE     = 0x0000080
		VER_SERVICEPACKMAJOR = 0x0000020
		VER_SERVICEPACKMINOR = 0x0000010
		VER_SUITENAME        = 0x0000040

VER_EQUAL         = 1
		VER_GREATER       = 2
		VER_GREATER_EQUAL = 3
		VER_LESS          = 4
		VER_LESS_EQUAL    = 5

ERROR_OLD_WIN_VERSION syscall.Errno = 1150
	)

type OSVersionInfoEx struct {
		OSVersionInfoSize uint32
		MajorVersion      uint32
		MinorVersion      uint32
		BuildNumber       uint32
		PlatformId        uint32
		CSDVersion        [128]uint16
		ServicePackMajor  uint16
		ServicePackMinor  uint16
		SuiteMask         uint16
		ProductType       byte
		Reserve           byte
	}

d := GetDLL(t, "kernel32.dll")

var m1, m2 uintptr
	VerSetConditionMask := d.Proc("VerSetConditionMask")
	m1, m2, _ = VerSetConditionMask.Call(m1, m2, VER_MAJORVERSION, VER_GREATER_EQUAL)
	m1, m2, _ = VerSetConditionMask.Call(m1, m2, VER_MINORVERSION, VER_GREATER_EQUAL)
	m1, m2, _ = VerSetConditionMask.Call(m1, m2, VER_SERVICEPACKMAJOR, VER_GREATER_EQUAL)
	m1, m2, _ = VerSetConditionMask.Call(m1, m2, VER_SERVICEPACKMINOR, VER_GREATER_EQUAL)

vi := OSVersionInfoEx{
		MajorVersion:     5,
		MinorVersion:     1,
		ServicePackMajor: 2,
		ServicePackMinor: 0,
	}
	vi.OSVersionInfoSize = uint32(unsafe.Sizeof(vi))
	r, _, e2 := d.Proc("VerifyVersionInfoW").Call(
		uintptr(unsafe.Pointer(&vi)),
		VER_MAJORVERSION|VER_MINORVERSION|VER_SERVICEPACKMAJOR|VER_SERVICEPACKMINOR,
		m1, m2)
	if r == 0 && e2 != ERROR_OLD_WIN_VERSION {
		t.Errorf("VerifyVersionInfo failed: %s", e2)
	}
}

func TestCDecl(t *testing.T) {
	var buf [50]byte
	fmtp, _ := syscall.BytePtrFromString("%d %d %d")
	a, _, _ := GetDLL(t, "user32.dll").Proc("wsprintfA").Call(
		uintptr(unsafe.Pointer(&buf[0])),
		uintptr(unsafe.Pointer(fmtp)),
		1000, 2000, 3000)
	if string(buf[:a]) != "1000 2000 3000" {
		t.Error("cdecl USER32.wsprintfA returns", a, "buf=", buf[:a])
	}
}

func TestEnumWindows(t *testing.T) {
	d := GetDLL(t, "user32.dll")
	isWindows := d.Proc("IsWindow")
	counter := 0
	cb := syscall.NewCallback(func(hwnd syscall.Handle, lparam uintptr) uintptr {
		if lparam != 888 {
			t.Error("lparam was not passed to callback")
		}
		b, _, _ := isWindows.Call(uintptr(hwnd))
		if b == 0 {
			t.Error("USER32.IsWindow returns FALSE")
		}
		counter++
		return 1 // continue enumeration
	})
	a, _, _ := d.Proc("EnumWindows").Call(cb, 888)
	if a == 0 {
		t.Error("USER32.EnumWindows returns FALSE")
	}
	if counter == 0 {
		t.Error("Callback has been never called or your have no windows")
	}
}

func callback(timeFormatString unsafe.Pointer, lparam uintptr) uintptr {
	(*(*func())(unsafe.Pointer(&lparam)))()
	return 0 // stop enumeration
}

// nestedCall calls into Windows, back into Go, and finally to f.
func nestedCall(t *testing.T, f func()) {
	c := syscall.NewCallback(callback)
	d := GetDLL(t, "kernel32.dll")
	defer d.Release()
	const LOCALE_NAME_USER_DEFAULT = 0
	d.Proc("EnumTimeFormatsEx").Call(c, LOCALE_NAME_USER_DEFAULT, 0, uintptr(*(*unsafe.Pointer)(unsafe.Pointer(&f))))
}

func TestCallback(t *testing.T) {
	var x = false
	nestedCall(t, func() { x = true })
	if !x {
		t.Fatal("nestedCall did not call func")
	}
}

func TestCallbackGC(t *testing.T) {
	nestedCall(t, runtime.GC)
}

func TestCallbackPanicLocked(t *testing.T) {
	runtime.LockOSThread()
	defer runtime.UnlockOSThread()

if !runtime.LockedOSThread() {
		t.Fatal("runtime.LockOSThread didn't")
	}
	defer func() {
		s := recover()
		if s == nil {
			t.Fatal("did not panic")
		}
		if s.(string) != "callback panic" {
			t.Fatal("wrong panic:", s)
		}
		if !runtime.LockedOSThread() {
			t.Fatal("lost lock on OS thread after panic")
		}
	}()
	nestedCall(t, func() { panic("callback panic") })
	panic("nestedCall returned")
}

func TestCallbackPanic(t *testing.T) {
	// Make sure panic during callback unwinds properly.
	if runtime.LockedOSThread() {
		t.Fatal("locked OS thread on entry to TestCallbackPanic")
	}
	defer func() {
		s := recover()
		if s == nil {
			t.Fatal("did not panic")
		}
		if s.(string) != "callback panic" {
			t.Fatal("wrong panic:", s)
		}
		if runtime.LockedOSThread() {
			t.Fatal("locked OS thread on exit from TestCallbackPanic")
		}
	}()
	nestedCall(t, func() { panic("callback panic") })
	panic("nestedCall returned")
}

func TestCallbackPanicLoop(t *testing.T) {
	// Make sure we don't blow out m->g0 stack.
	for i := 0; i < 100000; i++ {
		TestCallbackPanic(t)
	}
}

func TestBlockingCallback(t *testing.T) {
	c := make(chan int)
	go func() {
		for i := 0; i < 10; i++ {
			c <- <-c
		}
	}()
	nestedCall(t, func() {
		for i := 0; i < 10; i++ {
			c <- i
			if j := <-c; j != i {
				t.Errorf("out of sync %d != %d", j, i)
			}
		}
	})
}

func TestCallbackInAnotherThread(t *testing.T) {
	d := GetDLL(t, "kernel32.dll")

f := func(p uintptr) uintptr {
		return p
	}
	r, _, err := d.Proc("CreateThread").Call(0, 0, syscall.NewCallback(f), 123, 0, 0)
	if r == 0 {
		t.Fatalf("CreateThread failed: %v", err)
	}
	h := syscall.Handle(r)
	defer syscall.CloseHandle(h)

switch s, err := syscall.WaitForSingleObject(h, 100); s {
	case syscall.WAIT_OBJECT_0:
		break
	case syscall.WAIT_TIMEOUT:
		t.Fatal("timeout waiting for thread to exit")
	case syscall.WAIT_FAILED:
		t.Fatalf("WaitForSingleObject failed: %v", err)
	default:
		t.Fatalf("WaitForSingleObject returns unexpected value %v", s)
	}

var ec uint32
	r, _, err = d.Proc("GetExitCodeThread").Call(uintptr(h), uintptr(unsafe.Pointer(&ec)))
	if r == 0 {
		t.Fatalf("GetExitCodeThread failed: %v", err)
	}
	if ec != 123 {
		t.Fatalf("expected 123, but got %d", ec)
	}
}

type cbDLLFunc int // int determines number of callback parameters

func (f cbDLLFunc) stdcallName() string {
	return fmt.Sprintf("stdcall%d", f)
}

func (f cbDLLFunc) cdeclName() string {
	return fmt.Sprintf("cdecl%d", f)
}

func (f cbDLLFunc) buildOne(stdcall bool) string {
	var funcname, attr string
	if stdcall {
		funcname = f.stdcallName()
		attr = "__stdcall"
	} else {
		funcname = f.cdeclName()
		attr = "__cdecl"
	}
	typename := "t" + funcname
	p := make([]string, f)
	for i := range p {
		p[i] = "uintptr_t"
	}
	params := strings.Join(p, ",")
	for i := range p {
		p[i] = fmt.Sprintf("%d", i+1)
	}
	args := strings.Join(p, ",")
	return fmt.Sprintf(`
typedef void %s (*%s)(%s);
void %s(%s f, uintptr_t n) {
	uintptr_t i;
	for(i=0;i<n;i++){
		f(%s);
	}
}
	`, attr, typename, params, funcname, typename, args)
}

func (f cbDLLFunc) build() string {
	return "#include <stdint.h>\n\n" + f.buildOne(false) + f.buildOne(true)
}

var cbFuncs = [...]interface{}{
	2: func(i1, i2 uintptr) uintptr {
		if i1+i2 != 3 {
			panic("bad input")
		}
		return 0
	},
	3: func(i1, i2, i3 uintptr) uintptr {
		if i1+i2+i3 != 6 {
			panic("bad input")
		}
		return 0
	},
	4: func(i1, i2, i3, i4 uintptr) uintptr {
		if i1+i2+i3+i4 != 10 {
			panic("bad input")
		}
		return 0
	},
	5: func(i1, i2, i3, i4, i5 uintptr) uintptr {
		if i1+i2+i3+i4+i5 != 15 {
			panic("bad input")
		}
		return 0
	},
	6: func(i1, i2, i3, i4, i5, i6 uintptr) uintptr {
		if i1+i2+i3+i4+i5+i6 != 21 {
			panic("bad input")
		}
		return 0
	},
	7: func(i1, i2, i3, i4, i5, i6, i7 uintptr) uintptr {
		if i1+i2+i3+i4+i5+i6+i7 != 28 {
			panic("bad input")
		}
		return 0
	},
	8: func(i1, i2, i3, i4, i5, i6, i7, i8 uintptr) uintptr {
		if i1+i2+i3+i4+i5+i6+i7+i8 != 36 {
			panic("bad input")
		}
		return 0
	},
	9: func(i1, i2, i3, i4, i5, i6, i7, i8, i9 uintptr) uintptr {
		if i1+i2+i3+i4+i5+i6+i7+i8+i9 != 45 {
			panic("bad input")
		}
		return 0
	},
}

type cbDLL struct {
	name      string
	buildArgs func(out, src string) []string
}

func (d *cbDLL) buildSrc(t *testing.T, path string) {
	f, err := os.Create(path)
	if err != nil {
		t.Fatalf("failed to create source file: %v", err)
	}
	defer f.Close()

for i := 2; i < 10; i++ {
		fmt.Fprint(f, cbDLLFunc(i).build())
	}
}

func (d *cbDLL) build(t *testing.T, dir string) string {
	srcname := d.name + ".c"
	d.buildSrc(t, filepath.Join(dir, srcname))
	outname := d.name + ".dll"
	args := d.buildArgs(outname, srcname)
	cmd := exec.Command(args[0], args[1:]...)
	cmd.Dir = dir
	out, err := cmd.CombinedOutput()
	if err != nil {
		t.Fatalf("failed to build dll: %v - %v", err, string(out))
	}
	return filepath.Join(dir, outname)
}

var cbDLLs = []cbDLL{
	{
		"test",
		func(out, src string) []string {
			return []string{"gcc", "-shared", "-s", "-Werror", "-o", out, src}
		},
	},
	{
		"testO2",
		func(out, src string) []string {
			return []string{"gcc", "-shared", "-s", "-Werror", "-o", out, "-O2", src}
		},
	},
}

type cbTest struct {
	n     int     // number of callback parameters
	param uintptr // dll function parameter
}

func (test *cbTest) run(t *testing.T, dllpath string) {
	dll := syscall.MustLoadDLL(dllpath)
	defer dll.Release()
	cb := cbFuncs[test.n]
	stdcall := syscall.NewCallback(cb)
	f := cbDLLFunc(test.n)
	test.runOne(t, dll, f.stdcallName(), stdcall)
	cdecl := syscall.NewCallbackCDecl(cb)
	test.runOne(t, dll, f.cdeclName(), cdecl)
}

func (test *cbTest) runOne(t *testing.T, dll *syscall.DLL, proc string, cb uintptr) {
	defer func() {
		if r := recover(); r != nil {
			t.Errorf("dll call %v(..., %d) failed: %v", proc, test.param, r)
		}
	}()
	dll.MustFindProc(proc).Call(cb, test.param)
}

var cbTests = []cbTest{
	{2, 1},
	{2, 10000},
	{3, 3},
	{4, 5},
	{4, 6},
	{5, 2},
	{6, 7},
	{6, 8},
	{7, 6},
	{8, 1},
	{9, 8},
	{9, 10000},
	{3, 4},
	{5, 3},
	{7, 7},
	{8, 2},
	{9, 9},
}

func TestStdcallAndCDeclCallbacks(t *testing.T) {
	if _, err := exec.LookPath("gcc"); err != nil {
		t.Skip("skipping test: gcc is missing")
	}
	tmp, err := ioutil.TempDir("", "TestCDeclCallback")
	if err != nil {
		t.Fatal("TempDir failed: ", err)
	}
	defer os.RemoveAll(tmp)

for _, dll := range cbDLLs {
		dllPath := dll.build(t, tmp)
		for _, test := range cbTests {
			test.run(t, dllPath)
		}
	}
}

func TestRegisterClass(t *testing.T) {
	kernel32 := GetDLL(t, "kernel32.dll")
	user32 := GetDLL(t, "user32.dll")
	mh, _, _ := kernel32.Proc("GetModuleHandleW").Call(0)
	cb := syscall.NewCallback(func(hwnd syscall.Handle, msg uint32, wparam, lparam uintptr) (rc uintptr) {
		t.Fatal("callback should never get called")
		return 0
	})
	type Wndclassex struct {
		Size       uint32
		Style      uint32
		WndProc    uintptr
		ClsExtra   int32
		WndExtra   int32
		Instance   syscall.Handle
		Icon       syscall.Handle
		Cursor     syscall.Handle
		Background syscall.Handle
		MenuName   *uint16
		ClassName  *uint16
		IconSm     syscall.Handle
	}
	name := syscall.StringToUTF16Ptr("test_window")
	wc := Wndclassex{
		WndProc:   cb,
		Instance:  syscall.Handle(mh),
		ClassName: name,
	}
	wc.Size = uint32(unsafe.Sizeof(wc))
	a, _, err := user32.Proc("RegisterClassExW").Call(uintptr(unsafe.Pointer(&wc)))
	if a == 0 {
		t.Fatalf("RegisterClassEx failed: %v", err)
	}
	r, _, err := user32.Proc("UnregisterClassW").Call(uintptr(unsafe.Pointer(name)), 0)
	if r == 0 {
		t.Fatalf("UnregisterClass failed: %v", err)
	}
}

func TestOutputDebugString(t *testing.T) {
	d := GetDLL(t, "kernel32.dll")
	p := syscall.StringToUTF16Ptr("testing OutputDebugString")
	d.Proc("OutputDebugStringW").Call(uintptr(unsafe.Pointer(p)))
}

func TestRaiseException(t *testing.T) {
	o := runTestProg(t, "testprog", "RaiseException")
	if strings.Contains(o, "RaiseException should not return") {
		t.Fatalf("RaiseException did not crash program: %v", o)
	}
	if !strings.Contains(o, "Exception 0xbad") {
		t.Fatalf("No stack trace: %v", o)
	}
}

func TestZeroDivisionException(t *testing.T) {
	o := runTestProg(t, "testprog", "ZeroDivisionException")
	if !strings.Contains(o, "panic: runtime error: integer divide by zero") {
		t.Fatalf("No stack trace: %v", o)
	}
}

func TestWERDialogue(t *testing.T) {
	if os.Getenv("TESTING_WER_DIALOGUE") == "1" {
		defer os.Exit(0)

*runtime.TestingWER = true
		const EXCEPTION_NONCONTINUABLE = 1
		mod := syscall.MustLoadDLL("kernel32.dll")
		proc := mod.MustFindProc("RaiseException")
		proc.Call(0xbad, EXCEPTION_NONCONTINUABLE, 0, 0)
		println("RaiseException should not return")
		return
	}
	cmd := exec.Command(os.Args[0], "-test.run=TestWERDialogue")
	cmd.Env = []string{"TESTING_WER_DIALOGUE=1"}
	// Child process should not open WER dialogue, but return immediately instead.
	cmd.CombinedOutput()
}

func TestWindowsStackMemory(t *testing.T) {
	o := runTestProg(t, "testprog", "StackMemory")
	stackUsage, err := strconv.Atoi(o)
	if err != nil {
		t.Fatalf("Failed to read stack usage: %v", err)
	}
	if expected, got := 100<<10, stackUsage; got > expected {
		t.Fatalf("expected < %d bytes of memory per thread, got %d", expected, got)
	}
}

var used byte

func use(buf []byte) {
	for _, c := range buf {
		used += c
	}
}

func forceStackCopy() (r int) {
	var f func(int) int
	f = func(i int) int {
		var buf [256]byte
		use(buf[:])
		if i == 0 {
			return 0
		}
		return i + f(i-1)
	}
	r = f(128)
	return
}

func TestReturnAfterStackGrowInCallback(t *testing.T) {
	if _, err := exec.LookPath("gcc"); err != nil {
		t.Skip("skipping test: gcc is missing")
	}

const src = `
#include <stdint.h>
#include <windows.h>

typedef uintptr_t __stdcall (*callback)(uintptr_t);

uintptr_t cfunc(callback f, uintptr_t n) {
   uintptr_t r;
   r = f(n);
   SetLastError(333);
   return r;
}
`
	tmpdir, err := ioutil.TempDir("", "TestReturnAfterStackGrowInCallback")
	if err != nil {
		t.Fatal("TempDir failed: ", err)
	}
	defer os.RemoveAll(tmpdir)

srcname := "mydll.c"
	err = ioutil.WriteFile(filepath.Join(tmpdir, srcname), []byte(src), 0)
	if err != nil {
		t.Fatal(err)
	}
	outname := "mydll.dll"
	cmd := exec.Command("gcc", "-shared", "-s", "-Werror", "-o", outname, srcname)
	cmd.Dir = tmpdir
	out, err := cmd.CombinedOutput()
	if err != nil {
		t.Fatalf("failed to build dll: %v - %v", err, string(out))
	}
	dllpath := filepath.Join(tmpdir, outname)

dll := syscall.MustLoadDLL(dllpath)
	defer dll.Release()

proc := dll.MustFindProc("cfunc")

cb := syscall.NewCallback(func(n uintptr) uintptr {
		forceStackCopy()
		return n
	})

// Use a new goroutine so that we get a small stack.
	type result struct {
		r   uintptr
		err syscall.Errno
	}
	want := result{
		// Make it large enough to test issue #29331.
		r:   (^uintptr(0)) >> 24,
		err: 333,
	}
	c := make(chan result)
	go func() {
		r, _, err := proc.Call(cb, want.r)
		c <- result{r, err.(syscall.Errno)}
	}()
	if got := <-c; got != want {
		t.Errorf("got %d want %d", got, want)
	}
}

func TestFloatArgs(t *testing.T) {
	if _, err := exec.LookPath("gcc"); err != nil {
		t.Skip("skipping test: gcc is missing")
	}
	if runtime.GOARCH != "amd64" {
		t.Skipf("skipping test: GOARCH=%s", runtime.GOARCH)
	}

const src = `
#include <stdint.h>
#include <windows.h>

uintptr_t cfunc(uintptr_t a, double b, float c, double d) {
	if (a == 1 && b == 2.2 && c == 3.3f && d == 4.4e44) {
		return 1;
	}
	return 0;
}
`
	tmpdir, err := ioutil.TempDir("", "TestFloatArgs")
	if err != nil {
		t.Fatal("TempDir failed: ", err)
	}
	defer os.RemoveAll(tmpdir)

dll := syscall.MustLoadDLL(dllpath)
	defer dll.Release()

proc := dll.MustFindProc("cfunc")

r, _, err := proc.Call(
		1,
		uintptr(math.Float64bits(2.2)),
		uintptr(math.Float32bits(3.3)),
		uintptr(math.Float64bits(4.4e44)),
	)
	if r != 1 {
		t.Errorf("got %d want 1 (err=%v)", r, err)
	}
}

func TestTimeBeginPeriod(t *testing.T) {
	const TIMERR_NOERROR = 0
	if *runtime.TimeBeginPeriodRetValue != TIMERR_NOERROR {
		t.Fatalf("timeBeginPeriod failed: it returned %d", *runtime.TimeBeginPeriodRetValue)
	}
}

// removeOneCPU removes one (any) cpu from affinity mask.
// It returns new affinity mask.
func removeOneCPU(mask uintptr) (uintptr, error) {
	if mask == 0 {
		return 0, fmt.Errorf("cpu affinity mask is empty")
	}
	maskbits := int(unsafe.Sizeof(mask) * 8)
	for i := 0; i < maskbits; i++ {
		newmask := mask & ^(1 << uint(i))
		if newmask != mask {
			return newmask, nil
		}

}
	panic("not reached")
}

func resumeChildThread(kernel32 *syscall.DLL, childpid int) error {
	_OpenThread := kernel32.MustFindProc("OpenThread")
	_ResumeThread := kernel32.MustFindProc("ResumeThread")
	_Thread32First := kernel32.MustFindProc("Thread32First")
	_Thread32Next := kernel32.MustFindProc("Thread32Next")

snapshot, err := syscall.CreateToolhelp32Snapshot(syscall.TH32CS_SNAPTHREAD, 0)
	if err != nil {
		return err
	}
	defer syscall.CloseHandle(snapshot)

const _THREAD_SUSPEND_RESUME = 0x0002

type ThreadEntry32 struct {
		Size           uint32
		tUsage         uint32
		ThreadID       uint32
		OwnerProcessID uint32
		BasePri        int32
		DeltaPri       int32
		Flags          uint32
	}

var te ThreadEntry32
	te.Size = uint32(unsafe.Sizeof(te))
	ret, _, err := _Thread32First.Call(uintptr(snapshot), uintptr(unsafe.Pointer(&te)))
	if ret == 0 {
		return err
	}
	for te.OwnerProcessID != uint32(childpid) {
		ret, _, err = _Thread32Next.Call(uintptr(snapshot), uintptr(unsafe.Pointer(&te)))
		if ret == 0 {
			return err
		}
	}
	h, _, err := _OpenThread.Call(_THREAD_SUSPEND_RESUME, 1, uintptr(te.ThreadID))
	if h == 0 {
		return err
	}
	defer syscall.Close(syscall.Handle(h))

ret, _, err = _ResumeThread.Call(h)
	if ret == 0xffffffff {
		return err
	}
	return nil
}

func TestNumCPU(t *testing.T) {
	if os.Getenv("GO_WANT_HELPER_PROCESS") == "1" {
		// in child process
		fmt.Fprintf(os.Stderr, "%d", runtime.NumCPU())
		os.Exit(0)
	}

switch n := runtime.NumberOfProcessors(); {
	case n < 1:
		t.Fatalf("system cannot have %d cpu(s)", n)
	case n == 1:
		if runtime.NumCPU() != 1 {
			t.Fatalf("runtime.NumCPU() returns %d on single cpu system", runtime.NumCPU())
		}
		return
	}

const (
		_CREATE_SUSPENDED   = 0x00000004
		_PROCESS_ALL_ACCESS = syscall.STANDARD_RIGHTS_REQUIRED | syscall.SYNCHRONIZE | 0xfff
	)

kernel32 := syscall.MustLoadDLL("kernel32.dll")
	_GetProcessAffinityMask := kernel32.MustFindProc("GetProcessAffinityMask")
	_SetProcessAffinityMask := kernel32.MustFindProc("SetProcessAffinityMask")

cmd := exec.Command(os.Args[0], "-test.run=TestNumCPU")
	cmd.Env = append(os.Environ(), "GO_WANT_HELPER_PROCESS=1")
	var buf bytes.Buffer
	cmd.Stdout = &buf
	cmd.Stderr = &buf
	cmd.SysProcAttr = &syscall.SysProcAttr{CreationFlags: _CREATE_SUSPENDED}
	err := cmd.Start()
	if err != nil {
		t.Fatal(err)
	}
	defer func() {
		err = cmd.Wait()
		childOutput := string(buf.Bytes())
		if err != nil {
			t.Fatalf("child failed: %v: %v", err, childOutput)
		}
		// removeOneCPU should have decreased child cpu count by 1
		want := fmt.Sprintf("%d", runtime.NumCPU()-1)
		if childOutput != want {
			t.Fatalf("child output: want %q, got %q", want, childOutput)
		}
	}()

defer func() {
		err = resumeChildThread(kernel32, cmd.Process.Pid)
		if err != nil {
			t.Fatal(err)
		}
	}()

ph, err := syscall.OpenProcess(_PROCESS_ALL_ACCESS, false, uint32(cmd.Process.Pid))
	if err != nil {
		t.Fatal(err)
	}
	defer syscall.CloseHandle(ph)

var mask, sysmask uintptr
	ret, _, err := _GetProcessAffinityMask.Call(uintptr(ph), uintptr(unsafe.Pointer(&mask)), uintptr(unsafe.Pointer(&sysmask)))
	if ret == 0 {
		t.Fatal(err)
	}

newmask, err := removeOneCPU(mask)
	if err != nil {
		t.Fatal(err)
	}

ret, _, err = _SetProcessAffinityMask.Call(uintptr(ph), newmask)
	if ret == 0 {
		t.Fatal(err)
	}
	ret, _, err = _GetProcessAffinityMask.Call(uintptr(ph), uintptr(unsafe.Pointer(&mask)), uintptr(unsafe.Pointer(&sysmask)))
	if ret == 0 {
		t.Fatal(err)
	}
	if newmask != mask {
		t.Fatalf("SetProcessAffinityMask didn't set newmask of 0x%x. Current mask is 0x%x.", newmask, mask)
	}
}

// See Issue 14959
func TestDLLPreloadMitigation(t *testing.T) {
	if _, err := exec.LookPath("gcc"); err != nil {
		t.Skip("skipping test: gcc is missing")
	}

tmpdir, err := ioutil.TempDir("", "TestDLLPreloadMitigation")
	if err != nil {
		t.Fatal("TempDir failed: ", err)
	}
	defer func() {
		err := os.RemoveAll(tmpdir)
		if err != nil {
			t.Error(err)
		}
	}()

dir0, err := os.Getwd()
	if err != nil {
		t.Fatal(err)
	}
	defer os.Chdir(dir0)

const src = `
#include <stdint.h>
#include <windows.h>

uintptr_t cfunc() {
   SetLastError(123);
}
`
	srcname := "nojack.c"
	err = ioutil.WriteFile(filepath.Join(tmpdir, srcname), []byte(src), 0)
	if err != nil {
		t.Fatal(err)
	}
	name := "nojack.dll"
	cmd := exec.Command("gcc", "-shared", "-s", "-Werror", "-o", name, srcname)
	cmd.Dir = tmpdir
	out, err := cmd.CombinedOutput()
	if err != nil {
		t.Fatalf("failed to build dll: %v - %v", err, string(out))
	}
	dllpath := filepath.Join(tmpdir, name)

dll := syscall.MustLoadDLL(dllpath)
	dll.MustFindProc("cfunc")
	dll.Release()

// Get into the directory with the DLL we'll load by base name
	// ("nojack.dll") Think of this as the user double-clicking an
	// installer from their Downloads directory where a browser
	// silently downloaded some malicious DLLs.
	os.Chdir(tmpdir)

// First before we can load a DLL from the current directory,
	// loading it only as "nojack.dll", without an absolute path.
	delete(sysdll.IsSystemDLL, name) // in case test was run repeatedly
	dll, err = syscall.LoadDLL(name)
	if err != nil {
		t.Fatalf("failed to load %s by base name before sysdll registration: %v", name, err)
	}
	dll.Release()

// And now verify that if we register it as a system32-only
	// DLL, the implicit loading from the current directory no
	// longer works.
	sysdll.IsSystemDLL[name] = true
	dll, err = syscall.LoadDLL(name)
	if err == nil {
		dll.Release()
		if wantLoadLibraryEx() {
			t.Fatalf("Bad: insecure load of DLL by base name %q before sysdll registration: %v", name, err)
		}
		t.Skip("insecure load of DLL, but expected")
	}
}

// Test that C code called via a DLL can use large Windows thread
// stacks and call back in to Go without crashing. See issue #20975.
//
// See also TestBigStackCallbackCgo.
func TestBigStackCallbackSyscall(t *testing.T) {
	if _, err := exec.LookPath("gcc"); err != nil {
		t.Skip("skipping test: gcc is missing")
	}

srcname, err := filepath.Abs("testdata/testprogcgo/bigstack_windows.c")
	if err != nil {
		t.Fatal("Abs failed: ", err)
	}

tmpdir, err := ioutil.TempDir("", "TestBigStackCallback")
	if err != nil {
		t.Fatal("TempDir failed: ", err)
	}
	defer os.RemoveAll(tmpdir)

outname := "mydll.dll"
	cmd := exec.Command("gcc", "-shared", "-s", "-Werror", "-o", outname, srcname)
	cmd.Dir = tmpdir
	out, err := cmd.CombinedOutput()
	if err != nil {
		t.Fatalf("failed to build dll: %v - %v", err, string(out))
	}
	dllpath := filepath.Join(tmpdir, outname)

dll := syscall.MustLoadDLL(dllpath)
	defer dll.Release()

var ok bool
	proc := dll.MustFindProc("bigStack")
	cb := syscall.NewCallback(func() uintptr {
		// Do something interesting to force stack checks.
		forceStackCopy()
		ok = true
		return 0
	})
	proc.Call(cb)
	if !ok {
		t.Fatalf("callback not called")
	}
}

// wantLoadLibraryEx reports whether we expect LoadLibraryEx to work for tests.
func wantLoadLibraryEx() bool {
	return testenv.Builder() == "windows-amd64-gce" || testenv.Builder() == "windows-386-gce"
}

func TestLoadLibraryEx(t *testing.T) {
	use, have, flags := runtime.LoadLibraryExStatus()
	if use {
		return // success.
	}
	if wantLoadLibraryEx() {
		t.Fatalf("Expected LoadLibraryEx+flags to be available. (LoadLibraryEx=%v; flags=%v)",
			have, flags)
	}
	t.Skipf("LoadLibraryEx not usable, but not expected. (LoadLibraryEx=%v; flags=%v)",
		have, flags)
}

var (
	modwinmm    = syscall.NewLazyDLL("winmm.dll")
	modkernel32 = syscall.NewLazyDLL("kernel32.dll")

procCreateEvent = modkernel32.NewProc("CreateEventW")
	procSetEvent    = modkernel32.NewProc("SetEvent")
)

func createEvent() (syscall.Handle, error) {
	r0, _, e0 := syscall.Syscall6(procCreateEvent.Addr(), 4, 0, 0, 0, 0, 0, 0)
	if r0 == 0 {
		return 0, syscall.Errno(e0)
	}
	return syscall.Handle(r0), nil
}

func setEvent(h syscall.Handle) error {
	r0, _, e0 := syscall.Syscall(procSetEvent.Addr(), 1, uintptr(h), 0, 0)
	if r0 == 0 {
		return syscall.Errno(e0)
	}
	return nil
}

func BenchmarkChanToSyscallPing(b *testing.B) {
	n := b.N
	ch := make(chan int)
	event, err := createEvent()
	if err != nil {
		b.Fatal(err)
	}
	go func() {
		for i := 0; i < n; i++ {
			syscall.WaitForSingleObject(event, syscall.INFINITE)
			ch <- 1
		}
	}()
	for i := 0; i < n; i++ {
		err := setEvent(event)
		if err != nil {
			b.Fatal(err)
		}
		<-ch
	}
}

func BenchmarkSyscallToSyscallPing(b *testing.B) {
	n := b.N
	event1, err := createEvent()
	if err != nil {
		b.Fatal(err)
	}
	event2, err := createEvent()
	if err != nil {
		b.Fatal(err)
	}
	go func() {
		for i := 0; i < n; i++ {
			syscall.WaitForSingleObject(event1, syscall.INFINITE)
			err := setEvent(event2)
			if err != nil {
				b.Fatal(err)
			}
		}
	}()
	for i := 0; i < n; i++ {
		err := setEvent(event1)
		if err != nil {
			b.Fatal(err)
		}
		syscall.WaitForSingleObject(event2, syscall.INFINITE)
	}
}

func BenchmarkChanToChanPing(b *testing.B) {
	n := b.N
	ch1 := make(chan int)
	ch2 := make(chan int)
	go func() {
		for i := 0; i < n; i++ {
			<-ch1
			ch2 <- 1
		}
	}()
	for i := 0; i < n; i++ {
		ch1 <- 1
		<-ch2
	}
}

func BenchmarkOsYield(b *testing.B) {
	for i := 0; i < b.N; i++ {
		runtime.OsYield()
	}
}

func BenchmarkRunningGoProgram(b *testing.B) {
	tmpdir, err := ioutil.TempDir("", "BenchmarkRunningGoProgram")
	if err != nil {
		b.Fatal(err)
	}
	defer os.RemoveAll(tmpdir)

src := filepath.Join(tmpdir, "main.go")
	err = ioutil.WriteFile(src, []byte(benchmarkRunningGoProgram), 0666)
	if err != nil {
		b.Fatal(err)
	}

exe := filepath.Join(tmpdir, "main.exe")
	cmd := exec.Command(testenv.GoToolPath(b), "build", "-o", exe, src)
	cmd.Dir = tmpdir
	out, err := cmd.CombinedOutput()
	if err != nil {
		b.Fatalf("building main.exe failed: %v\n%s", err, out)
	}

b.ResetTimer()
	for i := 0; i < b.N; i++ {
		cmd := exec.Command(exe)
		out, err := cmd.CombinedOutput()
		if err != nil {
			b.Fatalf("running main.exe failed: %v\n%s", err, out)
		}
	}
}

const benchmarkRunningGoProgram = `
package main

import _ "os" // average Go program will use "os" package, do the same here

func main() {
}
`

${this.title}

Code Editor : syscall_windows_test.go