Received: by 2002:ac0:a582:0:0:0:0:0 with SMTP id m2-v6csp950776imm; Fri, 5 Oct 2018 14:58:09 -0700 (PDT) X-Google-Smtp-Source: ACcGV60Ohu9l3Sdfaq0dpIUG2kKp0X2SOEgev3mV7xyJm6O4nOvpuXe38tyyeWl6gYTgxjN42Q0h X-Received: by 2002:a63:6946:: with SMTP id e67-v6mr11755380pgc.119.1538776689737; Fri, 05 Oct 2018 14:58:09 -0700 (PDT) ARC-Seal: i=1; a=rsa-sha256; t=1538776689; cv=none; d=google.com; s=arc-20160816; b=lMjUa8j7csz/m1nUFC2S2PpECdbpZhxxV4Cu4IAI0XatmTwkrK+IC0h5RMIiQDDalO oiAo0uHIygkSSPW/XMtKttdF9EIGNYNjwL4tqG8t51FhQeZ+PJ8jiQalP8mxOb8pWNyM mrNelMMSRwmF5wP2XnXfRg65lJB5JynnPI5oN8ehZnHv0tSyfCYxKHi/ZaWDW1Tj20Ay n6pI3x0qM7XTCGAAgA3AZ8n6WsZklgv3RcSEj16onaAFqg0OUCsee7yjwwPbzw6Ire3O zP5b+rjXmGjeLqHYeX5rUundow7g/2gudUExOP7FfakEW7EbENqw2nJG/jSMHGvTxBZI jADQ== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=arc-20160816; h=list-id:precedence:sender:to:subject:message-id:date:from :in-reply-to:references:mime-version:dkim-signature; bh=Rl24sJAi0Y2HiAPQyt9R0IT0oB0epHMd3uPDxXcutMo=; b=bgokBbjkAJjnZONjryfA6sCrT5mVSz1jRKg8MCa350lqJlARQrnbfS79mo7wSgcFLG 9muBtdVfrjRfhgoN0SdWqOo673x8oK+J0YgCTDXs6ClIrhnOCmtsJCK9EQnhqGEH/uLH /RSnaEBwPdNZDTZAR5JgCb7srXKvSF8YEcN2Ty5MSTl+bipglNPMTY5rS/YjNxrxRx/w XOl+k3nuw+AdWtqq/lQDUsgJrKJMxhx7WordPNsdLqzxtU5OnzxQm6dAhe49HmYs18/6 VXZ60Uwqwz0B9vLNdfjUvxb5S1lGwk1viQL47nbm6z/QLjrJRGntwo8TCdcb6+l329Pb aMjQ== ARC-Authentication-Results: i=1; mx.google.com; dkim=pass header.i=@gmail.com header.s=20161025 header.b=awNqDUPJ; spf=pass (google.com: best guess record for domain of linux-kernel-owner@vger.kernel.org designates 209.132.180.67 as permitted sender) smtp.mailfrom=linux-kernel-owner@vger.kernel.org; dmarc=pass (p=NONE sp=QUARANTINE dis=NONE) header.from=gmail.com Return-Path: Received: from vger.kernel.org (vger.kernel.org. [209.132.180.67]) by mx.google.com with ESMTP id p7-v6si9481284plo.159.2018.10.05.14.57.53; Fri, 05 Oct 2018 14:58:09 -0700 (PDT) Received-SPF: pass (google.com: best guess record for domain of linux-kernel-owner@vger.kernel.org designates 209.132.180.67 as permitted sender) client-ip=209.132.180.67; Authentication-Results: mx.google.com; dkim=pass header.i=@gmail.com header.s=20161025 header.b=awNqDUPJ; spf=pass (google.com: best guess record for domain of linux-kernel-owner@vger.kernel.org designates 209.132.180.67 as permitted sender) smtp.mailfrom=linux-kernel-owner@vger.kernel.org; dmarc=pass (p=NONE sp=QUARANTINE dis=NONE) header.from=gmail.com Received: (majordomo@vger.kernel.org) by vger.kernel.org via listexpand id S1729141AbeJFE5G (ORCPT + 99 others); Sat, 6 Oct 2018 00:57:06 -0400 Received: from mail-ua1-f65.google.com ([209.85.222.65]:36180 "EHLO mail-ua1-f65.google.com" rhost-flags-OK-OK-OK-OK) by vger.kernel.org with ESMTP id S1726037AbeJFE4y (ORCPT ); Sat, 6 Oct 2018 00:56:54 -0400 Received: by mail-ua1-f65.google.com with SMTP id b3so5235689uak.3 for ; Fri, 05 Oct 2018 14:56:14 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20161025; h=mime-version:references:in-reply-to:from:date:message-id:subject:to; bh=Rl24sJAi0Y2HiAPQyt9R0IT0oB0epHMd3uPDxXcutMo=; b=awNqDUPJj+9P9OXhQ2Q/oHmb1zPeVm85B33J+11ZBYgW49GVDkJa/l0GeWVoq/hncp Hw2POhbXPT4UiqnMqjJrKbYOTu87cPcLBbO00VwpHZCN/YArA+Mj2iaOCoX7TpQ96tIl A1LiCITjEAVnwAvXa5hJzTQ46UXSDVH0bJcjWhcKUkIJGtdwhgP4N+6oQuwM52hO9P91 B8UK90Be/CAhFr0fZwgs1Q0eWegFrNYO0hoVVGBuSn1TcF1IKcL7kfE4ulPxkeYmeN9I qRHoiAb2gJW7zIvbbkYmyNLboGwwgtMSJJPiStNuwXPWCtCaspf9qJbQ6HYgSQi9aJa7 J5QA== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:mime-version:references:in-reply-to:from:date :message-id:subject:to; bh=Rl24sJAi0Y2HiAPQyt9R0IT0oB0epHMd3uPDxXcutMo=; b=pz7CytrNt6NdZYHVoF8CKuUySlslXoaX75obAaozxizgIuMPktI4Ybsbvoca2+m5ie 7372JcvdF9+P1V8P0g0K3PyT55bq3gcUi2CX+o6Povd4sH12mflCFPL/vuswQJ7dV1m8 /e3yM4RrWXwaVGgOpEjcwgncO4Drs9VgbPBgSwdIVlwgmma//CgLS6+CEAgvq7mR3Z8Y hKG6B//beA2SL9WmADW7XhOsQ8I8wJTsW54U4WfmNfU3jvtZ32iXRZ4MRWBTr8AqI3Xu cCHMF6CBuBwJiRiWCwbsN52S+ICg2loxpBxqN/WgxYogjAzW9kxZKaRx7JV7Lq2q4klk Prjg== X-Gm-Message-State: ABuFfohDPtoCSnHyS5qGMC50+s5J2iYoZx2PAeaZ5hhGYqbsiXsp44LF QDR9vpkV3TGY9i9a6S51utephQeIbQTssf6hpCzwVvhL X-Received: by 2002:ab0:6607:: with SMTP id r7mr4563049uam.6.1538776573350; Fri, 05 Oct 2018 14:56:13 -0700 (PDT) MIME-Version: 1.0 References: In-Reply-To: From: Sebastian Kuzminsky Date: Fri, 5 Oct 2018 15:56:02 -0600 Message-ID: Subject: Re: hung task in 4.14 (syzbot bug from 2018 April 17) To: linux-kernel@vger.kernel.org Content-Type: text/plain; charset="UTF-8" Sender: linux-kernel-owner@vger.kernel.org Precedence: bulk List-ID: X-Mailing-List: linux-kernel@vger.kernel.org Another instance of the same problem (also on 4.14.67), this time with the hung task timeout restored to its 120 second default: [ 980.954129] INFO: task systemd:1 blocked for more than 120 seconds. [ 980.954132] Tainted: G OE 4.14.67-solidfire1 #1 [ 980.954133] "echo 0 > /proc/sys/kernel/hung_task_timeout_secs" disables this message. [ 980.954135] systemd D 0 1 0 0x00000000 [ 980.954137] Call Trace: [ 980.954150] ? __schedule+0x27f/0x870 [ 980.954154] ? check_preempt_wakeup+0x102/0x230 [ 980.954156] schedule+0x28/0x80 [ 980.954159] schedule_timeout+0x1e7/0x340 [ 980.954163] ? radix_tree_node_ctor+0x20/0x20 [ 980.954165] ? delete_node+0x1b8/0x1f0 [ 980.954167] ? wait_for_completion+0xb0/0x120 [ 980.954169] wait_for_completion+0xb0/0x120 [ 980.954172] ? wake_up_q+0x70/0x70 [ 980.954176] flush_work+0x10d/0x1c0 [ 980.954179] ? worker_detach_from_pool+0xa0/0xa0 [ 980.954183] fsnotify_destroy_group+0x34/0xa0 [ 980.954185] inotify_release+0x1a/0x50 [ 980.954189] __fput+0xd8/0x220 [ 980.954194] task_work_run+0x8a/0xb0 [ 980.954198] exit_to_usermode_loop+0xb9/0xc0 [ 980.954200] do_syscall_64+0x10b/0x120 [ 980.954203] entry_SYSCALL_64_after_hwframe+0x3d/0xa2 [ 980.954206] RIP: 0033:0x7f031a552900 [ 980.954208] RSP: 002b:00007fff93fd18b0 EFLAGS: 00000293 ORIG_RAX: 0000000000000003 [ 980.954210] RAX: 0000000000000000 RBX: 0000000000000010 RCX: 00007f031a552900 [ 980.954211] RDX: 0000000000000000 RSI: 0000000000000000 RDI: 0000000000000010 [ 980.954212] RBP: 00007f031beba088 R08: 0000000000000020 R09: 000055ac5a21e2ad [ 980.954213] R10: 0000000000000000 R11: 0000000000000293 R12: 0000000000000000 [ 980.954214] R13: 000055ac5a488b20 R14: 000055ac5c0907f0 R15: 0000000000000000 [ 980.954724] INFO: task kworker/u114:4:41909 blocked for more than 120 seconds. [ 980.954725] Tainted: G OE 4.14.67-solidfire1 #1 [ 980.954726] "echo 0 > /proc/sys/kernel/hung_task_timeout_secs" disables this message. [ 980.954727] kworker/u114:4 D 0 41909 2 0x80000000 [ 980.954733] Workqueue: events_unbound fsnotify_mark_destroy_workfn [ 980.954734] Call Trace: [ 980.954739] ? __schedule+0x27f/0x870 [ 980.954741] schedule+0x28/0x80 [ 980.954743] schedule_timeout+0x1e7/0x340 [ 980.954746] ? __switch_to_asm+0x40/0x70 [ 980.954747] ? update_curr+0xe1/0x1a0 [ 980.954750] ? wait_for_completion+0xb0/0x120 [ 980.954751] wait_for_completion+0xb0/0x120 [ 980.954753] ? wake_up_q+0x70/0x70 [ 980.954758] __synchronize_srcu.part.13+0x76/0x90 [ 980.954761] ? trace_raw_output_rcu_utilization+0x40/0x40 [ 980.954762] ? try_to_wake_up+0x44/0x460 [ 980.954765] ? fsnotify_mark_destroy_workfn+0x67/0xb0 [ 980.954767] fsnotify_mark_destroy_workfn+0x67/0xb0 [ 980.954769] process_one_work+0x1da/0x3d0 [ 980.954772] worker_thread+0x21f/0x3f0 [ 980.954775] ? process_one_work+0x3d0/0x3d0 [ 980.954777] kthread+0x119/0x130 [ 980.954779] ? kthread_create_on_node+0x40/0x40 [ 980.954781] ret_from_fork+0x35/0x40 crash> print reaper_work $3 = { work = { data = { counter = -117148584927483 }, entry = { next = 0xffff95743772b770, prev = 0xffffa2aa800a3df8 }, func = 0xffffffffa8249df0 }, timer = { entry = { next = 0xdead000000000200, pprev = 0x0 }, expires = 4295020559, function = 0xffffffffa80778c0, data = 18446744072250514272, flags = 69206020 }, wq = 0xffff95443f011400, cpu = 128 } Any input is welcome. -- Sebastian Kuzminsky