src/runtime · bff29f2d1798cb0c8b6a4a8440c076f4b9460158 · go / golang

runtime: improve arm64 memmove implementation · 213a7517

Balaram Makam authored Dec 13, 2017

Improve runtime memmove_arm64.s specializing for small copies and
processing 32 bytes per iteration for 32 bytes or more.

Benchmark results of runtime/Memmove on Amberwing:
name old time/op new time/op delta
Memmove/0 7.61ns ± 0% 7.20ns ± 0% ~ (p=0.053 n=5+7)
Memmove/1 9.28ns ± 0% 8.80ns ± 0% -5.17% (p=0.000 n=4+8)
Memmove/2 9.65ns ± 0% 9.20ns ± 0% -4.68% (p=0.000 n=5+8)
Memmove/3 10.0ns ± 0% 9.2ns ± 0% -7.83% (p=0.000 n=5+8)
Memmove/4 10.6ns ± 0% 9.2ns ± 0% -13.21% (p=0.000 n=5+8)
Memmove/5 11.0ns ± 0% 9.2ns ± 0% -16.36% (p=0.000 n=5+8)
Memmove/6 12.4ns ± 0% 9.2ns ± 0% -25.81% (p=0.000 n=5+8)
Memmove/7 13.1ns ± 0% 9.2ns ± 0% -29.56% (p=0.000 n=5+8)
Memmove/8 9.10ns ± 1% 9.20ns ± 0% +1.08% (p=0.002 n=5+8)
Memmove/9 9.67ns ± 0% 9.20ns ± 0% -4.88% (p=0.000 n=5+8)
Memmove/10 10.4ns ± 0% 9.2ns ± 0% -11.54% (p=0.000 n=5+8)
Memmove/11 10.9ns ± 0% 9.2ns ± 0% -15.60% (p=0.000 n=5+8)
Memmove/12 11.5ns ± 0% 9.2ns ± 0% -20.00% (p=0.000 n=5+8)
Memmove/13 12.4ns ± 0% 9.2ns ± 0% -25.81% (p=0.000 n=5+8)
Memmove/14 13.1ns ± 0% 9.2ns ± 0% -29.77% (p=0.000 n=5+8)
Memmove/15 13.8ns ± 0% 9.2ns ± 0% -33.33% (p=0.000 n=5+8)
Memmove/16 9.70ns ± 0% 9.20ns ± 0% -5.19% (p=0.000 n=5+8)
Memmove/32 10.6ns ± 0% 9.2ns ± 0% -13.21% (p=0.000 n=4+8)
Memmove/64 13.4ns ± 0% 10.2ns ± 0% -23.88% (p=0.000 n=4+8)
Memmove/128 18.1ns ± 1% 13.2ns ± 0% -26.99% (p=0.000 n=5+8)
Memmove/256 25.2ns ± 0% 16.4ns ± 0% -34.92% (p=0.000 n=5+8)
Memmove/512 36.4ns ± 0% 22.8ns ± 0% -37.36% (p=0.000 n=5+8)
Memmove/1024 70.1ns ± 0% 36.8ns ±11% -47.49% (p=0.002 n=5+8)
Memmove/2048 121ns ± 0% 61ns ± 0% ~ (p=0.053 n=5+7)
Memmove/4096 224ns ± 0% 120ns ± 0% -46.43% (p=0.000 n=5+8)
MemmoveUnalignedDst/0 8.40ns ± 0% 8.00ns ± 0% -4.76% (p=0.000 n=5+8)
MemmoveUnalignedDst/1 9.87ns ± 1% 10.00ns ± 0% ~ (p=0.070 n=5+8)
MemmoveUnalignedDst/2 10.6ns ± 0% 10.4ns ± 0% -1.89% (p=0.000 n=5+8)
MemmoveUnalignedDst/3 10.8ns ± 0% 10.4ns ± 0% -3.70% (p=0.000 n=5+8)
MemmoveUnalignedDst/4 10.9ns ± 0% 10.3ns ± 0% ~ (p=0.053 n=5+7)
MemmoveUnalignedDst/5 11.5ns ± 0% 10.3ns ± 1% -10.22% (p=0.000 n=4+8)
MemmoveUnalignedDst/6 13.2ns ± 0% 10.4ns ± 1% -21.50% (p=0.000 n=5+8)
MemmoveUnalignedDst/7 13.7ns ± 0% 10.3ns ± 1% -24.64% (p=0.000 n=4+8)
MemmoveUnalignedDst/8 10.1ns ± 0% 10.4ns ± 0% +2.97% (p=0.002 n=5+8)
MemmoveUnalignedDst/9 10.7ns ± 0% 10.4ns ± 0% -2.80% (p=0.000 n=5+8)
MemmoveUnalignedDst/10 11.2ns ± 1% 10.4ns ± 0% -6.81% (p=0.000 n=5+8)
MemmoveUnalignedDst/11 11.6ns ± 0% 10.4ns ± 0% -10.34% (p=0.000 n=5+8)
MemmoveUnalignedDst/12 12.5ns ± 2% 10.4ns ± 0% -16.53% (p=0.000 n=5+8)
MemmoveUnalignedDst/13 13.7ns ± 0% 10.4ns ± 0% -24.09% (p=0.000 n=5+8)
MemmoveUnalignedDst/14 14.0ns ± 0% 10.4ns ± 0% -25.71% (p=0.000 n=5+8)
MemmoveUnalignedDst/15 14.6ns ± 0% 10.4ns ± 0% -28.77% (p=0.000 n=5+8)
MemmoveUnalignedDst/16 10.5ns ± 0% 10.4ns ± 0% -0.95% (p=0.000 n=5+8)
MemmoveUnalignedDst/32 12.4ns ± 0% 11.6ns ± 0% -6.05% (p=0.000 n=5+8)
MemmoveUnalignedDst/64 15.2ns ± 0% 12.3ns ± 0% -19.08% (p=0.000 n=5+8)
MemmoveUnalignedDst/128 18.7ns ± 0% 15.2ns ± 0% -18.72% (p=0.000 n=5+8)
MemmoveUnalignedDst/256 25.1ns ± 0% 18.6ns ± 0% -25.90% (p=0.000 n=5+8)
MemmoveUnalignedDst/512 37.8ns ± 0% 24.4ns ± 0% -35.45% (p=0.000 n=5+8)
MemmoveUnalignedDst/1024 74.6ns ± 0% 40.4ns ± 0% ~ (p=0.053 n=5+7)
MemmoveUnalignedDst/2048 133ns ± 0% 75ns ± 0% -43.91% (p=0.000 n=5+8)
MemmoveUnalignedDst/4096 247ns ± 0% 141ns ± 0% -42.91% (p=0.000 n=5+8)
MemmoveUnalignedSrc/0 8.40ns ± 0% 8.00ns ± 0% -4.76% (p=0.000 n=5+8)
MemmoveUnalignedSrc/1 9.81ns ± 0% 10.00ns ± 0% +1.98% (p=0.002 n=5+8)
MemmoveUnalignedSrc/2 10.5ns ± 0% 10.0ns ± 0% -4.76% (p=0.000 n=5+8)
MemmoveUnalignedSrc/3 10.7ns ± 1% 10.0ns ± 0% -6.89% (p=0.000 n=5+8)
MemmoveUnalignedSrc/4 11.3ns ± 0% 10.0ns ± 0% -11.50% (p=0.000 n=5+8)
MemmoveUnalignedSrc/5 11.6ns ± 0% 10.0ns ± 0% -13.79% (p=0.000 n=5+8)
MemmoveUnalignedSrc/6 13.6ns ± 0% 10.0ns ± 0% -26.47% (p=0.000 n=5+8)
MemmoveUnalignedSrc/7 14.4ns ± 0% 10.0ns ± 0% -30.75% (p=0.000 n=5+8)
MemmoveUnalignedSrc/8 9.87ns ± 1% 10.00ns ± 0% ~ (p=0.070 n=5+8)
MemmoveUnalignedSrc/9 10.4ns ± 0% 10.0ns ± 0% -3.85% (p=0.000 n=5+8)
MemmoveUnalignedSrc/10 11.2ns ± 0% 10.0ns ± 0% -10.71% (p=0.000 n=5+8)
MemmoveUnalignedSrc/11 11.8ns ± 0% 10.0ns ± 0% -15.25% (p=0.000 n=5+8)
MemmoveUnalignedSrc/12 12.1ns ± 0% 10.0ns ± 0% -17.36% (p=0.000 n=5+8)
MemmoveUnalignedSrc/13 13.6ns ± 0% 10.0ns ± 0% -26.47% (p=0.000 n=5+8)
MemmoveUnalignedSrc/14 14.7ns ± 0% 10.0ns ± 0% -31.79% (p=0.000 n=5+8)
MemmoveUnalignedSrc/15 14.4ns ± 0% 10.0ns ± 0% -30.56% (p=0.000 n=5+8)
MemmoveUnalignedSrc/16 11.0ns ± 0% 10.0ns ± 0% -9.09% (p=0.000 n=5+8)
MemmoveUnalignedSrc/32 11.5ns ± 0% 10.0ns ± 0% -13.04% (p=0.000 n=5+8)
MemmoveUnalignedSrc/64 14.9ns ± 0% 11.2ns ± 0% -24.83% (p=0.000 n=4+8)
MemmoveUnalignedSrc/128 19.5ns ± 0% 15.2ns ± 0% -22.05% (p=0.000 n=5+8)
MemmoveUnalignedSrc/256 27.3ns ± 2% 19.2ns ± 0% -29.62% (p=0.000 n=5+8)
MemmoveUnalignedSrc/512 40.4ns ± 0% 27.2ns ± 0% -32.67% (p=0.000 n=5+8)
MemmoveUnalignedSrc/1024 75.4ns ± 0% 44.4ns ± 0% -41.15% (p=0.000 n=5+8)
MemmoveUnalignedSrc/2048 131ns ± 0% 77ns ± 3% -41.56% (p=0.002 n=5+8)
MemmoveUnalignedSrc/4096 248ns ± 0% 145ns ± 0% -41.53% (p=0.000 n=5+8)

