* [Weekly meetings] MoM - 2nd of July 2025
@ 2025-07-02 17:15 Matthieu Baerts
0 siblings, 0 replies; only message in thread
From: Matthieu Baerts @ 2025-07-02 17:15 UTC (permalink / raw)
To: MPTCP Linux
Hello everyone,
Today, we just had our new meeting with Mat (Cruise) and myself (NGI0 Core).
Thanks again for this new good meeting!
Here are the minutes of the meeting:
Accepted patches:
- The list of accepted patches can be seen on PatchWork:
https://patchwork.kernel.org/project/mptcp/list/?state=3
netdev (if mptcp ML is in cc) (by: Jakub Kicinski):
14131177: [net,07/10] netlink: specs: mptcp: replace underscores with
dashes in names
our repo (by: /):
/
Pending patches:
- The list of pending patches can be seen on PatchWork:
https://patchwork.kernel.org/project/mptcp/list/?state=*
netdev (if mptcp ML is in cc) (by: /):
/
our repo (by: Gang Yan, Geliang Tang, Gregory Detal, Matthieu Baerts):
12282223: [RESEND,RFC,mptpcp-next] mptcp: add ooo prune support:
13070467: [mptcp-next,v4,1/2] mptcp: update mptcp_push_release
13070468: [mptcp-next,v4,2/2] mptcp: retrans for redundant sends:
- State: Changes requested
- Series: BPF redundant scheduler, part 3
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=703615&state=*&archive=both
- Status: same as last time
13305089: [mptcp-next,1/6] mptcp: sockopt: move tcp_inq code to a
dedicated function
13305091: [mptcp-next,2/6] mptcp: sockopt: update supported list
13305093: [mptcp-next,3/6] mptcp: sockopt: get val in a generic way
13305090: [mptcp-next,4/6] mptcp: sockopt: add missing getsockopt() options
13305094: [mptcp-next,5/6] mptcp: sockopt: set val in a generic way
13305092: [mptcp-next,6/6] mptcp: sockopt: support IP_TTL &
IPV6_UNICAST_HOPS:
- State: Changes requested
- Series: mptcp: sockopt: uniform code to get/set values
- Submitter: Matthieu Baerts
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=763505&state=*&archive=both
- Status: same as last time
13583230: [RFC] mptcp: react scheduler when subflow events pop up:
- State: Changes requested
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/patch/433320c3a9db77bea53a34fc9c43a3c7e3320399.1709693691.git.tanggeliang@kylinos.cn/-
Status: same as last time
13675217: [mptcp-next,RFC,1/4] mptcp: add push sched callback
13675218: [mptcp-next,RFC,2/4] mptcp: use new push callback to schedule
chunks
13675219: [mptcp-next,RFC,3/4] mptcp: bpf: allow to write to
mptcp_sched_chunk
13675220: [mptcp-next,RFC,4/4] selftests/bpf: mptcp RR: send 1 MSS on
each subflow:
- State: RFC
- Series: mptcp: update scheduler API
- Submitter: Gregory Detal
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=856158&state=*&archive=both
- Status: same as last time
13932555: [1/3] mptcp: fix invalid addr occupy 'add_addr_accepted'
13932556: [2/3] selftests: mptcp: relax conditions in SYN_TX validation
13932546: [3/3] selftests: mptcp: add a testcase for invalid addr timeout:
- State: Changes requested
- Series: [1/3] mptcp: fix invalid addr occupy 'add_addr_accepted'
- Submitter: Gang Yan
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=923771&state=*&archive=both
- Status: same as last time
14024767: [mptcp-next,v1,1/4] bpf: Add mptcp path manager struct_ops
14024768: [mptcp-next,v1,2/4] bpf: Export mptcp path manager kfuncs
14024769: [mptcp-next,v1,3/4] selftests/bpf: Add mptcp netlink pm subtest
14024770: [mptcp-next,v1,4/4] selftests/bpf: Add mptcp bpf_netlink pm
subtest:
- State: Changes requested
- Series: BPF path manager, part 7
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=946095&state=*&archive=both
- Status: same as last time
14053397: [mptcp-next,v3,1/3] mptcp: pm: userspace: drop
delete_local_addr helper
14053398: [mptcp-next,v3,2/3] selftests: mptcp: join: update userspace
dump_addr outputs
14053399: [mptcp-next,v3,3/3] selftests: mptcp: userspace: send RM_ADDR
between server and client:
- State: Under review
- Series: only remove entry from local_addr_list when sending a
REMOVE_ADDR
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=953862&state=*&archive=both
- TODO: Mat: check in a VM and do some tests with mptcpd
- TODO: Matth: check this series
- Status: same as last time
14077448: [mptcp-next,v7,1/5] mptcp: pm: call pm worker handler without
pm lock
14077447: [mptcp-next,v7,2/5] mptcp: pm: add accept_new_subflow() interface
14077449: [mptcp-next,v7,3/5] mptcp: pm: add established() interface
14077450: [mptcp-next,v7,4/5] mptcp: pm: add subflow_established() interface
14077451: [mptcp-next,v7,5/5] mptcp: pm: drop is_userspace in
subflow_check_next:
- State: Needs ack
- Series: BPF path manager, part 6
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=959912&state=*&archive=both
- Status: same as last time
14102233: [mptcp-next,v3,1/3] selftests/bpf: Add sndbuf for send_recv_data
14102235: [mptcp-next,v3,2/3] Squash to "selftests/bpf: Add bpf
scheduler test"
14102234: [mptcp-next,v3,3/3] DO-NOT-MERGE: selftests/bpf: Increase
total_bytes of bpf sched tests:
- State: Under review
- Series: send() fails with EAGAIN in blocking IO mode "487
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=967210&state=*&archive=both
- Mat will try to look at it
14135682: [1/2] mptcp: add splice test:
- Packetdrill PR has been sent too (and reviewed there)
14136062: [mptcp-next,v5,1/5] mptcp: use sk_eat_skb in recvmsg_mskq
14136063: [mptcp-next,v5,2/5] mptcp: add recvmsg_desc helper
14136064: [mptcp-next,v5,3/5] mptcp: implement .read_sock
14136065: [mptcp-next,v5,4/5] mptcp: set .splice_read
14136066: [mptcp-next,v5,5/5] selftests: mptcp: add splice io mode:
- State: New
- Series: implement mptcp read_sock
- Submitter: Geliang Tang
- URL:
https://patchwork.kernel.org/project/mptcp/list/?series=976876&state=*&archive=both
- Mat will try to look at it
Issues on GitHub:
https://github.com/multipath-tcp/mptcp_net-next/issues/
Recently opened (latest from the last meeting: 565):
570 [syzkaller] WARNING in `mptcp_incoming_options` [syzkaller]:
- Probably not urgent: looks like it was hit while changing
endpoints in parallel
568 socket option: support `IPV6_TCLASS` [enhancement]:
- We support the IPv4 equivalent (IP_TOS), but not this one
- should be easy to add, but it needs to be done
567 [syzbot] WARNING in `__mark_subflow_endp_available` [bug]
[syzkaller] [reproducer]:
- Probably not urgent: we can deal with the situation, but we
should avoid it (or suppress the warning)
566 How to maintain extra subflows for redundancy when client and
server are reversible? [question]:
- to use signal + subflow + fullmesh flags on the same endpoint
- it will likely create all possible paths twice
Recently discussed:
562 [performance] How much is the overhead of MPTCP? [question]
[triage]:
- Matth needs to look at it
336 Issues with BPF packet scheduler [bug] [sched] [bpf]:
- discussions are on #565: bpftool commands seems to be OK to load
a BPF packet sched, but it doesn't seem to work.
Bugs (opened, flagged as "bug" and assigned)
498 in-kernel PM: closed subflows before `RM_ADDR` will not decrement
`add_addr_accepted` [bug] [pm] @geliangtang
487 `send()` fails with `EAGAIN` in blocking IO mode [bug]
[selftests] [sched] @geliangtang
484 BPF: `setsockopt` on an MPTCP socket: check support [bug] [bpf]
@geliangtang
445 MPTCP Info counters: start seq numbers ones from 0 [bug] @geliangtang
403 userspace pm: only remove entry from `local_addr_list` when
sending a `REMOVE_ADDR` [bug] [pm] @geliangtang
343 scheduler: react when subflow-level events pop up (ACK/RTO) [bug]
[sched] @geliangtang
Bugs (opened and flagged as "bug" and not assigned)
567 [syzbot] WARNING in `__mark_subflow_endp_available` [bug]
[syzkaller] [reproducer]
561 [syzkaller] WARNING in `mptcp_pm_alloc_anno_list` [bug] [syzkaller]
559 Adapt `mptcp_rcv_space_adjust()` after the recent TCP
modifications (`tcp: receive side improvements`) [bug] [enhancement]
555 [syzbot] WARNING in `mptcp_do_fallback` [bug] [syzkaller]
549 pm: in-kernel: set `msk->pm.work_pending` back to `true` [bug]
[selftests] [pm]
508 Divide error on device removal [bug] [feedback-needed]
505 Subflows won't be used when the interface for the main flow is a
subinterface [bug] [feedback-needed]
495 [syzkaller] KASAN: slab-use-after-free Read in
`__inet6_lookup_established` [bug] [syzkaller]
494 [syzkaller] WARNING in `__skb_flow_dissect` [bug] [syzkaller]
492 userspace pm: subflows counter: not updated when a subflows is
removed from the other end [bug]
491 selftests: `mptcp_join`: tests `Infinite map` & `MP_FAIL MP_RST`
are unstable [bug] [selftests]
483 [6.1] selftests: `mptcp_connect.sh` failures with
`copyfd_io_poll: poll timed out` errors [bug] [selftests]
476 packetdrill: coalescing feature doesn't take into account MPTCP
options [bug] [packetdrill]
475 `simult_flows`: unbalanced bwidth tests are unstable [bug]
[selftests]
439 mptcp vs net.ipv4.tcp_shrink_window [bug]
336 Issues with BPF packet scheduler [bug] [sched] [bpf]
325 selftests: `mptcp_join`: test 18 `signal addresses race test` is
sometimes failing [bug] [selftests]
324 selftests: `mptcp_join`: tests `fastclose test` & `fastclose
server test` are sometimes failing [bug] [selftests]
315 Issues with backup flow [bug]
In Progress (opened, new feature and assigned)
514 Add MIB counters for fallback to TCP [enhancement] @geliangtang
480 MPTCP and KTLS support [enhancement] @geliangtang
434 in-kernel PM: increase subflows limit [enhancement] [pm] @matttbe
353 sockopt: uniform code to get/set values [enhancement] @matttbe
349 scheduler: (un)mark a subflow as "stale" [enhancement] [sched]
@geliangtang
296 Support IP_TTL & IPV6_UNICAST_HOPS [enhancement] @matttbe
167 packetdrill: add coverage for RM_ADDR [enhancement] [packetdrill]
@dcaratti
75 BPF: packet scheduler [enhancement] [sched] [bpf] @geliangtang
74 BPF: path manager [enhancement] [pm] [bpf] @geliangtang
Assigned Questions (opened, questions and assigned)
548 disable mptcp for an interface [question] @matttbe
Open questions (opened, questions and not assigned)
566 How to maintain extra subflows for redundancy when client and
server are reversible? [question]
562 [performance] How much is the overhead of MPTCP? [question] [triage]
530 about mptcp subflow creation question [question] [feedback-needed]
520 Question about proper MPTCP configuration over VPN. [question]
[feedback-needed]
412 shadowsocks-libev not working, need guidance for PM configuration
[question] [feedback-needed]
For later (opened and not assigned)
570 [syzkaller] WARNING in `mptcp_incoming_options` [syzkaller]
568 socket option: support `IPV6_TCLASS` [enhancement]
556 Implement all required bits to C/R MPTCP connections from
user-space (CRIU) [enhancement]
552 pm: in-kernel: delay before creating new subflows [enhancement]
545 Deal with multiple pure TCP ACK without MPTCP options [enhancement]
543 TCPDump: display `MP_TCPRST` info [enhancement]
542 in-kernel PM: limit to one subflow per network interface for each
connection [enhancement] [pm]
536 PM: new subflow: avoid selecting initial endpoint upon `ADD_ADDR`
reception if servers deny MPJ to initial address [enhancement] [pm]
535 TCPDump: display `MP_CAPABLE` C flag [enhancement]
532 Userspace PM doesn't have access to `allow_join_id0` /
`allow_join_initial_addr_port` bit from the SYN-ACK [enhancement]
525 tests: cover more MPTCP socket options [enhancement]
[packetdrill] [selftests]
521 Implement psock_update_sk_prot, for eBPF SOCKMAP support
[enhancement]
519 Reset the connection once "MPTCP has been verified" instead of a
fallback [enhancement]
511 Add MIB counters for sent `MPTCP_RST_EMPTCP` [enhancement]
503 in-kernel PM: use endpoints only to create subflows with received
`ADD_ADDR` [enhancement] [pm]
497 in-kernel PM: check to create new subflows when some are
destroyed [enhancement] [pm]
496 in-kernel PM: store received `ADD_ADDR` [enhancement] [pm]
481 remove refcount on TCP sockets for the timers [enhancement]
467 Scheduler: add redundant scheduler support in BPF [enhancement]
[sched]
462 selftests: print (and set?) random seed [enhancement] [selftests]
461 Protocol: extend Data-Level Length field [enhancement] [protocol]
448 Allow sending ADD_ADDR IPv6 with port-number if TCP-timestamps
are enabled [enhancement]
441 optimize established options generation [enhancement]
440 in-kernel PM: re-establish subflows after "network" errors
[enhancement] [pm]
426 selftests: validate listener sockets with multiple accepts
[enhancement] [selftests]
396 ci: periodically run selftests from the export branch on stable
kernels [enhancement] [selftests]
389 packetdrill: increase coverage for "early `close()`" cases
[enhancement] [packetdrill]
350 scheduler: API changes (tasks) [enhancement] [sched]
348 scheduler: frequently probe "stale" subflow with reinjected data
[enhancement] [sched]
345 scheduler: "penalise" some subflows by sending less than their
cwnd [enhancement] [sched]
344 scheduler: new callback to initiate optimisations [enhancement]
[sched]
337 in-kernel PM: listen socket: support "behind a NAT" use case
[enhancement] [pm]
335 Server to Client subflows: option to allow joining the initial
address and port [enhancement] [pm]
334 in-kernel PM: send >1 ADD_ADDR before the establishment of a new
subflow [enhancement] [pm]
332 scheduler: implement a "opportunistic retransmission"
[enhancement] [sched]
298 CG Memory accounting for passive MPTCP socket [enhancement]
289 mptcp: audit comments for non inclusive language [enhancement]
273 Packetdrill: test outgoing MP_FASTCLOSE [enhancement] [packetdrill]
266 Packetdrill: add MP_FAIL coverage [packetdrill]
236 Review supported sockopts list [enhancement]
234 Packetdrill: Support MPC+DATA+checksum error [enhancement]
[packetdrill]
222 Netlink event API: add SUBFLOW_CREATED event [enhancement]
215 TCP Urgent pointer and MPTCP [enhancement]
213 add MPTCP man page [enhancement]
208 better handing of ssk memory pressure in the TX path [enhancement]
202 Add sendmsg support for ancillary data [enhancement]
197 more mibs needed [enhancement]
180 Get an update when MPTCP fall back to TCP [enhancement]
177 improve retransmit subflow selection [enhancement]
169 packetdrill: add coverage for ADD_ADDR and MP_JOIN on a different
port [enhancement] [packetdrill]
150 remove completely workqueue usage [enhancement]
141 avoid acquiring mptcp_data_lock() twice in the receive path
[enhancement]
78 notify the application (userspace) when a subflow is
added/removed [enhancement]
41 reduce indirect call usage [enhancement]
24 Revisit layout of struct mptcp_subflow_context [enhancement]
Recently closed (since 2025-06-18)
569 Problems encountered in setting up subflows [question]:
- with the out-of-tree kernel
565 Testing Custom Scheduler on Newer Kernel Versions with MPTCP
[question]
564 Types of Schedulers available [question] @matttbe
Packetdrill PRs
162 1 day ago geliangtang mptcp: add splice test
161 1 day ago geliangtang packetdrill: validate maxseg sockopt
52 5 months ago dcaratti Add initial coverage for RM_ADDR
mptcp.dev PRs
/
mptcpd PRs
/
FYI: Current Roadmap:
- Bugs:
https://github.com/multipath-tcp/mptcp_net-next/issues?q=is%3Aissue+is%3Aopen+label%3Abug
- Current/Coming merge window (6.17):
https://github.com/orgs/multipath-tcp/projects/15
- For later: https://github.com/orgs/multipath-tcp/projects/1
Patches to send to NetDev:
- Fixes for other trees: /
- Fixes for -net: /
- Fixes for net-next: /
- Features for net-next:
- [fb6b0f23279c] mptcp: pm: init and release mptcp_pm_ops
(Geliang Tang)
- [87e06473732c] mptcp: pm: add get_local_id() interface
(Geliang Tang)
- [ed98432ed726] mptcp: pm: add get_priority() interface
(Geliang Tang):
- blocked: refactor pm->lock
- [3fe8ea995f31] mptcp: sockopt: drop redundant tcp_getsockopt
(Geliang Tang)
- [273b59f86a91] tcp: add tcp_sock_set_maxseg (Geliang Tang)
- [149704a8572e] mptcp: add TCP_MAXSEG sockopt support (Geliang
Tang):
- blocked: need a packetdrill test first
- [9ac5e4684813] mptcp: fix typos in comments (moyuanhao)
- Features for net-next (next): /
- Features for other trees:
- [8f48932bc2b0] bpf: Add mptcp_subflow bpf_iter (Geliang Tang)
- [23dd70d7a247] selftests/bpf: More endpoints for endpoint_init
(Geliang Tang)
- [8eb64e14e51f] selftests/bpf: Drop cgroup_fd of run_mptcpify
(Geliang Tang)
- [319b26bed9fc] bpf: Add mptcp packet scheduler struct_ops
(Geliang Tang)
- [64f4fa0cd366] bpf: Export mptcp packet scheduler helpers
(Geliang Tang)
- [dfe95157afef] selftests/bpf: Add bpf scheduler test (Geliang
Tang)
- [f7e237d231c9] selftests/bpf: Add bpf_first scheduler & test
(Geliang Tang)
- [312b44eaa196] selftests/bpf: Add bpf_bkup scheduler & test
(Geliang Tang)
- [9453c89d87ec] selftests/bpf: Add bpf_rr scheduler & test
(Geliang Tang)
- [badb3d1234e2] selftests/bpf: Add bpf_red scheduler & test
(Geliang Tang)
- [44fe69b21296] selftests/bpf: Add bpf_burst scheduler & test
(Geliang Tang):
- blocked: need sched API refactor
Extra tests:
- news about Syzkaller? (Matth):
- found 2 new issues, not urgent
- Packetdrill (Davide):
- some PR that are in review
- Patchew (Davide):
- TODO: it looks like it is no longer applying new patches → WIP
- CI (Matth):
- https://ci-results.mptcp.dev/flakes.html
- https://netdev.bots.linux.dev/flakes.html?tn-needle=mptcp
- /
Next meeting:
- Next one on Wednesday, the 16th of July.
- 17:30 UTC (8.30am PDT, 5.30pm CEST, 11.30pm CST)
- Still open to everyone!
- https://annuel2.framapad.org/p/mptcp_upstreaming_20250716
Feel free to comment on these topics and suggest new ones for the next
meeting!
Talk to you soon,
Matt
--
Sponsored by the NGI0 Core fund.
^ permalink raw reply [flat|nested] only message in thread
only message in thread, other threads:[~2025-07-02 17:15 UTC | newest]
Thread overview: (only message) (download: mbox.gz follow: Atom feed
-- links below jump to the message on this page --
2025-07-02 17:15 [Weekly meetings] MoM - 2nd of July 2025 Matthieu Baerts
This is an external index of several public inboxes,
see mirroring instructions on how to clone and mirror
all data and code used by this external index.