v9: - use queue_rcu_work to release the listening socket. - squash v8's patch 2 with patch 3. - add two new patches, "mptcp: drop unused skb in subflow_token_join_request" and "mptcp: add a new helper subflow_req_create_thmac" v8: - release the listening socket when removing the entry. - initialize addr.port and lsk in mptcp_pm_nl_get_local_id(). - change kernel_listen's backlog to 1024. - enable address_zero's use_port. v7: - use the MPTCP listening socket instead of TCP one - release subflow_req->msk in subflow_init_req - add mismatched port MIBs - use sock_common in source_address v6: - create and bind the listening socket in mptcp_nl_cmd_add_addr. - drop the patch "mptcp: add port number listened in kernel check" in v5. v5: - use the per netns listening socket. - First 8 patches in v4 had been merged to the export branch, drop them from this patchset. v4: - hold msk->pm.lock in mptcp_pm_sport_in_anno_list. - Merge the patchset 'Squash to "ADD_ADDR: ports support v3"' into v4. v3: - add two new patches, 8 and 11 - add more IS_ENABLED(CONFIG_MPTCP_IPV6) in patch 2 - define TCPOLEN_MPTCP_ADD_ADDR_HMAC in patch 4 - add flags check in patch 10 - update the testcases v2: - change mptcp_out_options's port field in CPU bype order. - keep mptcp_options_received's port field in CPU bype order. - add two new patches to simplify ADD_ADDR suboption writing. - update mptcp_add_addr_len helper use adding up size. - add more commit messages. v1: This series is the first version of ADD_ADDR ports support. I have solved the listener problem which I mentioned at the meeting on 15th of October by adding a new listening socket from the userspace (see patch 8). Up to now this patchset works well. Closes: https://github.com/multipath-tcp/mptcp_net-next/issues/54 Geliang Tang (9): mptcp: create the listening socket for new port mptcp: drop unused skb in subflow_token_join_request mptcp: add a new helper subflow_req_create_thmac mptcp: add port number check for MP_JOIN mptcp: enable use_port when invoke addresses_equal mptcp: deal with MPTCP_PM_ADDR_ATTR_PORT in PM netlink selftests: mptcp: add port argument for pm_nl_ctl mptcp: add the mibs for ADD_ADDR with port selftests: mptcp: add testcases for ADD_ADDR with port net/mptcp/mib.c | 6 + net/mptcp/mib.h | 6 + net/mptcp/options.c | 4 + net/mptcp/pm_netlink.c | 132 ++++++++++++++- net/mptcp/protocol.c | 2 +- net/mptcp/protocol.h | 5 + net/mptcp/subflow.c | 79 +++++++-- .../testing/selftests/net/mptcp/mptcp_join.sh | 160 +++++++++++++++++- tools/testing/selftests/net/mptcp/pm_nl_ctl.c | 24 ++- 9 files changed, 393 insertions(+), 25 deletions(-) -- 2.29.2