[MPTCP] [MPTCP][PATCH v10 mptcp-next 0/9] ADD_ADDR: ports support

[MPTCP] [MPTCP][PATCH v10 mptcp-next 0/9] ADD_ADDR: ports support

[Geliang Tang]

[-- Attachment #1: Type: text/plain, Size: 3270 bytes --]

v10:
 - use &w->rwork in mptcp_pm_free_addr_entry instead of casting w
 - rebase on export/20210113T185637
 - please apply this patchset after the following patchsets:
    add IPv4-mapped address support (v5)
    mptcp: create subflow for newly added address and testcases (v5)

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