name old speed new speed delta
Memmove/1 108MB/s ± 0% 114MB/s ± 0% +5.37% (p=0.004 n=4+8)
Memmove/2 207MB/s ± 0% 217MB/s ± 0% +4.85% (p=0.002 n=5+8)
Memmove/3 301MB/s ± 0% 326MB/s ± 0% +8.45% (p=0.002 n=5+8)
Memmove/4 377MB/s ± 0% 435MB/s ± 0% +15.31% (p=0.004 n=4+8)
Memmove/5 455MB/s ± 0% 543MB/s ± 0% +19.46% (p=0.002 n=5+8)
Memmove/6 483MB/s ± 0% 652MB/s ± 0% +34.88% (p=0.003 n=5+7)
Memmove/7 537MB/s ± 0% 761MB/s ± 0% +41.71% (p=0.002 n=5+8)
Memmove/8 879MB/s ± 1% 869MB/s ± 0% -1.15% (p=0.000 n=5+7)
Memmove/9 931MB/s ± 0% 978MB/s ± 0% +5.05% (p=0.002 n=5+8)
Memmove/10 960MB/s ± 0% 1086MB/s ± 0% +13.13% (p=0.002 n=5+8)
Memmove/11 1.00GB/s ± 0% 1.20GB/s ± 0% +18.92% (p=0.003 n=5+7)
Memmove/12 1.04GB/s ± 0% 1.30GB/s ± 0% +25.40% (p=0.002 n=5+8)
Memmove/13 1.05GB/s ± 0% 1.41GB/s ± 0% +34.87% (p=0.002 n=5+8)
Memmove/14 1.07GB/s ± 0% 1.52GB/s ± 0% +42.14% (p=0.002 n=5+8)
Memmove/15 1.09GB/s ± 0% 1.63GB/s ± 0% +49.91% (p=0.002 n=5+8)
Memmove/16 1.65GB/s ± 0% 1.74GB/s ± 0% +5.40% (p=0.003 n=5+7)
Memmove/32 3.01GB/s ± 0% 3.48GB/s ± 0% +15.58% (p=0.003 n=5+7)
Memmove/64 4.76GB/s ± 0% 6.27GB/s ± 0% +31.75% (p=0.003 n=5+7)
Memmove/128 7.08GB/s ± 1% 9.69GB/s ± 0% +36.96% (p=0.002 n=5+8)
Memmove/256 10.2GB/s ± 0% 15.6GB/s ± 0% +53.58% (p=0.002 n=5+8)
Memmove/512 14.1GB/s ± 0% 22.4GB/s ± 0% +59.57% (p=0.003 n=5+7)
Memmove/1024 14.6GB/s ± 0% 27.9GB/s ±10% +91.00% (p=0.002 n=5+8)
Memmove/2048 16.9GB/s ± 0% 33.4GB/s ± 0% +98.32% (p=0.003 n=5+7)
Memmove/4096 18.3GB/s ± 0% 33.9GB/s ± 0% +85.80% (p=0.002 n=5+8)
MemmoveUnalignedDst/1 101MB/s ± 1% 100MB/s ± 0% ~ (p=0.586 n=5+8)
MemmoveUnalignedDst/2 189MB/s ± 0% 192MB/s ± 0% +1.82% (p=0.002 n=5+8)
MemmoveUnalignedDst/3 278MB/s ± 0% 288MB/s ± 0% +3.88% (p=0.003 n=5+7)
MemmoveUnalignedDst/4 368MB/s ± 0% 387MB/s ± 0% +5.41% (p=0.003 n=5+7)
MemmoveUnalignedDst/5 434MB/s ± 0% 484MB/s ± 0% +11.52% (p=0.002 n=5+8)
MemmoveUnalignedDst/6 454MB/s ± 0% 580MB/s ± 0% +27.62% (p=0.002 n=5+8)
MemmoveUnalignedDst/7 509MB/s ± 0% 677MB/s ± 0% +33.01% (p=0.002 n=5+8)
MemmoveUnalignedDst/8 792MB/s ± 0% 770MB/s ± 0% -2.77% (p=0.002 n=5+8)
MemmoveUnalignedDst/9 841MB/s ± 0% 866MB/s ± 0% +2.92% (p=0.002 n=5+8)
MemmoveUnalignedDst/10 896MB/s ± 0% 962MB/s ± 0% +7.35% (p=0.003 n=5+7)
MemmoveUnalignedDst/11 947MB/s ± 0% 1058MB/s ± 0% +11.80% (p=0.002 n=5+8)
MemmoveUnalignedDst/12 962MB/s ± 2% 1154MB/s ± 0% +19.97% (p=0.002 n=5+8)
MemmoveUnalignedDst/13 947MB/s ± 0% 1251MB/s ± 0% +32.08% (p=0.002 n=5+8)
MemmoveUnalignedDst/14 1.00GB/s ± 0% 1.35GB/s ± 0% +34.55% (p=0.002 n=5+8)
MemmoveUnalignedDst/15 1.03GB/s ± 0% 1.44GB/s ± 0% +40.50% (p=0.002 n=5+8)
MemmoveUnalignedDst/16 1.53GB/s ± 0% 1.54GB/s ± 0% +0.77% (p=0.002 n=5+8)
MemmoveUnalignedDst/32 2.58GB/s ± 0% 2.75GB/s ± 0% +6.52% (p=0.003 n=5+7)
MemmoveUnalignedDst/64 4.21GB/s ± 0% 5.19GB/s ± 0% +23.40% (p=0.004 n=5+6)
MemmoveUnalignedDst/128 6.86GB/s ± 0% 8.42GB/s ± 0% +22.78% (p=0.003 n=5+7)
MemmoveUnalignedDst/256 10.2GB/s ± 0% 13.8GB/s ± 0% +35.15% (p=0.002 n=5+8)
MemmoveUnalignedDst/512 13.5GB/s ± 0% 21.0GB/s ± 0% +54.90% (p=0.002 n=5+8)
MemmoveUnalignedDst/1024 13.7GB/s ± 0% 25.3GB/s ± 0% +84.61% (p=0.003 n=5+7)
MemmoveUnalignedDst/2048 15.3GB/s ± 0% 27.5GB/s ± 0% +79.52% (p=0.002 n=5+8)
MemmoveUnalignedDst/4096 16.5GB/s ± 0% 28.9GB/s ± 0% +74.74% (p=0.002 n=5+8)
MemmoveUnalignedSrc/1 102MB/s ± 0% 100MB/s ± 0% -2.02% (p=0.000 n=5+7)
MemmoveUnalignedSrc/2 191MB/s ± 0% 200MB/s ± 0% +4.78% (p=0.002 n=5+8)
MemmoveUnalignedSrc/3 279MB/s ± 0% 300MB/s ± 0% +7.45% (p=0.002 n=5+8)
MemmoveUnalignedSrc/4 354MB/s ± 0% 400MB/s ± 0% +13.10% (p=0.002 n=5+8)
MemmoveUnalignedSrc/5 431MB/s ± 0% 500MB/s ± 0% +16.02% (p=0.002 n=5+8)
MemmoveUnalignedSrc/6 441MB/s ± 0% 600MB/s ± 0% +36.03% (p=0.002 n=5+8)
MemmoveUnalignedSrc/7 485MB/s ± 0% 700MB/s ± 0% +44.29% (p=0.002 n=5+8)
MemmoveUnalignedSrc/8 811MB/s ± 1% 800MB/s ± 0% -1.36% (p=0.016 n=5+8)
MemmoveUnalignedSrc/9 864MB/s ± 0% 900MB/s ± 0% +4.07% (p=0.002 n=5+8)
MemmoveUnalignedSrc/10 893MB/s ± 0% 999MB/s ± 0% +11.97% (p=0.002 n=5+8)
MemmoveUnalignedSrc/11 932MB/s ± 0% 1099MB/s ± 0% +18.01% (p=0.002 n=5+8)
MemmoveUnalignedSrc/12 988MB/s ± 0% 1199MB/s ± 0% +21.35% (p=0.002 n=5+8)
MemmoveUnalignedSrc/13 955MB/s ± 0% 1299MB/s ± 0% +36.02% (p=0.002 n=5+8)
MemmoveUnalignedSrc/14 955MB/s ± 0% 1399MB/s ± 0% +46.52% (p=0.002 n=5+8)
MemmoveUnalignedSrc/15 1.04GB/s ± 0% 1.50GB/s ± 0% +44.18% (p=0.002 n=5+8)
MemmoveUnalignedSrc/16 1.45GB/s ± 0% 1.60GB/s ± 0% +10.14% (p=0.002 n=5+8)
MemmoveUnalignedSrc/32 2.78GB/s ± 0% 3.20GB/s ± 0% +15.16% (p=0.003 n=5+7)
MemmoveUnalignedSrc/64 4.30GB/s ± 0% 5.72GB/s ± 0% +32.90% (p=0.003 n=5+7)
MemmoveUnalignedSrc/128 6.57GB/s ± 0% 8.42GB/s ± 0% +28.06% (p=0.002 n=5+8)
MemmoveUnalignedSrc/256 9.39GB/s ± 1% 13.33GB/s ± 0% +41.96% (p=0.002 n=5+8)
MemmoveUnalignedSrc/512 12.7GB/s ± 0% 18.8GB/s ± 0% +48.53% (p=0.003 n=5+7)
MemmoveUnalignedSrc/1024 13.6GB/s ± 0% 23.0GB/s ± 0% +69.82% (p=0.002 n=5+8)
MemmoveUnalignedSrc/2048 15.6GB/s ± 0% 26.8GB/s ± 3% +71.37% (p=0.002 n=5+8)
MemmoveUnalignedSrc/4096 16.5GB/s ± 0% 28.2GB/s ± 0% +71.40% (p=0.002 n=5+8)

