syzbot |
sign-in | mailing list | source | docs |
WARNING: DATA RACE
Read at 0x00c0034df368 by goroutine 319:
reflect.typedmemmove()
GOROOT/src/runtime/mbarrier.go:178 +0x0
reflect.packEface()
GOROOT/src/reflect/value.go:123 +0xae
reflect.valueInterface()
GOROOT/src/reflect/value.go:1394 +0x18a
reflect.Value.Interface()
GOROOT/src/reflect/value.go:1364 +0xc9
fmt.(*pp).printValue()
GOROOT/src/fmt/print.go:722 +0xca
fmt.(*pp).printValue()
GOROOT/src/fmt/print.go:876 +0x12be
fmt.(*pp).printArg()
GOROOT/src/fmt/print.go:712 +0xdf4
fmt.(*pp).doPrintf()
GOROOT/src/fmt/print.go:1026 +0x46f
fmt.Sprintf()
GOROOT/src/fmt/print.go:219 +0x67
gvisor.dev/gvisor/pkg/sentry/fsimpl/kernfs.(*OrderedChildren).checkExistingLocked()
pkg/sentry/fsimpl/kernfs/inode_impl_util.go:593 +0x20f
gvisor.dev/gvisor/pkg/sentry/fsimpl/kernfs.(*OrderedChildren).Unlink()
pkg/sentry/fsimpl/kernfs/inode_impl_util.go:605 +0x114
gvisor.dev/gvisor/pkg/sentry/fsimpl/kernfs.(*OrderedChildren).RmDir()
pkg/sentry/fsimpl/kernfs/inode_impl_util.go:617 +0x386
gvisor.dev/gvisor/pkg/sentry/fsimpl/cgroupfs.(*dir).RmDir()
pkg/sentry/fsimpl/cgroupfs/cgroupfs.go:534 +0x34e
gvisor.dev/gvisor/pkg/sentry/fsimpl/cgroupfs.(*cgroupInode).RmDir()
<autogenerated>:1 +0x8b
gvisor.dev/gvisor/pkg/sentry/fsimpl/kernfs.(*Filesystem).RmdirAt()
pkg/sentry/fsimpl/kernfs/filesystem.go:793 +0x52a
gvisor.dev/gvisor/pkg/sentry/fsimpl/cgroupfs.(*filesystem).RmdirAt()
<autogenerated>:1 +0x64
gvisor.dev/gvisor/pkg/sentry/vfs.(*VirtualFilesystem).RmdirAt()
pkg/sentry/vfs/vfs.go:562 +0x1f3
gvisor.dev/gvisor/pkg/sentry/syscalls/linux/vfs2.rmdirat()
pkg/sentry/syscalls/linux/vfs2/filesystem.go:263 +0x1e8
gvisor.dev/gvisor/pkg/sentry/syscalls/linux/vfs2.Unlinkat()
pkg/sentry/syscalls/linux/vfs2/filesystem.go:296 +0x53
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).executeSyscall()
pkg/sentry/kernel/task_syscall.go:103 +0x4db
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).doSyscallInvoke()
pkg/sentry/kernel/task_syscall.go:238 +0x69
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).doSyscallEnter()
pkg/sentry/kernel/task_syscall.go:198 +0x8e
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).doSyscall()
pkg/sentry/kernel/task_syscall.go:173 +0x3c4
gvisor.dev/gvisor/pkg/sentry/kernel.(*runApp).execute()
pkg/sentry/kernel/task_run.go:254 +0x1697
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).run()
pkg/sentry/kernel/task_run.go:95 +0x35a
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).Start·dwrap·235()
pkg/sentry/kernel/task_start.go:339 +0x47
Previous write at 0x00c0034df368 by goroutine 290:
sync/atomic.AddInt32()
src/runtime/race_amd64.s:305 +0xb
sync/atomic.AddInt32()
<autogenerated>:1 +0x1a
gvisor.dev/gvisor/pkg/sync.(*CrossGoroutineMutex).Unlock()
pkg/sync/mutex_unsafe.go:44 +0x30
gvisor.dev/gvisor/pkg/sync.(*Mutex).Unlock()
pkg/sync/mutex_unsafe.go:91 +0x25
gvisor.dev/gvisor/pkg/sentry/fs/lock.(*Locks).UnlockRegion·dwrap·3()
pkg/sentry/fs/lock/lock.go:197 +0x39
gvisor.dev/gvisor/pkg/sentry/fs/lock.(*Locks).UnlockRegion()
pkg/sentry/fs/lock/lock.go:204 +0xf4
gvisor.dev/gvisor/pkg/sentry/vfs.(*FileLocks).UnlockPOSIX()
pkg/sentry/vfs/lock.go:70 +0x6e
gvisor.dev/gvisor/pkg/sentry/vfs.(*LockFD).UnlockPOSIX()
pkg/sentry/vfs/file_description_impl_util.go:461 +0x37
gvisor.dev/gvisor/pkg/sentry/fsimpl/kernfs.(*GenericDirectoryFD).UnlockPOSIX()
<autogenerated>:1 +0x8b
gvisor.dev/gvisor/pkg/sentry/vfs.(*FileDescription).UnlockPOSIX()
pkg/sentry/vfs/file_description.go:855 +0xd3
gvisor.dev/gvisor/pkg/sentry/kernel.(*FDTable).dropVFS2()
pkg/sentry/kernel/fd_table.go:162 +0x8a
gvisor.dev/gvisor/pkg/sentry/kernel.(*FDTable).RemoveIf()
pkg/sentry/kernel/fd_table.go:714 +0x204
gvisor.dev/gvisor/pkg/sentry/kernel.(*FDTable).DecRef.func1()
pkg/sentry/kernel/fd_table.go:184 +0x53
gvisor.dev/gvisor/pkg/sentry/kernel.(*FDTableRefs).DecRef()
bazel-out/k8-fastbuild-ST-fa7f2b6368d1/bin/pkg/sentry/kernel/fd_table_refs.go:131 +0x5e
gvisor.dev/gvisor/pkg/sentry/kernel.(*FDTable).DecRef()
pkg/sentry/kernel/fd_table.go:183 +0x6e
gvisor.dev/gvisor/pkg/sentry/kernel.(*runExitMain).execute()
pkg/sentry/kernel/task_exit.go:248 +0x4f3
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).run()
pkg/sentry/kernel/task_run.go:95 +0x35a
gvisor.dev/gvisor/pkg/sentry/kernel.(*Task).Start·dwrap·235()
pkg/sentry/kernel/task_start.go:339 +0x47
| Time | Kernel | Commit | Syzkaller | Config | Log | Report | Syz repro | C repro | VM info | Assets (help?) | Manager | Title |
|---|---|---|---|---|---|---|---|---|---|---|---|---|
| 2022/03/02 15:35 | gvisor | 5cfaa79a1a20 | 45a13a73 | .config | console log | report | syz | C | ci-gvisor-ptrace-2-race | DATA RACE in kernfs.(*OrderedChildren).checkExistingLocked |