Description
In the Linux kernel, the following vulnerability has been resolved: mptcp: fix race in mptcp_pm_nl_flush_addrs_doit() syzbot and Eulgyu Kim reported crashes in mptcp_pm_nl_get_local_id() and/or mptcp_pm_nl_is_backup() Root cause is list_splice_init() in mptcp_pm_nl_flush_addrs_doit() which is not RCU ready. list_splice_init_rcu() can not be called here while holding pernet->lock spinlock. Many thanks to Eulgyu Kim for providing a repro and testing our patches.
Affected products
Version statuses are supplied by the assigning organization. Consult the original record for detailed ranges and platform conditions.
Linux Linux
Default version status: unaffected
141694df6573b49aa4143c92556544b4b0bbda72 to < 338d40bab283da2639780ee3e458fb61f1567d8caffected141694df6573b49aa4143c92556544b4b0bbda72 to < 7896dbe990d56d5bb8097863b2645355633665ebaffected141694df6573b49aa4143c92556544b4b0bbda72 to < 455e882192c9833f176f3fbbbb2f036b6c5bf555affected141694df6573b49aa4143c92556544b4b0bbda72 to < 51223bdd0f60b06cfc7f25885c4d4be917adba94affected141694df6573b49aa4143c92556544b4b0bbda72 to < 1f1b9523527df02685dde603f20ff6e603d8e4a1affected141694df6573b49aa4143c92556544b4b0bbda72 to < e2a9eeb69f7d4ca4cf4c70463af77664fdb6ab1daffected
Linux Linux
Default version status: affected
5.11affected0 to < 5.11unaffected5.15.201 to ≤ 5.15.*unaffected6.1.164 to ≤ 6.1.*unaffected6.6.125 to ≤ 6.6.*unaffected6.12.72 to ≤ 6.12.*unaffected6.18.9 to ≤ 6.18.*unaffected6.19 to ≤ *unaffected
References
- https://git.kernel.org/stable/c/338d40bab283da2639780ee3e458fb61f1567d8c ↗
- https://git.kernel.org/stable/c/7896dbe990d56d5bb8097863b2645355633665eb ↗
- https://git.kernel.org/stable/c/455e882192c9833f176f3fbbbb2f036b6c5bf555 ↗
- https://git.kernel.org/stable/c/51223bdd0f60b06cfc7f25885c4d4be917adba94 ↗
- https://git.kernel.org/stable/c/1f1b9523527df02685dde603f20ff6e603d8e4a1 ↗
- https://git.kernel.org/stable/c/e2a9eeb69f7d4ca4cf4c70463af77664fdb6ab1d ↗