| /linux/fs/afs/ |
| H A D | vl_probe.c | 49 struct afs_addr_list *alist = call->vl_probe; in afs_vlserver_probe_result() local
51 struct afs_address *addr = &alist->addrs[call->probe_index]; in afs_vlserver_probe_result()
92 clear_bit(index, &alist->responded); in afs_vlserver_probe_result()
93 set_bit(index, &alist->probe_failed); in afs_vlserver_probe_result()
104 set_bit(index, &alist->responded); in afs_vlserver_probe_result()
105 clear_bit(index, &alist->probe_failed); in afs_vlserver_probe_result()
123 alist->preferred = index; in afs_vlserver_probe_result()
134 trace_afs_vl_probe(server, false, alist, index, call->error, call->abort_code, rtt_us); in afs_vlserver_probe_result()
152 struct afs_addr_list *alist; in afs_do_probe_vlserver() local
162 alist = rcu_dereference_protected(server->addresses, in afs_do_probe_vlserver()
[all …]
|
| H A D | vlclient.c | 139 call->peer = rxrpc_kernel_get_peer(vc->alist->addrs[vc->addr_index].peer); in afs_vl_get_entry_by_name_u()
175 struct afs_addr_list *alist; in afs_deliver_vl_get_addrs_u() local
203 alist = afs_alloc_addrlist(nentries); in afs_deliver_vl_get_addrs_u()
204 if (!alist) in afs_deliver_vl_get_addrs_u()
206 alist->version = uniquifier; in afs_deliver_vl_get_addrs_u()
207 call->ret_alist = alist; in afs_deliver_vl_get_addrs_u()
222 alist = call->ret_alist; in afs_deliver_vl_get_addrs_u()
226 if (alist->nr_addrs < call->count2) { in afs_deliver_vl_get_addrs_u()
227 ret = afs_merge_fs_addr4(call->net, alist, *bp++, AFS_FS_PORT); in afs_deliver_vl_get_addrs_u()
262 struct afs_addr_list *alist; in afs_vl_get_addrs_u() local
[all …]
|
| H A D | server.c | 156 struct afs_addr_list *alist = NULL; in afs_vl_lookup_addrs() local
163 alist = afs_yfsvl_get_endpoints(&vc, &server->uuid); in afs_vl_lookup_addrs()
165 alist = afs_vl_get_addrs_u(&vc, &server->uuid); in afs_vl_lookup_addrs()
171 return ret < 0 ? ERR_PTR(ret) : alist; in afs_vl_lookup_addrs()
181 struct afs_addr_list *alist = NULL; in afs_lookup_server() local
204 afs_put_addrlist(alist, afs_alist_trace_put_server_oom); in afs_lookup_server()
229 alist = afs_vl_lookup_addrs(server, key); in afs_lookup_server()
230 if (IS_ERR(alist)) { in afs_lookup_server()
231 ret = PTR_ERR(alist); in afs_lookup_server()
235 ret = afs_fs_probe_fileserver(cell->net, server, alist, key); in afs_lookup_server()
[all …]
|
| H A D | vl_list.c | 94 struct afs_addr_list *alist; in afs_extract_vl_addrs() local
98 alist = afs_alloc_addrlist(nr_addrs); in afs_extract_vl_addrs()
99 if (!alist) in afs_extract_vl_addrs()
102 return alist; in afs_extract_vl_addrs()
117 ret = afs_merge_fs_addr4(net, alist, x[0], port); in afs_extract_vl_addrs()
129 ret = afs_merge_fs_addr6(net, alist, x, port); in afs_extract_vl_addrs()
144 if (alist->nr_ipv4 < alist->nr_addrs) in afs_extract_vl_addrs()
145 alist->preferred = alist->nr_ipv4; in afs_extract_vl_addrs()
148 return alist; in afs_extract_vl_addrs()
152 afs_put_addrlist(alist, afs_alist_trace_put_parse_error); in afs_extract_vl_addrs()
|
| H A D | addr_prefs.c | 457 void afs_get_address_preferences_rcu(struct afs_net *net, struct afs_addr_list *alist) in afs_get_address_preferences_rcu() argument
468 if (!preflist || !preflist->nr || !alist->nr_addrs || in afs_get_address_preferences_rcu()
469 smp_load_acquire(&alist->addr_pref_version) == preflist->version) in afs_get_address_preferences_rcu()
475 for (i = 0; i < alist->nr_ipv4; i++) { in afs_get_address_preferences_rcu()
476 sa = rxrpc_kernel_remote_addr(alist->addrs[i].peer); in afs_get_address_preferences_rcu()
488 WRITE_ONCE(alist->addrs[i].prio, preflist->prefs[j].prio); in afs_get_address_preferences_rcu()
497 for (; i < alist->nr_addrs; i++) { in afs_get_address_preferences_rcu()
498 sa = rxrpc_kernel_remote_addr(alist->addrs[i].peer); in afs_get_address_preferences_rcu()
510 WRITE_ONCE(alist->addrs[i].prio, preflist->prefs[j].prio); in afs_get_address_preferences_rcu()
516 smp_store_release(&alist->addr_pref_version, preflist->version); in afs_get_address_preferences_rcu()
[all …]
|
| H A D | proc.c | 346 const struct afs_addr_list *alist; in afs_proc_cell_vlservers_show() local
358 alist = rcu_dereference(vlserver->addresses); in afs_proc_cell_vlservers_show()
362 dns_record_sources[alist ? alist->source : entry->source], in afs_proc_cell_vlservers_show()
363 dns_lookup_statuses[alist ? alist->status : entry->status]); in afs_proc_cell_vlservers_show()
364 if (alist) { in afs_proc_cell_vlservers_show()
365 for (i = 0; i < alist->nr_addrs; i++) in afs_proc_cell_vlservers_show()
367 alist->preferred == i ? '>' : '-', in afs_proc_cell_vlservers_show()
368 rxrpc_kernel_remote_addr(alist->addrs[i].peer)); in afs_proc_cell_vlservers_show()
437 struct afs_addr_list *alist; in afs_proc_servers_show() local
466 alist = estate->addresses; in afs_proc_servers_show()
[all …]
|
| H A D | fs_probe.c | 141 struct afs_addr_list *alist = estate->addresses; in afs_fileserver_probe_result() local
142 struct afs_address *addr = &alist->addrs[call->probe_index]; in afs_fileserver_probe_result()
215 alist->preferred = index; in afs_fileserver_probe_result()
228 rxrpc_kernel_remote_addr(alist->addrs[index].peer), in afs_fileserver_probe_result()
242 struct afs_addr_list *old_alist = NULL, *alist; in afs_fs_probe_fileserver() local
269 alist = estate->addresses; in afs_fs_probe_fileserver()
271 atomic_set(&estate->nr_probing, alist->nr_addrs); in afs_fs_probe_fileserver()
286 unprobed = (1UL << alist->nr_addrs) - 1; in afs_fs_probe_fileserver()
291 for (i = 0; i < alist->nr_addrs; i++) { in afs_fs_probe_fileserver()
293 alist->addrs[i].prio > best_prio) { in afs_fs_probe_fileserver()
[all …]
|
| H A D | fs_operation.c | 331 struct afs_addr_list *alist; in afs_put_operation() local
355 alist = op->estate->addresses; in afs_put_operation()
356 if (alist) { in afs_put_operation()
358 op->addr_index != alist->preferred && in afs_put_operation()
359 test_bit(alist->preferred, &op->addr_tried)) in afs_put_operation()
360 WRITE_ONCE(alist->preferred, op->addr_index); in afs_put_operation()
|
| H A D | rotate.c | 154 struct afs_addr_list *alist; in afs_select_fileserver() local
616 alist = op->estate->addresses; in afs_select_fileserver()
619 for (i = 0; i < alist->nr_addrs; i++) { in afs_select_fileserver()
622 if (alist->addrs[i].prio > best_prio) { in afs_select_fileserver()
624 best_prio = alist->addrs[i].prio; in afs_select_fileserver()
628 alist->preferred = addr_index; in afs_select_fileserver()
634 op->server_index, addr_index, alist->nr_addrs, in afs_select_fileserver()
635 rxrpc_kernel_remote_addr(alist->addrs[op->addr_index].peer)); in afs_select_fileserver()
|
| H A D | internal.h | 797 struct afs_addr_list *alist; /* Current address list (pins ref) */ member
1001 struct afs_addr_list *afs_get_addrlist(struct afs_addr_list *alist, enum afs_alist_trace reason);
1003 extern void afs_put_addrlist(struct afs_addr_list *alist, enum afs_alist_trace reason);
1023 void afs_get_address_preferences_rcu(struct afs_net *net, struct afs_addr_list *alist);
1024 void afs_get_address_preferences(struct afs_net *net, struct afs_addr_list *alist);
1420 struct afs_addr_list *alist = op->estate->addresses; in afs_make_op_call() local
1427 call->peer = rxrpc_kernel_get_peer(alist->addrs[op->addr_index].peer); in afs_make_op_call()
1617 struct afs_addr_list *alist,
|
| /linux/kernel/trace/ |
| H A D | fprobe.c | 549 static int fprobe_addr_list_add(struct fprobe_addr_list *alist, unsigned long addr) in fprobe_addr_list_add() argument
554 if (alist->index == alist->size) in fprobe_addr_list_add()
557 alist->addrs[alist->index++] = addr; in fprobe_addr_list_add()
558 if (alist->index < alist->size) in fprobe_addr_list_add()
562 addrs = kcalloc(alist->size * 2, sizeof(*addrs), GFP_KERNEL); in fprobe_addr_list_add()
566 memcpy(addrs, alist->addrs, alist->size * sizeof(*addrs)); in fprobe_addr_list_add()
567 alist->size *= 2; in fprobe_addr_list_add()
568 kfree(alist->addrs); in fprobe_addr_list_add()
569 alist->addrs = addrs; in fprobe_addr_list_add()
575 struct fprobe_addr_list *alist) in fprobe_remove_node_in_module() argument
[all …]
|
| /linux/net/sched/ |
| H A D | sch_drr.c | 24 struct list_head alist; member
40 return !list_empty(&cl->alist); in cl_is_active()
113 INIT_LIST_HEAD(&cl->alist); in drr_change_class()
238 list_del_init(&cl->alist); in drr_qlen_notify()
364 list_add_tail(&cl->alist, &q->active); in drr_enqueue()
383 cl = list_first_entry(&q->active, struct drr_class, alist); in drr_dequeue()
397 list_del_init(&cl->alist); in drr_dequeue()
407 list_move_tail(&cl->alist, &q->active); in drr_dequeue()
438 list_del_init(&cl->alist); in drr_reset_qdisc()
|
| H A D | sch_ets.c | 40 struct list_head alist; /* In struct ets_sched.active. */ member
79 return !list_empty(&cl->alist); in cl_is_active()
301 list_del_init(&cl->alist); in ets_class_qlen_notify()
443 list_add_tail(&cl->alist, &q->active); in ets_qdisc_enqueue()
480 cl = list_first_entry(&q->active, struct ets_class, alist); in ets_qdisc_dequeue()
494 list_del_init(&cl->alist); in ets_qdisc_dequeue()
499 list_move_tail(&cl->alist, &q->active); in ets_qdisc_dequeue()
656 list_del_init(&q->classes[i].alist); in ets_qdisc_change()
663 list_add_tail(&q->classes[i].alist, &q->active); in ets_qdisc_change()
669 list_del_init(&q->classes[i].alist); in ets_qdisc_change()
[all...] |
| H A D | sch_qfq.c | 137 struct list_head alist; /* Link for active-classes list. */ member
207 return !list_empty(&cl->alist); in cl_is_active()
328 list_add_tail(&cl->alist, &agg->active); in qfq_add_to_agg()
329 if (list_first_entry(&agg->active, struct qfq_class, alist) == in qfq_add_to_agg()
355 list_del_init(&cl->alist); /* remove from RR queue of the aggregate */ in qfq_deactivate_class()
486 INIT_LIST_HEAD(&cl->alist); in qfq_change_class()
1001 list_del_init(&cl->alist); in agg_dequeue()
1004 list_move_tail(&cl->alist, &agg->active); in agg_dequeue()
1016 *cl = list_first_entry(&agg->active, struct qfq_class, alist); in qfq_peek_skb()
1272 list_first_entry(&agg->active, struct qfq_class, alist) in qfq_enqueue()
[all...] |
| /linux/net/mptcp/ |
| H A D | pm_kernel.c | 1224 struct mptcp_rm_list alist = { .nr = 0 }, slist = { .nr = 0 }; in mptcp_pm_flush_addrs_and_subflows() local
1232 if (alist.nr < MPTCP_RM_IDS_MAX && in mptcp_pm_flush_addrs_and_subflows()
1234 alist.ids[alist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr); in mptcp_pm_flush_addrs_and_subflows()
1238 if (alist.nr) { in mptcp_pm_flush_addrs_and_subflows()
1239 msk->pm.add_addr_signaled -= alist.nr; in mptcp_pm_flush_addrs_and_subflows()
1240 mptcp_pm_remove_addr(msk, &alist); in mptcp_pm_flush_addrs_and_subflows()
|
| /linux/include/trace/events/ |
| H A D | afs.h | 1621 __field(unsigned int, alist)
1628 __entry->alist = alist_debug_id;
1634 __entry->alist,
1685 struct afs_addr_list *alist = estate->addresses;
1693 memcpy(&__entry->srx, rxrpc_kernel_remote_srx(alist->addrs[addr_index].peer),
1704 TP_PROTO(struct afs_vlserver *server, bool tx, struct afs_addr_list *alist,
1707 TP_ARGS(server, tx, alist, addr_index, error, abort_code, rtt_us),
1727 memcpy(&__entry->srx, rxrpc_kernel_remote_srx(alist->addrs[addr_index].peer),
|
| /linux/Documentation/translations/zh_TW/process/ |
| H A D | coding-style.rst | 610 (c-offsets-alist . (
|
| /linux/Documentation/process/ |
| H A D | coding-style.rst | 670 (c-offsets-alist . (
|
| /linux/Documentation/translations/sp_SP/process/ |
| H A D | coding-style.rst | 698 (c-offsets-alist . (
|