Description (CNA)
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 (CNA)
| Vendor / product | Versions |
|---|---|
| Linux / Linux | affected 141694df6573b49aa4143c92556544b4b0bbda72 before 338d40bab283da2639780ee3e458fb61f1567d8c; affected 141694df6573b49aa4143c92556544b4b0bbda72 before 7896dbe990d56d5bb8097863b2645355633665eb; affected 141694df6573b49aa4143c92556544b4b0bbda72 before 455e882192c9833f176f3fbbbb2f036b6c5bf555; affected 141694df6573b49aa4143c92556544b4b0bbda72 before 51223bdd0f60b06cfc7f25885c4d4be917adba94; affected 141694df6573b49aa4143c92556544b4b0bbda72 before 1f1b9523527df02685dde603f20ff6e603d8e4a1; affected 141694df6573b49aa4143c92556544b4b0bbda72 before e2a9eeb69f7d4ca4cf4c70463af77664fdb6ab1d |
| Linux / Linux | affected 5.11; unaffected 0 before 5.11; unaffected 5.15.201 through 5.15.*; unaffected 6.1.164 through 6.1.*; unaffected 6.6.125 through 6.6.*; unaffected 6.12.72 through 6.12.*; unaffected 6.18.9 through 6.18.*; unaffected 6.19 through * |
CWE
No CWE identifiers supplied.
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