Fixes #22925

Change-Id: I38c1a9ad5c6e3f4f95fc521c4b7e3140b58b4737
Reviewed-on: https://go-review.googlesource.com/83799
Run-TryBot: Cherry Zhang <cherryyz@google.com>
Reviewed-by: Cherry Zhang <cherryyz@google.com>

213a7517

Name	Last commit	Last update
..
cgo		Loading commit data...
debug		Loading commit data...
internal		Loading commit data...
msan		Loading commit data...
pprof		Loading commit data...
race		Loading commit data...
testdata		Loading commit data...
trace		Loading commit data...
HACKING.md		Loading commit data...
Makefile		Loading commit data...
alg.go		Loading commit data...
asm.s		Loading commit data...
asm_386.s		Loading commit data...
asm_amd64.s		Loading commit data...
asm_amd64p32.s		Loading commit data...
asm_arm.s		Loading commit data...
asm_arm64.s		Loading commit data...
asm_mips64x.s		Loading commit data...
asm_mipsx.s		Loading commit data...
asm_ppc64x.h		Loading commit data...
asm_ppc64x.s		Loading commit data...
asm_s390x.s		Loading commit data...
atomic_arm64.s		Loading commit data...
atomic_mips64x.s		Loading commit data...
atomic_mipsx.s		Loading commit data...
atomic_pointer.go		Loading commit data...
atomic_ppc64x.s		Loading commit data...
callers_test.go		Loading commit data...
cgo.go		Loading commit data...
cgo_mmap.go		Loading commit data...
cgo_ppc64x.go		Loading commit data...
cgo_sigaction.go		Loading commit data...
cgocall.go		Loading commit data...
cgocallback.go		Loading commit data...
cgocheck.go		Loading commit data...
chan.go		Loading commit data...
chan_test.go		Loading commit data...
chanbarrier_test.go		Loading commit data...
closure_test.go		Loading commit data...
compiler.go		Loading commit data...
complex.go		Loading commit data...
complex_test.go		Loading commit data...
cpuflags_amd64.go		Loading commit data...
cpuprof.go		Loading commit data...
cputicks.go		Loading commit data...
crash_cgo_test.go		Loading commit data...
crash_nonunix_test.go		Loading commit data...
crash_test.go		Loading commit data...
crash_unix_test.go		Loading commit data...
debug.go		Loading commit data...
defs1_linux.go		Loading commit data...
defs1_netbsd_386.go		Loading commit data...
defs1_netbsd_amd64.go		Loading commit data...
defs1_netbsd_arm.go		Loading commit data...
defs1_solaris_amd64.go		Loading commit data...
defs2_linux.go		Loading commit data...
defs3_linux.go		Loading commit data...
defs_arm_linux.go		Loading commit data...
defs_darwin.go		Loading commit data...
defs_darwin_386.go		Loading commit data...
defs_darwin_amd64.go		Loading commit data...
defs_darwin_arm.go		Loading commit data...
defs_darwin_arm64.go		Loading commit data...
defs_dragonfly.go		Loading commit data...
defs_dragonfly_amd64.go		Loading commit data...
defs_freebsd.go		Loading commit data...
defs_freebsd_386.go		Loading commit data...
defs_freebsd_amd64.go		Loading commit data...
defs_freebsd_arm.go		Loading commit data...
defs_linux.go		Loading commit data...
defs_linux_386.go		Loading commit data...
defs_linux_amd64.go		Loading commit data...
defs_linux_arm.go		Loading commit data...
defs_linux_arm64.go		Loading commit data...
defs_linux_mips64x.go		Loading commit data...
defs_linux_mipsx.go		Loading commit data...
defs_linux_ppc64.go		Loading commit data...
defs_linux_ppc64le.go		Loading commit data...
defs_linux_s390x.go		Loading commit data...
defs_nacl_386.go		Loading commit data...
defs_nacl_amd64p32.go		Loading commit data...
defs_nacl_arm.go		Loading commit data...
defs_netbsd.go		Loading commit data...
defs_netbsd_386.go		Loading commit data...
defs_netbsd_amd64.go		Loading commit data...
defs_netbsd_arm.go		Loading commit data...
defs_openbsd.go		Loading commit data...
defs_openbsd_386.go		Loading commit data...
defs_openbsd_amd64.go		Loading commit data...
defs_openbsd_arm.go		Loading commit data...
defs_plan9_386.go		Loading commit data...
defs_plan9_amd64.go		Loading commit data...
defs_plan9_arm.go		Loading commit data...
defs_solaris.go		Loading commit data...
defs_solaris_amd64.go		Loading commit data...
defs_windows.go		Loading commit data...
defs_windows_386.go		Loading commit data...
defs_windows_amd64.go		Loading commit data...
duff_386.s		Loading commit data...
duff_amd64.s		Loading commit data...
duff_arm.s		Loading commit data...
duff_arm64.s		Loading commit data...
duff_mips64x.s		Loading commit data...
duff_ppc64x.s		Loading commit data...
env_plan9.go		Loading commit data...
env_posix.go		Loading commit data...
env_test.go		Loading commit data...
error.go		Loading commit data...
example_test.go		Loading commit data...
export_arm_test.go		Loading commit data...
export_futex_test.go		Loading commit data...
export_linux_test.go		Loading commit data...
export_mmap_test.go		Loading commit data...
export_test.go		Loading commit data...
export_unix_test.go		Loading commit data...
export_windows_test.go		Loading commit data...
extern.go		Loading commit data...
fastlog2.go		Loading commit data...
fastlog2_test.go		Loading commit data...
fastlog2table.go		Loading commit data...
float.go		Loading commit data...
funcdata.h		Loading commit data...
futex_test.go		Loading commit data...
gc_test.go		Loading commit data...
gcinfo_test.go		Loading commit data...
go_tls.h		Loading commit data...
hash32.go		Loading commit data...
hash64.go		Loading commit data...
hash_test.go		Loading commit data...
heapdump.go		Loading commit data...
iface.go		Loading commit data...
iface_test.go		Loading commit data...
lfstack.go		Loading commit data...
lfstack_32bit.go		Loading commit data...
lfstack_64bit.go		Loading commit data...
lfstack_test.go		Loading commit data...
lock_futex.go		Loading commit data...
lock_sema.go		Loading commit data...
malloc.go		Loading commit data...
malloc_test.go		Loading commit data...
map.go		Loading commit data...
map_benchmark_test.go		Loading commit data...
map_fast32.go		Loading commit data...
map_fast64.go		Loading commit data...
map_faststr.go		Loading commit data...
map_test.go		Loading commit data...
mbarrier.go		Loading commit data...
mbitmap.go		Loading commit data...
mcache.go		Loading commit data...
mcentral.go		Loading commit data...
mem_bsd.go		Loading commit data...
mem_darwin.go		Loading commit data...
mem_linux.go		Loading commit data...
mem_plan9.go		Loading commit data...
mem_windows.go		Loading commit data...
memclr_386.s		Loading commit data...
memclr_amd64.s		Loading commit data...
memclr_amd64p32.s		Loading commit data...
memclr_arm.s		Loading commit data...
memclr_arm64.s		Loading commit data...
memclr_mips64x.s		Loading commit data...
memclr_mipsx.s		Loading commit data...
memclr_plan9_386.s		Loading commit data...
memclr_plan9_amd64.s		Loading commit data...
memclr_ppc64x.s		Loading commit data...
memclr_s390x.s		Loading commit data...
memmove_386.s		Loading commit data...
memmove_amd64.s		Loading commit data...
memmove_amd64p32.s		Loading commit data...
memmove_arm.s		Loading commit data...
memmove_arm64.s		Loading commit data...
memmove_linux_amd64_test.go		Loading commit data...
memmove_mips64x.s		Loading commit data...
memmove_mipsx.s		Loading commit data...
memmove_plan9_386.s		Loading commit data...
memmove_plan9_amd64.s		Loading commit data...
memmove_ppc64x.s		Loading commit data...
memmove_s390x.s		Loading commit data...
memmove_test.go		Loading commit data...
mfinal.go		Loading commit data...
mfinal_test.go		Loading commit data...
mfixalloc.go		Loading commit data...
mgc.go		Loading commit data...
mgclarge.go		Loading commit data...
mgcmark.go		Loading commit data...
mgcsweep.go		Loading commit data...
mgcsweepbuf.go		Loading commit data...
mgcwork.go		Loading commit data...
mheap.go		Loading commit data...
mkduff.go		Loading commit data...
mkfastlog2table.go		Loading commit data...
mknacl.sh		Loading commit data...
mksizeclasses.go		Loading commit data...
mmap.go		Loading commit data...
mprof.go		Loading commit data...
msan.go		Loading commit data...
msan0.go		Loading commit data...
msan_amd64.s		Loading commit data...
msize.go		Loading commit data...
mstats.go		Loading commit data...
mwbbuf.go		Loading commit data...
net_plan9.go		Loading commit data...
netpoll.go		Loading commit data...
netpoll_epoll.go		Loading commit data...
netpoll_kqueue.go		Loading commit data...
netpoll_nacl.go		Loading commit data...
netpoll_solaris.go		Loading commit data...
netpoll_stub.go		Loading commit data...
netpoll_windows.go		Loading commit data...
noasm.go		Loading commit data...
norace_linux_test.go		Loading commit data...
norace_test.go		Loading commit data...
numcpu_freebsd_test.go		Loading commit data...
os2_freebsd.go		Loading commit data...
os2_nacl.go		Loading commit data...
os2_openbsd.go		Loading commit data...
os2_plan9.go		Loading commit data...
os2_solaris.go		Loading commit data...
os3_plan9.go		Loading commit data...
os3_solaris.go		Loading commit data...
os_android.go		Loading commit data...
os_darwin.go		Loading commit data...
os_darwin_arm.go		Loading commit data...
os_darwin_arm64.go		Loading commit data...
os_dragonfly.go		Loading commit data...
os_freebsd.go		Loading commit data...
os_freebsd_arm.go		Loading commit data...
os_linux.go		Loading commit data...
os_linux_arm.go		Loading commit data...
os_linux_arm64.go		Loading commit data...
os_linux_be64.go		Loading commit data...
os_linux_generic.go		Loading commit data...
os_linux_mips64x.go		Loading commit data...
os_linux_mipsx.go		Loading commit data...
os_linux_noauxv.go		Loading commit data...
os_linux_ppc64x.go		Loading commit data...
os_linux_s390x.go		Loading commit data...
os_nacl.go		Loading commit data...
os_nacl_arm.go		Loading commit data...
os_netbsd.go		Loading commit data...
os_netbsd_386.go		Loading commit data...
os_netbsd_amd64.go		Loading commit data...
os_netbsd_arm.go		Loading commit data...
os_openbsd.go		Loading commit data...
os_openbsd_arm.go		Loading commit data...
os_plan9.go		Loading commit data...
os_plan9_arm.go		Loading commit data...
os_solaris.go		Loading commit data...
os_windows.go		Loading commit data...
panic.go		Loading commit data...
plugin.go		Loading commit data...
print.go		Loading commit data...
proc.go		Loading commit data...
proc_runtime_test.go		Loading commit data...
proc_test.go		Loading commit data...
profbuf.go		Loading commit data...
profbuf_test.go		Loading commit data...
proflabel.go		Loading commit data...
race.go		Loading commit data...
race0.go		Loading commit data...
race_amd64.s		Loading commit data...
rand_test.go		Loading commit data...
rdebug.go		Loading commit data...
relax_stub.go		Loading commit data...
rt0_android_386.s		Loading commit data...
rt0_android_amd64.s		Loading commit data...
rt0_android_arm.s		Loading commit data...
rt0_android_arm64.s		Loading commit data...
rt0_darwin_386.s		Loading commit data...
rt0_darwin_amd64.s		Loading commit data...
rt0_darwin_arm.s		Loading commit data...
rt0_darwin_arm64.s		Loading commit data...
rt0_dragonfly_amd64.s		Loading commit data...
rt0_freebsd_386.s		Loading commit data...
rt0_freebsd_amd64.s		Loading commit data...
rt0_freebsd_arm.s		Loading commit data...
rt0_linux_386.s		Loading commit data...
rt0_linux_amd64.s		Loading commit data...
rt0_linux_arm.s		Loading commit data...
rt0_linux_arm64.s		Loading commit data...
rt0_linux_mips64x.s		Loading commit data...
rt0_linux_mipsx.s		Loading commit data...
rt0_linux_ppc64.s		Loading commit data...
rt0_linux_ppc64le.s		Loading commit data...
rt0_linux_s390x.s		Loading commit data...
rt0_nacl_386.s		Loading commit data...
rt0_nacl_amd64p32.s		Loading commit data...
rt0_nacl_arm.s		Loading commit data...
rt0_netbsd_386.s		Loading commit data...
rt0_netbsd_amd64.s		Loading commit data...
rt0_netbsd_arm.s		Loading commit data...
rt0_openbsd_386.s		Loading commit data...
rt0_openbsd_amd64.s		Loading commit data...
rt0_openbsd_arm.s		Loading commit data...
rt0_plan9_386.s		Loading commit data...
rt0_plan9_amd64.s		Loading commit data...
rt0_plan9_arm.s		Loading commit data...
rt0_solaris_amd64.s		Loading commit data...
rt0_windows_386.s		Loading commit data...
rt0_windows_amd64.s		Loading commit data...
runtime-gdb.py		Loading commit data...
runtime-gdb_test.go		Loading commit data...
runtime-lldb_test.go		Loading commit data...
runtime.go		Loading commit data...
runtime1.go		Loading commit data...
runtime2.go		Loading commit data...
runtime_linux_test.go		Loading commit data...
runtime_mmap_test.go		Loading commit data...
runtime_test.go		Loading commit data...
runtime_unix_test.go		Loading commit data...
rwmutex.go		Loading commit data...
rwmutex_test.go		Loading commit data...
select.go		Loading commit data...
sema.go		Loading commit data...
sigaction_linux.go		Loading commit data...
signal_386.go		Loading commit data...
signal_amd64x.go		Loading commit data...
signal_arm.go		Loading commit data...
signal_arm64.go		Loading commit data...
signal_darwin.go		Loading commit data...
signal_darwin_386.go		Loading commit data...
signal_darwin_amd64.go		Loading commit data...
signal_darwin_arm.go		Loading commit data...
signal_darwin_arm64.go		Loading commit data...
signal_dragonfly.go		Loading commit data...
signal_dragonfly_amd64.go		Loading commit data...
signal_freebsd.go		Loading commit data...
signal_freebsd_386.go		Loading commit data...
signal_freebsd_amd64.go		Loading commit data...
signal_freebsd_arm.go		Loading commit data...
signal_linux_386.go		Loading commit data...
signal_linux_amd64.go		Loading commit data...
signal_linux_arm.go		Loading commit data...
signal_linux_arm64.go		Loading commit data...
signal_linux_mips64x.go		Loading commit data...
signal_linux_mipsx.go		Loading commit data...
signal_linux_ppc64x.go		Loading commit data...
signal_linux_s390x.go		Loading commit data...
signal_mips64x.go		Loading commit data...
signal_mipsx.go		Loading commit data...
signal_nacl.go		Loading commit data...
signal_nacl_386.go		Loading commit data...
signal_nacl_amd64p32.go		Loading commit data...
signal_nacl_arm.go		Loading commit data...
signal_netbsd.go		Loading commit data...
signal_netbsd_386.go		Loading commit data...
signal_netbsd_amd64.go		Loading commit data...
signal_netbsd_arm.go		Loading commit data...
signal_openbsd.go		Loading commit data...
signal_openbsd_386.go		Loading commit data...
signal_openbsd_amd64.go		Loading commit data...
signal_openbsd_arm.go		Loading commit data...
signal_plan9.go		Loading commit data...
signal_ppc64x.go		Loading commit data...
signal_sighandler.go		Loading commit data...
signal_solaris.go		Loading commit data...
signal_solaris_amd64.go		Loading commit data...
signal_unix.go		Loading commit data...
signal_windows.go		Loading commit data...
sigqueue.go		Loading commit data...
sigqueue_plan9.go		Loading commit data...
sigtab_linux_generic.go		Loading commit data...
sigtab_linux_mipsx.go		Loading commit data...
sizeclasses.go		Loading commit data...
slice.go		Loading commit data...
slice_test.go		Loading commit data...
softfloat64.go		Loading commit data...
softfloat64_test.go		Loading commit data...
softfloat_arm.go		Loading commit data...
sqrt.go		Loading commit data...
sqrt_test.go		Loading commit data...
stack.go		Loading commit data...
stack_test.go		Loading commit data...
string.go		Loading commit data...
string_test.go		Loading commit data...
stubs.go		Loading commit data...
stubs2.go		Loading commit data...
stubs32.go		Loading commit data...
stubs_android.go		Loading commit data...
stubs_asm.go		Loading commit data...
stubs_linux.go		Loading commit data...
stubs_nonlinux.go		Loading commit data...
symtab.go		Loading commit data...
symtab_test.go		Loading commit data...
sys_arm.go		Loading commit data...
sys_arm64.go		Loading commit data...
sys_darwin_386.s		Loading commit data...
sys_darwin_amd64.s		Loading commit data...
sys_darwin_arm.s		Loading commit data...
sys_darwin_arm64.s		Loading commit data...
sys_dragonfly_amd64.s		Loading commit data...
sys_freebsd_386.s		Loading commit data...
sys_freebsd_amd64.s		Loading commit data...
sys_freebsd_arm.s		Loading commit data...
sys_linux_386.s		Loading commit data...
sys_linux_amd64.s		Loading commit data...
sys_linux_arm.s		Loading commit data...
sys_linux_arm64.s		Loading commit data...
sys_linux_mips64x.s		Loading commit data...
sys_linux_mipsx.s		Loading commit data...
sys_linux_ppc64x.s		Loading commit data...
sys_linux_s390x.s		Loading commit data...
sys_mips64x.go		Loading commit data...
sys_mipsx.go		Loading commit data...
sys_nacl_386.s		Loading commit data...
sys_nacl_amd64p32.s		Loading commit data...
sys_nacl_arm.s		Loading commit data...
sys_netbsd_386.s		Loading commit data...
sys_netbsd_amd64.s		Loading commit data...
sys_netbsd_arm.s		Loading commit data...
sys_nonppc64x.go		Loading commit data...
sys_openbsd_386.s		Loading commit data...
sys_openbsd_amd64.s		Loading commit data...
sys_openbsd_arm.s		Loading commit data...
sys_plan9_386.s		Loading commit data...
sys_plan9_amd64.s		Loading commit data...
sys_plan9_arm.s		Loading commit data...
sys_ppc64x.go		Loading commit data...
sys_s390x.go		Loading commit data...
sys_solaris_amd64.s		Loading commit data...
sys_windows_386.s		Loading commit data...
sys_windows_amd64.s		Loading commit data...
sys_x86.go		Loading commit data...
syscall2_solaris.go		Loading commit data...
syscall_nacl.h		Loading commit data...
syscall_solaris.go		Loading commit data...
syscall_windows.go		Loading commit data...
syscall_windows_test.go		Loading commit data...
textflag.h		Loading commit data...
time.go		Loading commit data...
timeasm.go		Loading commit data...
timestub.go		Loading commit data...
tls_arm.s		Loading commit data...
tls_arm64.h		Loading commit data...
tls_arm64.s		Loading commit data...
tls_mips64x.s		Loading commit data...
tls_mipsx.s		Loading commit data...
tls_ppc64x.s		Loading commit data...
tls_s390x.s		Loading commit data...
trace.go		Loading commit data...
traceback.go		Loading commit data...
type.go		Loading commit data...
typekind.go		Loading commit data...
unaligned1.go		Loading commit data...
unaligned2.go		Loading commit data...
utf8.go		Loading commit data...
vdso_elf32.go		Loading commit data...
vdso_elf64.go		Loading commit data...
vdso_linux.go		Loading commit data...
vdso_linux_386.go		Loading commit data...
vdso_linux_amd64.go		Loading commit data...
vdso_linux_test.go		Loading commit data...
vdso_none.go		Loading commit data...
vlop_386.s		Loading commit data...
vlop_arm.s		Loading commit data...
vlop_arm_test.go		Loading commit data...
vlrt.go		Loading commit data...
wincallback.go		Loading commit data...
write_err.go		Loading commit data...
write_err_android.go		Loading commit data...
zcallback_windows.go		Loading commit data...
zcallback_windows.s		Loading commit data...