| /net/openvswitch/ |
| A D | vport.c | 406 if (!nla_len(ids) || nla_len(ids) % sizeof(u32)) in ovs_vport_set_upcall_portids()
418 nla_memcpy(vport_portids->ids, ids, nla_len(ids)); in ovs_vport_set_upcall_portids()
444 struct vport_portids *ids; in ovs_vport_get_upcall_portids() local
450 ids->n_ids * sizeof(u32), (void *)ids->ids); in ovs_vport_get_upcall_portids()
452 return nla_put_u32(skb, OVS_VPORT_ATTR_UPCALL_PID, ids->ids[0]); in ovs_vport_get_upcall_portids()
469 struct vport_portids *ids; in ovs_vport_find_upcall_portid() local
473 ids = rcu_dereference(vport->upcall_portids); in ovs_vport_find_upcall_portid()
476 if (ids->n_ids == 1) in ovs_vport_find_upcall_portid()
477 return ids->ids[0]; in ovs_vport_find_upcall_portid()
480 ids_index = hash - ids->n_ids * reciprocal_divide(hash, ids->rn_ids); in ovs_vport_find_upcall_portid()
[all …]
|
| A D | datapath.c | 1685 const struct nlattr *ids) in ovs_dp_set_upcall_portids() argument
1689 if (!nla_len(ids) || nla_len(ids) % sizeof(u32)) in ovs_dp_set_upcall_portids()
1694 dp_nlsk_pids = kmalloc(sizeof(*dp_nlsk_pids) + nla_len(ids), in ovs_dp_set_upcall_portids()
1699 dp_nlsk_pids->n_pids = nla_len(ids) / sizeof(u32); in ovs_dp_set_upcall_portids()
1700 nla_memcpy(dp_nlsk_pids->pids, ids, nla_len(ids)); in ovs_dp_set_upcall_portids()
2406 struct nlattr *ids = a[OVS_VPORT_ATTR_UPCALL_PID]; in ovs_vport_cmd_set() local
2408 err = ovs_vport_set_upcall_portids(vport, ids); in ovs_vport_cmd_set()
|
| A D | vport.h | 57 u32 ids[]; member
|
| /net/ipv6/netfilter/ |
| A D | ip6t_frag.c | 64 id_match(fraginfo->ids[0], fraginfo->ids[1], in frag_mt6()
88 return id_match(fraginfo->ids[0], fraginfo->ids[1], in frag_mt6()
|
| /net/mptcp/ |
| A D | pm_kernel.c | 861 list.ids[list.nr++] = mptcp_endp_get_local_id(msk, addr); in mptcp_pm_remove_anno_addr()
906 list.ids[0] = mptcp_endp_get_local_id(msk, addr); in mptcp_nl_remove_subflow_and_signal_addr()
915 __mark_subflow_endp_available(msk, list.ids[0]); in mptcp_nl_remove_subflow_and_signal_addr()
938 list.ids[list.nr++] = 0; in mptcp_nl_remove_id_zero_address()
1029 slist.ids[slist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr); in mptcp_pm_flush_addrs_and_subflows()
1033 alist.ids[alist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr); in mptcp_pm_flush_addrs_and_subflows()
1240 list.ids[list.nr++] = mptcp_endp_get_local_id(msk, addr); in mptcp_pm_nl_fullmesh()
1244 __mark_subflow_endp_available(msk, list.ids[0]); in mptcp_pm_nl_fullmesh()
|
| A D | options.c | 305 mp_opt->rm_list.ids[i] = *ptr++; in mptcp_parse_option()
733 pr_debug("rm_list_ids[%d]=%d\n", i, opts->rm_list.ids[i]); in mptcp_established_options_rm_addr()
1631 0, opts->rm_list.ids[0]); in mptcp_write_options()
1636 id1 = opts->rm_list.ids[i]; in mptcp_write_options()
1637 id2 = i + 1 < opts->rm_list.nr ? opts->rm_list.ids[i + 1] : TCPOPT_NOP; in mptcp_write_options()
1638 id3 = i + 2 < opts->rm_list.nr ? opts->rm_list.ids[i + 2] : TCPOPT_NOP; in mptcp_write_options()
1639 id4 = i + 3 < opts->rm_list.nr ? opts->rm_list.ids[i + 3] : TCPOPT_NOP; in mptcp_write_options()
|
| A D | pm_userspace.c | 264 list.ids[list.nr++] = 0; in mptcp_userspace_pm_remove_id_zero_address()
289 alist.ids[alist.nr++] = entry->addr.id; in mptcp_pm_remove_addr_entry()
|
| A D | pm.c | 677 u8 rm_id = rm_list->ids[i]; in mptcp_pm_rm_addr_or_subflow()
737 mptcp_event_addr_removed(msk, rm_list->ids[i]); in mptcp_pm_rm_addr_received()
|
| /net/ceph/crush/ |
| A D | mapper.c | 320 if (!arg || !arg->ids) in get_choose_arg_ids()
323 return arg->ids; in get_choose_arg_ids()
335 __s32 *ids = get_choose_arg_ids(bucket, arg); in bucket_straw2_choose() local
338 dprintk("weight 0x%x item %d\n", weights[i], ids[i]); in bucket_straw2_choose()
340 u = crush_hash32_3(bucket->h.hash, x, ids[i], r); in bucket_straw2_choose()
|
| /net/wireless/ |
| A D | util.c | 1984 static bool ieee80211_id_in_list(const u8 *ids, int n_ids, u8 id, bool id_ext) in ieee80211_id_in_list() argument
1989 if (WARN_ON(ids[n_ids - 1] == WLAN_EID_EXTENSION)) in ieee80211_id_in_list()
1994 if (ids[i] == WLAN_EID_EXTENSION) { in ieee80211_id_in_list()
1995 if (id_ext && (ids[i + 1] == id)) in ieee80211_id_in_list()
2002 if (ids[i] == id && !id_ext) in ieee80211_id_in_list()
2030 const u8 *ids, int n_ids, in ieee80211_ie_split_ric() argument
2044 if (!ieee80211_id_in_list(ids, n_ids, ies[pos + ext], in ieee80211_ie_split_ric()
|
| /net/ceph/ |
| A D | osdmap.c | 255 kfree(arg->ids); in free_choose_arg_map()
337 arg->ids = decode_array_32_alloc(p, end, &arg->ids_size); in decode_choose_arg()
338 if (IS_ERR(arg->ids)) { in decode_choose_arg()
339 ret = PTR_ERR(arg->ids); in decode_choose_arg()
340 arg->ids = NULL; in decode_choose_arg()
|
| /net/9p/ |
| A D | trans_xen.c | 537 .ids = xen_9pfs_front_ids,
|
| /net/sctp/ |
| A D | socket.c | 7127 struct sctp_assoc_ids *ids; in sctp_getsockopt_assoc_ids() local
7141 ids_size = struct_size(ids, gaids_assoc_id, num); in sctp_getsockopt_assoc_ids()
7146 ids = kmalloc(len, GFP_USER | __GFP_NOWARN); in sctp_getsockopt_assoc_ids()
7147 if (unlikely(!ids)) in sctp_getsockopt_assoc_ids()
7150 ids->gaids_number_of_ids = num; in sctp_getsockopt_assoc_ids()
7153 ids->gaids_assoc_id[num++] = asoc->assoc_id; in sctp_getsockopt_assoc_ids()
7156 if (put_user(len, optlen) || copy_to_user(optval, ids, len)) { in sctp_getsockopt_assoc_ids()
7157 kfree(ids); in sctp_getsockopt_assoc_ids()
7161 kfree(ids); in sctp_getsockopt_assoc_ids()
|