diff options
| author | Paolo Abeni <pabeni@redhat.com> | 2022-10-22 00:58:54 +0200 |
|---|---|---|
| committer | Jakub Kicinski <kuba@kernel.org> | 2022-10-25 06:13:55 +0200 |
| commit | e72e4032637f4646554794ac28a3abecc6c2416d (patch) | |
| tree | 450eaea62bb1923c1b52664e71b4558b079285bc /net/rds/recv.c | |
| parent | net: lan966x: Stop replacing tx dcbs and dcbs_buf when changing MTU (diff) | |
| download | linux-e72e4032637f4646554794ac28a3abecc6c2416d.tar.xz linux-e72e4032637f4646554794ac28a3abecc6c2416d.zip | |
mptcp: set msk local address earlier
The mptcp_pm_nl_get_local_id() code assumes that the msk local address
is available at that point. For passive sockets, we initialize such
address at accept() time.
Depending on the running configuration and the user-space timing, a
passive MPJ subflow can join the msk socket before accept() completes.
In such case, the PM assigns a wrong local id to the MPJ subflow
and later PM netlink operations will end-up touching the wrong/unexpected
subflow.
All the above causes sporadic self-tests failures, especially when
the host is heavy loaded.
Closes: https://github.com/multipath-tcp/mptcp_net-next/issues/308
Fixes: 01cacb00b35c ("mptcp: add netlink-based PM")
Fixes: d045b9eb95a9 ("mptcp: introduce implicit endpoints")
Reviewed-by: Mat Martineau <mathew.j.martineau@linux.intel.com>
Signed-off-by: Paolo Abeni <pabeni@redhat.com>
Signed-off-by: Mat Martineau <mathew.j.martineau@linux.intel.com>
Signed-off-by: Jakub Kicinski <kuba@kernel.org>
Diffstat (limited to 'net/rds/recv.c')
0 files changed, 0 insertions, 0 deletions