Line data Source code
1 : #include "fd_gui.h"
2 : #include "fd_gui_printf.h"
3 : #include "fd_gui_metrics.h"
4 :
5 : #include "../metrics/fd_metrics.h"
6 : #include "../plugin/fd_plugin.h"
7 :
8 : #include "../../ballet/base58/fd_base58.h"
9 : #include "../../ballet/json/cJSON.h"
10 : #include "../../disco/genesis/fd_genesis_cluster.h"
11 : #include "../../disco/pack/fd_pack.h"
12 : #include "../../disco/pack/fd_pack_cost.h"
13 :
14 : #include <stdio.h>
15 :
16 : FD_FN_CONST ulong
17 0 : fd_gui_align( void ) {
18 0 : return 128UL;
19 0 : }
20 :
21 : FD_FN_CONST ulong
22 0 : fd_gui_footprint( void ) {
23 0 : ulong l = FD_LAYOUT_INIT;
24 0 : l = FD_LAYOUT_APPEND( l, fd_gui_align(), sizeof( fd_gui_t ) );
25 0 : return FD_LAYOUT_FINI( l, fd_gui_align() );
26 0 : }
27 :
28 : void *
29 : fd_gui_new( void * shmem,
30 : fd_http_server_t * http,
31 : char const * version,
32 : char const * cluster,
33 : uchar const * identity_key,
34 : int has_vote_key,
35 : uchar const * vote_key,
36 : int is_full_client,
37 : int snapshots_enabled,
38 : int is_voting,
39 : int schedule_strategy,
40 : fd_topo_t * topo,
41 0 : long now ) {
42 :
43 0 : if( FD_UNLIKELY( !shmem ) ) {
44 0 : FD_LOG_WARNING(( "NULL shmem" ));
45 0 : return NULL;
46 0 : }
47 :
48 0 : if( FD_UNLIKELY( !fd_ulong_is_aligned( (ulong)shmem, fd_gui_align() ) ) ) {
49 0 : FD_LOG_WARNING(( "misaligned shmem" ));
50 0 : return NULL;
51 0 : }
52 :
53 0 : if( FD_UNLIKELY( topo->tile_cnt>FD_GUI_TILE_TIMER_TILE_CNT ) ) {
54 0 : FD_LOG_WARNING(( "too many tiles" ));
55 0 : return NULL;
56 0 : }
57 :
58 0 : FD_SCRATCH_ALLOC_INIT( l, shmem );
59 0 : fd_gui_t * gui = FD_SCRATCH_ALLOC_APPEND( l, fd_gui_align(), sizeof(fd_gui_t) );
60 :
61 0 : gui->http = http;
62 0 : gui->topo = topo;
63 :
64 0 : gui->leader_slot = ULONG_MAX;
65 0 : gui->summary.schedule_strategy = schedule_strategy;
66 :
67 :
68 0 : gui->next_sample_400millis = now;
69 0 : gui->next_sample_100millis = now;
70 0 : gui->next_sample_50millis = now;
71 0 : gui->next_sample_25millis = now;
72 0 : gui->next_sample_10millis = now;
73 :
74 0 : memcpy( gui->summary.identity_key->uc, identity_key, 32UL );
75 0 : fd_base58_encode_32( identity_key, NULL, gui->summary.identity_key_base58 );
76 0 : gui->summary.identity_key_base58[ FD_BASE58_ENCODED_32_SZ-1UL ] = '\0';
77 :
78 0 : if( FD_LIKELY( has_vote_key ) ) {
79 0 : gui->summary.has_vote_key = 1;
80 0 : memcpy( gui->summary.vote_key->uc, vote_key, 32UL );
81 0 : fd_base58_encode_32( vote_key, NULL, gui->summary.vote_key_base58 );
82 0 : gui->summary.vote_key_base58[ FD_BASE58_ENCODED_32_SZ-1UL ] = '\0';
83 0 : } else {
84 0 : gui->summary.has_vote_key = 0;
85 0 : memset( gui->summary.vote_key_base58, 0, sizeof(gui->summary.vote_key_base58) );
86 0 : }
87 :
88 0 : gui->summary.is_full_client = is_full_client;
89 0 : gui->summary.version = version;
90 0 : gui->summary.cluster = cluster;
91 0 : gui->summary.startup_time_nanos = gui->next_sample_400millis;
92 :
93 0 : if( FD_UNLIKELY( is_full_client ) ) {
94 0 : if( FD_UNLIKELY( snapshots_enabled ) ) {
95 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_JOINING_GOSSIP;
96 0 : gui->summary.boot_progress.joining_gossip_time_nanos = gui->next_sample_400millis;
97 0 : for( ulong i=0UL; i<FD_GUI_BOOT_PROGRESS_SNAPSHOT_CNT; i++ ) {
98 0 : gui->summary.boot_progress.loading_snapshot[ i ].reset_cnt = ULONG_MAX; /* ensures other fields are reset initially */
99 0 : gui->summary.boot_progress.loading_snapshot[ i ].read_path[ 0 ] = '\0';
100 0 : gui->summary.boot_progress.loading_snapshot[ i ].insert_path[ 0 ] = '\0';
101 0 : }
102 0 : gui->summary.boot_progress.catching_up_time_nanos = 0L;
103 0 : gui->summary.boot_progress.catching_up_first_replay_slot = ULONG_MAX;
104 0 : } else {
105 0 : fd_memset( &gui->summary.boot_progress, 0, sizeof(gui->summary.boot_progress) );
106 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_RUNNING;
107 0 : }
108 0 : } else {
109 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_INITIALIZING;
110 0 : gui->summary.startup_progress.startup_got_full_snapshot = 0;
111 0 : gui->summary.startup_progress.startup_full_snapshot_slot = 0;
112 0 : gui->summary.startup_progress.startup_incremental_snapshot_slot = 0;
113 0 : gui->summary.startup_progress.startup_waiting_for_supermajority_slot = ULONG_MAX;
114 0 : gui->summary.startup_progress.startup_ledger_max_slot = ULONG_MAX;
115 0 : }
116 :
117 0 : gui->summary.identity_account_balance = 0UL;
118 0 : gui->summary.vote_account_balance = 0UL;
119 0 : gui->summary.estimated_slot_duration_nanos = 0UL;
120 :
121 0 : gui->summary.vote_distance = 0UL;
122 0 : gui->summary.vote_state = is_voting ? FD_GUI_VOTE_STATE_VOTING : FD_GUI_VOTE_STATE_NON_VOTING;
123 :
124 0 : gui->summary.sock_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "sock" );
125 0 : gui->summary.net_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "net" );
126 0 : gui->summary.quic_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "quic" );
127 0 : gui->summary.verify_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "verify" );
128 0 : gui->summary.resolh_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "resolh" );
129 0 : gui->summary.resolv_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "resolv" );
130 0 : gui->summary.bank_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "bank" );
131 0 : gui->summary.execle_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "execle" );
132 0 : gui->summary.shred_tile_cnt = fd_topo_tile_name_cnt( gui->topo, "shred" );
133 :
134 0 : gui->summary.slot_rooted = ULONG_MAX;
135 0 : gui->summary.slot_optimistically_confirmed = ULONG_MAX;
136 0 : gui->summary.slot_completed = ULONG_MAX;
137 0 : gui->summary.slot_estimated = ULONG_MAX;
138 0 : gui->summary.slot_caught_up = ULONG_MAX;
139 0 : gui->summary.slot_repair = ULONG_MAX;
140 0 : gui->summary.slot_turbine = ULONG_MAX;
141 0 : gui->summary.slot_reset = ULONG_MAX;
142 0 : gui->summary.slot_storage = ULONG_MAX;
143 0 : gui->summary.active_fork_cnt = 1UL;
144 :
145 0 : for( ulong i=0UL; i < (FD_GUI_REPAIR_SLOT_HISTORY_SZ+1UL); i++ ) gui->summary.slots_max_repair[ i ].slot = ULONG_MAX;
146 0 : for( ulong i=0UL; i < (FD_GUI_TURBINE_SLOT_HISTORY_SZ+1UL); i++ ) gui->summary.slots_max_turbine[ i ].slot = ULONG_MAX;
147 :
148 0 : for( ulong i=0UL; i < FD_GUI_TURBINE_RECV_TIMESTAMPS; i++ ) gui->turbine_slots[ i ].slot = ULONG_MAX;
149 :
150 0 : gui->summary.estimated_tps_history_idx = 0UL;
151 0 : memset( gui->summary.estimated_tps_history, 0, sizeof(gui->summary.estimated_tps_history) );
152 :
153 0 : memset( gui->summary.txn_waterfall_reference, 0, sizeof(gui->summary.txn_waterfall_reference) );
154 0 : memset( gui->summary.txn_waterfall_current, 0, sizeof(gui->summary.txn_waterfall_current) );
155 :
156 0 : memset( gui->summary.tile_stats_reference, 0, sizeof(gui->summary.tile_stats_reference) );
157 0 : memset( gui->summary.tile_stats_current, 0, sizeof(gui->summary.tile_stats_current) );
158 :
159 0 : memset( gui->summary.tile_timers_snap[ 0 ], 0, sizeof(gui->summary.tile_timers_snap[ 0 ]) );
160 0 : memset( gui->summary.tile_timers_snap[ 1 ], 0, sizeof(gui->summary.tile_timers_snap[ 1 ]) );
161 0 : gui->summary.tile_timers_snap_idx = 2UL;
162 :
163 0 : memset( gui->summary.scheduler_counts_snap[ 0 ], 0, sizeof(gui->summary.scheduler_counts_snap[ 0 ]) );
164 0 : memset( gui->summary.scheduler_counts_snap[ 1 ], 0, sizeof(gui->summary.scheduler_counts_snap[ 1 ]) );
165 0 : gui->summary.scheduler_counts_snap_idx = 2UL;
166 :
167 0 : for( ulong i=0UL; i<FD_GUI_SLOTS_CNT; i++ ) gui->slots[ i ]->slot = ULONG_MAX;
168 0 : for( ulong i=0UL; i<FD_GUI_LEADER_CNT; i++ ) gui->leader_slots[ i ]->slot = ULONG_MAX;
169 0 : gui->leader_slots_cnt = 0UL;
170 :
171 0 : gui->tower_cnt = 0UL;
172 :
173 0 : gui->block_engine.has_block_engine = 0;
174 :
175 0 : gui->epoch.has_epoch[ 0 ] = 0;
176 0 : gui->epoch.has_epoch[ 1 ] = 0;
177 :
178 0 : gui->gossip.peer_cnt = 0UL;
179 0 : gui->vote_account.vote_account_cnt = 0UL;
180 0 : gui->validator_info.info_cnt = 0UL;
181 :
182 0 : gui->pack_txn_idx = 0UL;
183 :
184 0 : gui->shreds.leader_shred_cnt = 0UL;
185 0 : gui->shreds.staged_next_broadcast = 0UL;
186 0 : gui->shreds.staged_head = 0UL;
187 0 : gui->shreds.staged_tail = 0UL;
188 0 : gui->shreds.history_tail = 0UL;
189 0 : gui->shreds.history_slot = ULONG_MAX;
190 0 : gui->summary.catch_up_repair_sz = 0UL;
191 0 : gui->summary.catch_up_turbine_sz = 0UL;
192 0 : gui->summary.late_votes_sz = 0UL;
193 :
194 0 : return gui;
195 0 : }
196 :
197 : fd_gui_t *
198 0 : fd_gui_join( void * shmem ) {
199 0 : return (fd_gui_t *)shmem;
200 0 : }
201 :
202 : void
203 : fd_gui_set_identity( fd_gui_t * gui,
204 0 : uchar const * identity_pubkey ) {
205 0 : memcpy( gui->summary.identity_key->uc, identity_pubkey, 32UL );
206 0 : fd_base58_encode_32( identity_pubkey, NULL, gui->summary.identity_key_base58 );
207 0 : gui->summary.identity_key_base58[ FD_BASE58_ENCODED_32_SZ-1UL ] = '\0';
208 :
209 0 : fd_gui_printf_identity_key( gui );
210 0 : fd_http_server_ws_broadcast( gui->http );
211 :
212 0 : fd_gui_printf_identity_balance( gui );
213 0 : fd_http_server_ws_broadcast( gui->http );
214 0 : }
215 :
216 : void
217 : fd_gui_ws_open( fd_gui_t * gui,
218 : ulong ws_conn_id,
219 0 : long now ) {
220 0 : void (* printers[] )( fd_gui_t * gui ) = {
221 0 : gui->summary.is_full_client ? fd_gui_printf_boot_progress : fd_gui_printf_startup_progress,
222 0 : fd_gui_printf_version,
223 0 : fd_gui_printf_cluster,
224 0 : fd_gui_printf_commit_hash,
225 0 : fd_gui_printf_identity_key,
226 0 : fd_gui_printf_vote_key,
227 0 : fd_gui_printf_startup_time_nanos,
228 0 : fd_gui_printf_vote_state,
229 0 : fd_gui_printf_vote_distance,
230 0 : fd_gui_printf_turbine_slot,
231 0 : fd_gui_printf_repair_slot,
232 0 : fd_gui_printf_slot_caught_up,
233 0 : fd_gui_printf_skipped_history,
234 0 : fd_gui_printf_skipped_history_cluster,
235 0 : fd_gui_printf_tps_history,
236 0 : fd_gui_printf_tiles,
237 0 : fd_gui_printf_schedule_strategy,
238 0 : fd_gui_printf_identity_balance,
239 0 : fd_gui_printf_vote_balance,
240 0 : fd_gui_printf_estimated_slot_duration_nanos,
241 0 : fd_gui_printf_root_slot,
242 0 : fd_gui_printf_storage_slot,
243 0 : fd_gui_printf_reset_slot,
244 0 : fd_gui_printf_active_fork_cnt,
245 0 : fd_gui_printf_optimistically_confirmed_slot,
246 0 : fd_gui_printf_completed_slot,
247 0 : fd_gui_printf_estimated_slot,
248 0 : fd_gui_printf_live_tile_timers,
249 0 : fd_gui_printf_live_tile_metrics,
250 0 : fd_gui_printf_catch_up_history,
251 0 : fd_gui_printf_vote_latency_history,
252 0 : fd_gui_printf_late_votes_history
253 0 : };
254 :
255 0 : ulong printers_len = sizeof(printers) / sizeof(printers[0]);
256 0 : for( ulong i=0UL; i<printers_len; i++ ) {
257 0 : printers[ i ]( gui );
258 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
259 0 : }
260 :
261 0 : if( FD_LIKELY( gui->block_engine.has_block_engine ) ) {
262 0 : fd_gui_printf_block_engine( gui );
263 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
264 0 : }
265 :
266 0 : for( ulong i=0UL; i<2UL; i++ ) {
267 0 : if( FD_LIKELY( gui->epoch.has_epoch[ i ] ) ) {
268 0 : fd_gui_printf_skip_rate( gui, i );
269 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
270 0 : fd_gui_printf_epoch( gui, i );
271 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
272 0 : }
273 0 : }
274 :
275 : /* Print peers last because it's the largest message and would
276 : block other information. */
277 0 : fd_gui_printf_peers_all( gui );
278 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
279 :
280 : /* rebroadcast 10s of historical shred data */
281 0 : if( FD_LIKELY( gui->shreds.staged_next_broadcast!=ULONG_MAX ) ) {
282 0 : fd_gui_printf_shred_rebroadcast( gui, now-(long)(10*1e9) );
283 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
284 0 : }
285 0 : }
286 :
287 : static void
288 0 : fd_gui_tile_timers_snap( fd_gui_t * gui ) {
289 0 : fd_gui_tile_timers_t * cur = gui->summary.tile_timers_snap[ gui->summary.tile_timers_snap_idx ];
290 0 : gui->summary.tile_timers_snap_idx = (gui->summary.tile_timers_snap_idx+1UL)%FD_GUI_TILE_TIMER_SNAP_CNT;
291 0 : for( ulong i=0UL; i<gui->topo->tile_cnt; i++ ) {
292 0 : fd_topo_tile_t * tile = &gui->topo->tiles[ i ];
293 0 : if ( FD_UNLIKELY( !tile->metrics ) ) {
294 : /* bench tiles might not have been booted initially.
295 : This check shouldn't be necessary if all tiles barrier after boot. */
296 : // TODO(FIXME) this probably isn't the right fix but it makes fddev bench work for now
297 0 : return;
298 0 : }
299 0 : volatile ulong const * tile_metrics = fd_metrics_tile( tile->metrics );
300 :
301 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_CAUGHT_UP_HOUSEKEEPING_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_CAUGHT_UP_HOUSEKEEPING ) ];
302 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_PROCESSING_HOUSEKEEPING_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_PROCESSING_HOUSEKEEPING ) ];
303 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_BACKPRESSURE_HOUSEKEEPING_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_BACKPRESSURE_HOUSEKEEPING ) ];
304 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_CAUGHT_UP_PREFRAG_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_CAUGHT_UP_PREFRAG ) ];
305 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_PROCESSING_PREFRAG_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_PROCESSING_PREFRAG ) ];
306 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_BACKPRESSURE_PREFRAG_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_BACKPRESSURE_PREFRAG ) ];
307 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_CAUGHT_UP_POSTFRAG_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_CAUGHT_UP_POSTFRAG ) ];
308 0 : cur[ i ].timers[ FD_METRICS_ENUM_TILE_REGIME_V_PROCESSING_POSTFRAG_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, REGIME_DURATION_NANOS_PROCESSING_POSTFRAG ) ];
309 :
310 0 : cur[ i ].sched_timers[ FD_METRICS_ENUM_CPU_REGIME_V_WAIT_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, CPU_DURATION_NANOS_WAIT ) ];
311 0 : cur[ i ].sched_timers[ FD_METRICS_ENUM_CPU_REGIME_V_USER_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, CPU_DURATION_NANOS_USER ) ];
312 0 : cur[ i ].sched_timers[ FD_METRICS_ENUM_CPU_REGIME_V_SYSTEM_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, CPU_DURATION_NANOS_SYSTEM ) ];
313 0 : cur[ i ].sched_timers[ FD_METRICS_ENUM_CPU_REGIME_V_IDLE_IDX ] = tile_metrics[ MIDX( COUNTER, TILE, CPU_DURATION_NANOS_IDLE ) ];
314 :
315 0 : cur[ i ].in_backp = (int)tile_metrics[ MIDX(GAUGE, TILE, IN_BACKPRESSURE) ];
316 0 : cur[ i ].status = (uchar)tile_metrics[ MIDX( GAUGE, TILE, STATUS ) ];
317 0 : cur[ i ].heartbeat = tile_metrics[ MIDX( GAUGE, TILE, HEARTBEAT ) ];
318 0 : cur[ i ].backp_cnt = tile_metrics[ MIDX( COUNTER, TILE, BACKPRESSURE_COUNT ) ];
319 0 : cur[ i ].nvcsw = tile_metrics[ MIDX( COUNTER, TILE, CONTEXT_SWITCH_VOLUNTARY_COUNT ) ];
320 0 : cur[ i ].nivcsw = tile_metrics[ MIDX( COUNTER, TILE, CONTEXT_SWITCH_INVOLUNTARY_COUNT ) ];
321 0 : cur[ i ].minflt = tile_metrics[ MIDX( COUNTER, TILE, PAGE_FAULT_MINOR_COUNT ) ];
322 0 : cur[ i ].majflt = tile_metrics[ MIDX( COUNTER, TILE, PAGE_FAULT_MAJOR_COUNT ) ];
323 0 : cur[ i ].last_cpu = (ushort)tile_metrics[ MIDX( GAUGE, TILE, LAST_CPU ) ];
324 0 : }
325 0 : }
326 :
327 : static void
328 0 : fd_gui_scheduler_counts_snap( fd_gui_t * gui, long now ) {
329 0 : fd_gui_scheduler_counts_t * cur = gui->summary.scheduler_counts_snap[ gui->summary.scheduler_counts_snap_idx ];
330 0 : gui->summary.scheduler_counts_snap_idx = (gui->summary.scheduler_counts_snap_idx+1UL)%FD_GUI_SCHEDULER_COUNT_SNAP_CNT;
331 :
332 0 : fd_topo_tile_t const * pack = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "pack", 0UL ) ];
333 0 : volatile ulong const * pack_metrics = fd_metrics_tile( pack->metrics );
334 :
335 0 : cur->sample_time_ns = now;
336 :
337 0 : cur->regular = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS_REGULAR ) ];
338 0 : cur->votes = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS_VOTES ) ];
339 0 : cur->conflicting = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS_CONFLICTING ) ];
340 0 : cur->bundles = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS_BUNDLES ) ];
341 0 : }
342 :
343 : static void
344 0 : fd_gui_estimated_tps_snap( fd_gui_t * gui ) {
345 0 : ulong total_txn_cnt = 0UL;
346 0 : ulong vote_txn_cnt = 0UL;
347 0 : ulong nonvote_failed_txn_cnt = 0UL;
348 :
349 0 : if( FD_LIKELY( gui->summary.slot_completed==ULONG_MAX ) ) return;
350 0 : for( ulong i=0UL; i<fd_ulong_min( gui->summary.slot_completed+1UL, FD_GUI_SLOTS_CNT ); i++ ) {
351 0 : ulong _slot = gui->summary.slot_completed-i;
352 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, _slot );
353 0 : if( FD_UNLIKELY( !slot ) ) break; /* Slot no longer exists, no TPS. */
354 0 : if( FD_UNLIKELY( slot->completed_time==LONG_MAX ) ) continue; /* Slot is on this fork but was never completed, must have been in root path on boot. */
355 0 : if( FD_UNLIKELY( slot->completed_time+FD_GUI_TPS_HISTORY_WINDOW_DURATION_SECONDS*1000L*1000L*1000L<gui->next_sample_400millis ) ) break; /* Slot too old. */
356 0 : if( FD_UNLIKELY( slot->skipped ) ) continue; /* Skipped slots don't count to TPS. */
357 :
358 0 : total_txn_cnt += slot->total_txn_cnt;
359 0 : vote_txn_cnt += slot->vote_txn_cnt;
360 0 : nonvote_failed_txn_cnt += slot->nonvote_failed_txn_cnt;
361 0 : }
362 :
363 0 : gui->summary.estimated_tps_history[ gui->summary.estimated_tps_history_idx ][ 0 ] = total_txn_cnt;
364 0 : gui->summary.estimated_tps_history[ gui->summary.estimated_tps_history_idx ][ 1 ] = vote_txn_cnt;
365 0 : gui->summary.estimated_tps_history[ gui->summary.estimated_tps_history_idx ][ 2 ] = nonvote_failed_txn_cnt;
366 0 : gui->summary.estimated_tps_history_idx = (gui->summary.estimated_tps_history_idx+1UL) % FD_GUI_TPS_HISTORY_SAMPLE_CNT;
367 0 : }
368 :
369 : static void
370 : fd_gui_network_stats_snap( fd_gui_t * gui,
371 0 : fd_gui_network_stats_t * cur ) {
372 0 : fd_topo_t * topo = gui->topo;
373 0 : ulong gossvf_tile_cnt = fd_topo_tile_name_cnt( topo, "gossvf" );
374 0 : ulong gossip_tile_cnt = fd_topo_tile_name_cnt( topo, "gossip" );
375 0 : ulong shred_tile_cnt = fd_topo_tile_name_cnt( topo, "shred" );
376 0 : ulong net_tile_cnt = fd_topo_tile_name_cnt( topo, "net" );
377 0 : ulong quic_tile_cnt = fd_topo_tile_name_cnt( topo, "quic" );
378 :
379 0 : cur->in.gossip = fd_gui_metrics_gossip_total_ingress_bytes( topo, gossvf_tile_cnt );
380 0 : cur->out.gossip = fd_gui_metrics_gosip_total_egress_bytes( topo, gossip_tile_cnt );
381 0 : cur->in.turbine = fd_gui_metrics_sum_tiles_counter( topo, "shred", shred_tile_cnt, MIDX( COUNTER, SHRED, SHRED_TURBINE_RCV_BYTES ) );
382 :
383 0 : cur->out.turbine = 0UL;
384 0 : cur->out.repair = 0UL;
385 0 : cur->out.tpu = 0UL;
386 0 : for( ulong i=0UL; i<net_tile_cnt; i++ ) {
387 0 : ulong net_tile_idx = fd_topo_find_tile( topo, "net", i );
388 0 : if( FD_UNLIKELY( net_tile_idx==ULONG_MAX ) ) continue;
389 0 : fd_topo_tile_t const * net = &topo->tiles[ net_tile_idx ];
390 0 : for( ulong j=0UL; j<net->in_cnt; j++ ) {
391 0 : if( FD_UNLIKELY( !strcmp( topo->links[ net->in_link_id[ j ] ].name, "shred_net" ) ) ) {
392 0 : cur->out.turbine += fd_metrics_link_in( net->metrics, j )[ FD_METRICS_COUNTER_LINK_CONSUMED_SIZE_BYTES_OFF ];
393 0 : }
394 :
395 0 : if( FD_UNLIKELY( !strcmp( topo->links[ net->in_link_id[ j ] ].name, "repair_net" ) ) ) {
396 0 : cur->out.repair += fd_metrics_link_in( net->metrics, j )[ FD_METRICS_COUNTER_LINK_CONSUMED_SIZE_BYTES_OFF ];
397 0 : }
398 :
399 0 : if( FD_UNLIKELY( !strcmp( topo->links[ net->in_link_id[ j ] ].name, "send_net" ) ) ) {
400 0 : cur->out.tpu += fd_metrics_link_in( net->metrics, j )[ FD_METRICS_COUNTER_LINK_CONSUMED_SIZE_BYTES_OFF ];
401 0 : }
402 0 : }
403 0 : }
404 :
405 0 : cur->in.repair = fd_gui_metrics_sum_tiles_counter( topo, "shred", shred_tile_cnt, MIDX( COUNTER, SHRED, SHRED_REPAIR_RCV_BYTES ) );
406 0 : ulong repair_tile_idx = fd_topo_find_tile( topo, "repair", 0UL );
407 0 : if( FD_LIKELY( repair_tile_idx!=ULONG_MAX ) ) {
408 0 : fd_topo_tile_t const * repair = &topo->tiles[ repair_tile_idx ];
409 :
410 0 : for( ulong i=0UL; i<repair->in_cnt; i++ ) {
411 0 : if( FD_UNLIKELY( !strcmp( topo->links[ repair->in_link_id[ i ] ].name, "net_repair" ) ) ) {
412 0 : cur->in.repair += fd_metrics_link_in( repair->metrics, i )[ FD_METRICS_COUNTER_LINK_CONSUMED_SIZE_BYTES_OFF ];
413 0 : }
414 0 : }
415 0 : }
416 :
417 0 : cur->in.tpu = 0UL;
418 0 : for( ulong i=0UL; i<quic_tile_cnt; i++ ) {
419 0 : ulong quic_tile_idx = fd_topo_find_tile( topo, "quic", i );
420 0 : if( FD_UNLIKELY( quic_tile_idx==ULONG_MAX ) ) continue;
421 0 : fd_topo_tile_t const * quic = &topo->tiles[ quic_tile_idx ];
422 0 : volatile ulong * quic_metrics = fd_metrics_tile( quic->metrics );
423 0 : cur->in.tpu += quic_metrics[ MIDX( COUNTER, QUIC, RECEIVED_BYTES ) ];
424 0 : }
425 :
426 0 : ulong bundle_tile_idx = fd_topo_find_tile( topo, "bundle", 0UL );
427 0 : if( FD_LIKELY( bundle_tile_idx!=ULONG_MAX ) ) {
428 0 : fd_topo_tile_t const * bundle = &topo->tiles[ bundle_tile_idx ];
429 0 : volatile ulong * bundle_metrics = fd_metrics_tile( bundle->metrics );
430 0 : cur->in.tpu += bundle_metrics[ MIDX( COUNTER, BUNDLE, PROTO_RECEIVED_BYTES ) ];
431 0 : }
432 :
433 0 : ulong metric_tile_idx = fd_topo_find_tile( topo, "metric", 0UL );
434 0 : if( FD_LIKELY( metric_tile_idx!=ULONG_MAX ) ) {
435 0 : fd_topo_tile_t const * metric = &topo->tiles[ metric_tile_idx ];
436 0 : volatile ulong * metric_metrics = fd_metrics_tile( metric->metrics );
437 0 : cur->in.metric = metric_metrics[ MIDX( COUNTER, METRIC, BYTES_READ ) ];
438 0 : cur->out.metric = metric_metrics[ MIDX( COUNTER, METRIC, BYTES_WRITTEN ) ];
439 0 : } else {
440 0 : cur->in.metric = 0UL;
441 0 : cur->out.metric = 0UL;
442 0 : }
443 0 : }
444 :
445 : /* Snapshot all of the data from metrics to construct a view of the
446 : transaction waterfall.
447 :
448 : Tiles are sampled in reverse pipeline order: this helps prevent data
449 : discrepancies where a later tile has "seen" more transactions than an
450 : earlier tile, which shouldn't typically happen. */
451 :
452 : static void
453 : fd_gui_txn_waterfall_snap( fd_gui_t * gui,
454 0 : fd_gui_txn_waterfall_t * cur ) {
455 0 : fd_topo_t * topo = gui->topo;
456 :
457 0 : cur->out.block_success = 0UL;
458 0 : cur->out.block_fail = 0UL;
459 :
460 0 : cur->out.bank_invalid = 0UL;
461 0 : for( ulong i=0UL; i<gui->summary.bank_tile_cnt; i++ ) {
462 0 : fd_topo_tile_t const * bank = &topo->tiles[ fd_topo_find_tile( topo, "bank", i ) ];
463 :
464 0 : volatile ulong const * bank_metrics = fd_metrics_tile( bank->metrics );
465 0 : cur->out.block_success += bank_metrics[ MIDX( COUNTER, BANK, SUCCESSFUL_TRANSACTIONS ) ];
466 :
467 0 : cur->out.block_fail +=
468 0 : bank_metrics[ MIDX( COUNTER, BANK, EXECUTED_FAILED_TRANSACTIONS ) ]
469 0 : + bank_metrics[ MIDX( COUNTER, BANK, FEE_ONLY_TRANSACTIONS ) ];
470 :
471 0 : cur->out.bank_invalid +=
472 0 : bank_metrics[ MIDX( COUNTER, BANK, TRANSACTION_LOAD_ADDRESS_TABLES_ACCOUNT_UNINITIALIZED ) ]
473 0 : + bank_metrics[ MIDX( COUNTER, BANK, TRANSACTION_LOAD_ADDRESS_TABLES_ACCOUNT_NOT_FOUND ) ]
474 0 : + bank_metrics[ MIDX( COUNTER, BANK, TRANSACTION_LOAD_ADDRESS_TABLES_INVALID_ACCOUNT_OWNER ) ]
475 0 : + bank_metrics[ MIDX( COUNTER, BANK, TRANSACTION_LOAD_ADDRESS_TABLES_INVALID_ACCOUNT_DATA ) ]
476 0 : + bank_metrics[ MIDX( COUNTER, BANK, TRANSACTION_LOAD_ADDRESS_TABLES_INVALID_LOOKUP_INDEX ) ];
477 :
478 0 : cur->out.bank_invalid +=
479 0 : bank_metrics[ MIDX( COUNTER, BANK, PROCESSING_FAILED ) ];
480 :
481 : /* These branches are unused in Frankendancer */
482 0 : cur->out.bank_nonce_already_advanced = 0UL;
483 0 : cur->out.bank_nonce_advance_failed = 0UL;
484 0 : cur->out.bank_nonce_wrong_blockhash = 0UL;
485 0 : }
486 :
487 0 : for( ulong i=0UL; i<gui->summary.execle_tile_cnt; i++ ) {
488 0 : fd_topo_tile_t const * execle = &topo->tiles[ fd_topo_find_tile( topo, "execle", i ) ];
489 :
490 0 : volatile ulong const * execle_metrics = fd_metrics_tile( execle->metrics );
491 :
492 0 : cur->out.block_success += execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_LANDED_LANDED_SUCCESS ) ];
493 0 : cur->out.block_fail +=
494 0 : execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_LANDED_LANDED_FEES_ONLY ) ]
495 0 : + execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_LANDED_LANDED_FAILED ) ];
496 0 : cur->out.bank_invalid += execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_LANDED_UNLANDED ) ];
497 :
498 0 : cur->out.bank_nonce_already_advanced = execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_RESULT_NONCE_ALREADY_ADVANCED ) ];
499 0 : cur->out.bank_nonce_advance_failed = execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_RESULT_NONCE_ADVANCE_FAILED ) ];
500 0 : cur->out.bank_nonce_wrong_blockhash = execle_metrics[ MIDX( COUNTER, EXECLE, TRANSACTION_RESULT_NONCE_WRONG_BLOCKHASH ) ];
501 0 : }
502 :
503 0 : fd_topo_tile_t const * pack = &topo->tiles[ fd_topo_find_tile( topo, "pack", 0UL ) ];
504 0 : volatile ulong const * pack_metrics = fd_metrics_tile( pack->metrics );
505 :
506 0 : cur->out.pack_invalid_bundle =
507 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_DROPPED_PARTIAL_BUNDLE ) ]
508 0 : + pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_INSERTION_FAILED ) ]
509 0 : + pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_CREATION_FAILED ) ];
510 :
511 0 : cur->out.pack_invalid =
512 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_NONCE_CONFLICT ) ]
513 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_BUNDLE_BLACKLIST ) ]
514 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_INVALID_NONCE ) ]
515 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_WRITE_SYSVAR ) ]
516 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_ESTIMATION_FAIL ) ]
517 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_DUPLICATE_ACCOUNT ) ]
518 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_TOO_MANY_ACCOUNTS ) ]
519 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_TOO_LARGE ) ]
520 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_ADDR_LUT ) ]
521 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_UNAFFORDABLE ) ]
522 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_DUPLICATE ) ]
523 0 : - pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_INSERTION_FAILED ) ]; /* so we don't double count this, since its already accounted for in invalid_bundle */
524 :
525 0 : cur->out.pack_expired = pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_EXPIRED ) ] +
526 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_EXPIRED ) ] +
527 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_DELETED ) ] +
528 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_NONCE_PRIORITY ) ];
529 :
530 0 : cur->out.pack_already_executed = pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_ALREADY_EXECUTED ) ];
531 :
532 0 : cur->out.pack_leader_slow = pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_PRIORITY ) ];
533 :
534 0 : cur->out.pack_wait_full =
535 0 : pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_DROPPED_FROM_EXTRA ) ];
536 :
537 0 : cur->out.pack_retained = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS ) ];
538 :
539 0 : ulong inserted_to_extra = pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_TO_EXTRA ) ];
540 0 : ulong inserted_from_extra = pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_INSERTED_FROM_EXTRA ) ]
541 0 : + pack_metrics[ MIDX( COUNTER, PACK, TRANSACTION_DROPPED_FROM_EXTRA ) ];
542 0 : cur->out.pack_retained += fd_ulong_if( inserted_to_extra>=inserted_from_extra, inserted_to_extra-inserted_from_extra, 0UL );
543 :
544 0 : cur->out.resolv_lut_failed = 0UL;
545 0 : cur->out.resolv_expired = 0UL;
546 0 : cur->out.resolv_ancient = 0UL;
547 0 : cur->out.resolv_no_ledger = 0UL;
548 0 : cur->out.resolv_retained = 0UL;
549 0 : for( ulong i=0UL; i<gui->summary.resolh_tile_cnt; i++ ) {
550 0 : fd_topo_tile_t const * resolv = &topo->tiles[ fd_topo_find_tile( topo, "resolh", i ) ];
551 0 : volatile ulong const * resolv_metrics = fd_metrics_tile( resolv->metrics );
552 :
553 0 : cur->out.resolv_no_ledger += resolv_metrics[ MIDX( COUNTER, RESOLH, NO_BANK_DROP ) ];
554 0 : cur->out.resolv_expired += resolv_metrics[ MIDX( COUNTER, RESOLH, BLOCKHASH_EXPIRED ) ]
555 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, TRANSACTION_BUNDLE_PEER_FAILURE ) ];
556 0 : cur->out.resolv_lut_failed += resolv_metrics[ MIDX( COUNTER, RESOLH, LUT_RESOLVED_ACCOUNT_NOT_FOUND ) ]
557 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, LUT_RESOLVED_INVALID_ACCOUNT_OWNER ) ]
558 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, LUT_RESOLVED_INVALID_ACCOUNT_DATA ) ]
559 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, LUT_RESOLVED_ACCOUNT_UNINITIALIZED ) ]
560 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, LUT_RESOLVED_INVALID_LOOKUP_INDEX ) ];
561 0 : cur->out.resolv_ancient += resolv_metrics[ MIDX( COUNTER, RESOLH, STASH_OPERATION_OVERRUN ) ];
562 :
563 0 : ulong inserted_to_resolv = resolv_metrics[ MIDX( COUNTER, RESOLH, STASH_OPERATION_INSERTED ) ];
564 0 : ulong removed_from_resolv = resolv_metrics[ MIDX( COUNTER, RESOLH, STASH_OPERATION_OVERRUN ) ]
565 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, STASH_OPERATION_PUBLISHED ) ]
566 0 : + resolv_metrics[ MIDX( COUNTER, RESOLH, STASH_OPERATION_REMOVED ) ];
567 0 : cur->out.resolv_retained += fd_ulong_if( inserted_to_resolv>=removed_from_resolv, inserted_to_resolv-removed_from_resolv, 0UL );
568 0 : }
569 :
570 0 : for( ulong i=0UL; i<gui->summary.resolv_tile_cnt; i++ ) {
571 0 : fd_topo_tile_t const * resolv = &topo->tiles[ fd_topo_find_tile( topo, "resolv", i ) ];
572 0 : volatile ulong const * resolv_metrics = fd_metrics_tile( resolv->metrics );
573 :
574 0 : cur->out.resolv_no_ledger += resolv_metrics[ MIDX( COUNTER, RESOLV, NO_BANK_DROP ) ];
575 0 : cur->out.resolv_expired += resolv_metrics[ MIDX( COUNTER, RESOLV, BLOCKHASH_EXPIRED ) ]
576 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, TRANSACTION_BUNDLE_PEER_FAILURE ) ];
577 0 : cur->out.resolv_lut_failed += resolv_metrics[ MIDX( COUNTER, RESOLV, LUT_RESOLVED_ACCOUNT_NOT_FOUND ) ]
578 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, LUT_RESOLVED_INVALID_ACCOUNT_OWNER ) ]
579 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, LUT_RESOLVED_INVALID_ACCOUNT_DATA ) ]
580 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, LUT_RESOLVED_ACCOUNT_UNINITIALIZED ) ]
581 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, LUT_RESOLVED_INVALID_LOOKUP_INDEX ) ];
582 0 : cur->out.resolv_ancient += resolv_metrics[ MIDX( COUNTER, RESOLV, STASH_OPERATION_OVERRUN ) ];
583 :
584 0 : ulong inserted_to_resolv = resolv_metrics[ MIDX( COUNTER, RESOLV, STASH_OPERATION_INSERTED ) ];
585 0 : ulong removed_from_resolv = resolv_metrics[ MIDX( COUNTER, RESOLV, STASH_OPERATION_OVERRUN ) ]
586 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, STASH_OPERATION_PUBLISHED ) ]
587 0 : + resolv_metrics[ MIDX( COUNTER, RESOLV, STASH_OPERATION_REMOVED ) ];
588 0 : cur->out.resolv_retained += fd_ulong_if( inserted_to_resolv>=removed_from_resolv, inserted_to_resolv-removed_from_resolv, 0UL );
589 0 : }
590 :
591 :
592 0 : fd_topo_tile_t const * dedup = &topo->tiles[ fd_topo_find_tile( topo, "dedup", 0UL ) ];
593 0 : volatile ulong const * dedup_metrics = fd_metrics_tile( dedup->metrics );
594 :
595 0 : cur->out.dedup_duplicate = dedup_metrics[ MIDX( COUNTER, DEDUP, TRANSACTION_RESULT_DEDUP_FAILURE ) ]
596 0 : + dedup_metrics[ MIDX( COUNTER, DEDUP, TRANSACTION_RESULT_BUNDLE_PEER_FAILURE ) ];
597 :
598 :
599 0 : cur->out.verify_overrun = 0UL;
600 0 : cur->out.verify_duplicate = 0UL;
601 0 : cur->out.verify_parse = 0UL;
602 0 : cur->out.verify_failed = 0UL;
603 :
604 0 : for( ulong i=0UL; i<gui->summary.verify_tile_cnt; i++ ) {
605 0 : fd_topo_tile_t const * verify = &topo->tiles[ fd_topo_find_tile( topo, "verify", i ) ];
606 0 : volatile ulong const * verify_metrics = fd_metrics_tile( verify->metrics );
607 :
608 0 : for( ulong j=0UL; j<gui->summary.quic_tile_cnt; j++ ) {
609 : /* TODO: Not precise... even if 1 frag gets skipped, it could have been for this verify tile. */
610 0 : cur->out.verify_overrun += fd_metrics_link_in( verify->metrics, j )[ FD_METRICS_COUNTER_LINK_OVERRUN_POLLING_FRAG_COUNT_OFF ] / gui->summary.verify_tile_cnt;
611 0 : cur->out.verify_overrun += fd_metrics_link_in( verify->metrics, j )[ FD_METRICS_COUNTER_LINK_OVERRUN_READING_FRAG_COUNT_OFF ];
612 0 : }
613 :
614 0 : cur->out.verify_failed += verify_metrics[ MIDX( COUNTER, VERIFY, TRANSACTION_RESULT_VERIFY_FAILURE ) ] +
615 0 : verify_metrics[ MIDX( COUNTER, VERIFY, TRANSACTION_RESULT_BUNDLE_PEER_FAILURE ) ];
616 0 : cur->out.verify_parse += verify_metrics[ MIDX( COUNTER, VERIFY, TRANSACTION_RESULT_PARSE_FAILURE ) ];
617 0 : cur->out.verify_duplicate += verify_metrics[ MIDX( COUNTER, VERIFY, TRANSACTION_RESULT_DEDUP_FAILURE ) ];
618 0 : }
619 :
620 :
621 0 : cur->out.quic_overrun = 0UL;
622 0 : cur->out.quic_frag_drop = 0UL;
623 0 : cur->out.quic_abandoned = 0UL;
624 0 : cur->out.tpu_quic_invalid = 0UL;
625 0 : cur->out.tpu_udp_invalid = 0UL;
626 0 : for( ulong i=0UL; i<gui->summary.quic_tile_cnt; i++ ) {
627 0 : fd_topo_tile_t const * quic = &topo->tiles[ fd_topo_find_tile( topo, "quic", i ) ];
628 0 : volatile ulong * quic_metrics = fd_metrics_tile( quic->metrics );
629 :
630 0 : cur->out.tpu_udp_invalid += quic_metrics[ MIDX( COUNTER, QUIC, LEGACY_TXN_UNDERSZ ) ];
631 0 : cur->out.tpu_udp_invalid += quic_metrics[ MIDX( COUNTER, QUIC, LEGACY_TXN_OVERSZ ) ];
632 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_UNDERSZ ) ];
633 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_OVERSZ ) ];
634 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, TXN_OVERSZ ) ];
635 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_CRYPTO_FAILED ) ];
636 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_NO_CONN ) ];
637 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_NET_HEADER_INVALID ) ];
638 0 : cur->out.tpu_quic_invalid += quic_metrics[ MIDX( COUNTER, QUIC, PKT_QUIC_HEADER_INVALID ) ];
639 0 : cur->out.quic_abandoned += quic_metrics[ MIDX( COUNTER, QUIC, TXNS_ABANDONED ) ];
640 0 : cur->out.quic_frag_drop += quic_metrics[ MIDX( COUNTER, QUIC, TXNS_OVERRUN ) ];
641 :
642 0 : for( ulong j=0UL; j<gui->summary.net_tile_cnt; j++ ) {
643 : /* TODO: Not precise... net frags that were skipped might not have been destined for QUIC tile */
644 : /* TODO: Not precise... even if 1 frag gets skipped, it could have been for this QUIC tile */
645 0 : cur->out.quic_overrun += fd_metrics_link_in( quic->metrics, j )[ FD_METRICS_COUNTER_LINK_OVERRUN_POLLING_FRAG_COUNT_OFF ] / gui->summary.quic_tile_cnt;
646 0 : cur->out.quic_overrun += fd_metrics_link_in( quic->metrics, j )[ FD_METRICS_COUNTER_LINK_OVERRUN_READING_FRAG_COUNT_OFF ];
647 0 : }
648 0 : }
649 :
650 0 : cur->out.net_overrun = 0UL;
651 0 : for( ulong i=0UL; i<gui->summary.net_tile_cnt; i++ ) {
652 0 : fd_topo_tile_t const * net = &topo->tiles[ fd_topo_find_tile( topo, "net", i ) ];
653 0 : volatile ulong * net_metrics = fd_metrics_tile( net->metrics );
654 :
655 0 : cur->out.net_overrun += net_metrics[ MIDX( COUNTER, NET, XDP_RX_RING_FULL ) ];
656 0 : cur->out.net_overrun += net_metrics[ MIDX( COUNTER, NET, XDP_RX_DROPPED_OTHER ) ];
657 0 : cur->out.net_overrun += net_metrics[ MIDX( COUNTER, NET, XDP_RX_FILL_RING_EMPTY_DESCS ) ];
658 0 : }
659 :
660 0 : ulong bundle_txns_received = 0UL;
661 0 : ulong bundle_tile_idx = fd_topo_find_tile( topo, "bundle", 0UL );
662 0 : if( FD_LIKELY( bundle_tile_idx!=ULONG_MAX ) ) {
663 0 : fd_topo_tile_t const * bundle = &topo->tiles[ bundle_tile_idx ];
664 0 : volatile ulong const * bundle_metrics = fd_metrics_tile( bundle->metrics );
665 :
666 0 : bundle_txns_received = bundle_metrics[ MIDX( COUNTER, BUNDLE, TRANSACTION_RECEIVED ) ];
667 0 : }
668 :
669 0 : cur->in.pack_cranked =
670 0 : pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_INSERTED ) ]
671 0 : + pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_INSERTION_FAILED ) ]
672 0 : + pack_metrics[ MIDX( COUNTER, PACK, BUNDLE_CRANK_STATUS_CREATION_FAILED ) ];
673 :
674 0 : if( FD_UNLIKELY( gui->summary.is_full_client ) ) {
675 0 : cur->in.gossip = 0UL;
676 0 : for( ulong i=0UL; i<gui->summary.verify_tile_cnt; i++ ) {
677 0 : fd_topo_tile_t const * verify = &topo->tiles[ fd_topo_find_tile( topo, "verify", i ) ];
678 0 : volatile ulong const * verify_metrics = fd_metrics_tile( verify->metrics );
679 0 : cur->in.gossip += verify_metrics[ MIDX( COUNTER, VERIFY, GOSSIPED_VOTES_RECEIVED ) ];
680 0 : }
681 0 : } else {
682 0 : cur->in.gossip = dedup_metrics[ MIDX( COUNTER, DEDUP, GOSSIPED_VOTES_RECEIVED ) ];
683 0 : }
684 :
685 0 : cur->in.quic = cur->out.tpu_quic_invalid +
686 0 : cur->out.quic_overrun +
687 0 : cur->out.quic_frag_drop +
688 0 : cur->out.quic_abandoned +
689 0 : cur->out.net_overrun;
690 0 : cur->in.udp = cur->out.tpu_udp_invalid;
691 0 : cur->in.block_engine = bundle_txns_received;
692 0 : for( ulong i=0UL; i<gui->summary.quic_tile_cnt; i++ ) {
693 0 : fd_topo_tile_t const * quic = &topo->tiles[ fd_topo_find_tile( topo, "quic", i ) ];
694 0 : volatile ulong * quic_metrics = fd_metrics_tile( quic->metrics );
695 :
696 0 : cur->in.quic += quic_metrics[ MIDX( COUNTER, QUIC, TXNS_RECEIVED_QUIC_FAST ) ];
697 0 : cur->in.quic += quic_metrics[ MIDX( COUNTER, QUIC, TXNS_RECEIVED_QUIC_FRAG ) ];
698 0 : cur->in.udp += quic_metrics[ MIDX( COUNTER, QUIC, TXNS_RECEIVED_UDP ) ];
699 0 : }
700 0 : }
701 :
702 : static void
703 : fd_gui_tile_stats_snap( fd_gui_t * gui,
704 : fd_gui_txn_waterfall_t const * waterfall,
705 : fd_gui_tile_stats_t * stats,
706 0 : long now ) {
707 0 : fd_topo_t const * topo = gui->topo;
708 :
709 0 : stats->sample_time_nanos = now;
710 :
711 0 : stats->net_in_rx_bytes = 0UL;
712 0 : stats->net_out_tx_bytes = 0UL;
713 0 : for( ulong i=0UL; i<gui->summary.net_tile_cnt; i++ ) {
714 0 : fd_topo_tile_t const * net = &topo->tiles[ fd_topo_find_tile( topo, "net", i ) ];
715 0 : volatile ulong * net_metrics = fd_metrics_tile( net->metrics );
716 :
717 0 : stats->net_in_rx_bytes += net_metrics[ MIDX( COUNTER, NET, RX_BYTES_TOTAL ) ];
718 0 : stats->net_out_tx_bytes += net_metrics[ MIDX( COUNTER, NET, TX_BYTES_TOTAL ) ];
719 0 : }
720 :
721 0 : for( ulong i=0UL; i<gui->summary.sock_tile_cnt; i++ ) {
722 0 : fd_topo_tile_t const * sock = &topo->tiles[ fd_topo_find_tile( topo, "sock", i ) ];
723 0 : volatile ulong * sock_metrics = fd_metrics_tile( sock->metrics );
724 :
725 0 : stats->net_in_rx_bytes += sock_metrics[ MIDX( COUNTER, SOCK, RX_BYTES_TOTAL ) ];
726 0 : stats->net_out_tx_bytes += sock_metrics[ MIDX( COUNTER, SOCK, TX_BYTES_TOTAL ) ];
727 0 : }
728 :
729 0 : stats->quic_conn_cnt = 0UL;
730 0 : for( ulong i=0UL; i<gui->summary.quic_tile_cnt; i++ ) {
731 0 : fd_topo_tile_t const * quic = &topo->tiles[ fd_topo_find_tile( topo, "quic", i ) ];
732 0 : volatile ulong * quic_metrics = fd_metrics_tile( quic->metrics );
733 :
734 0 : stats->quic_conn_cnt += quic_metrics[ MIDX( GAUGE, QUIC, CONNECTIONS_ALLOC ) ];
735 0 : }
736 :
737 0 : ulong bundle_tile_idx = fd_topo_find_tile( topo, "bundle", 0UL );
738 0 : if( FD_LIKELY( bundle_tile_idx!=ULONG_MAX ) ) {
739 0 : fd_topo_tile_t const * bundle = &topo->tiles[ bundle_tile_idx ];
740 0 : volatile ulong * bundle_metrics = fd_metrics_tile( bundle->metrics );
741 0 : stats->bundle_rtt_smoothed_nanos = bundle_metrics[ MIDX( GAUGE, BUNDLE, RTT_SMOOTHED ) ];
742 :
743 0 : fd_histf_new( &stats->bundle_rx_delay_hist, FD_MHIST_MIN( BUNDLE, MESSAGE_RX_DELAY_NANOS ), FD_MHIST_MAX( BUNDLE, MESSAGE_RX_DELAY_NANOS ) );
744 0 : stats->bundle_rx_delay_hist.sum = bundle_metrics[ MIDX( HISTOGRAM, BUNDLE, MESSAGE_RX_DELAY_NANOS ) + FD_HISTF_BUCKET_CNT ];
745 0 : for( ulong b=0; b<FD_HISTF_BUCKET_CNT; b++ ) stats->bundle_rx_delay_hist.counts[ b ] = bundle_metrics[ MIDX( HISTOGRAM, BUNDLE, MESSAGE_RX_DELAY_NANOS ) + b ];
746 0 : }
747 :
748 0 : stats->verify_drop_cnt = waterfall->out.verify_duplicate +
749 0 : waterfall->out.verify_parse +
750 0 : waterfall->out.verify_failed;
751 0 : stats->verify_total_cnt = waterfall->in.gossip +
752 0 : waterfall->in.quic +
753 0 : waterfall->in.udp -
754 0 : waterfall->out.net_overrun -
755 0 : waterfall->out.tpu_quic_invalid -
756 0 : waterfall->out.tpu_udp_invalid -
757 0 : waterfall->out.quic_abandoned -
758 0 : waterfall->out.quic_frag_drop -
759 0 : waterfall->out.quic_overrun -
760 0 : waterfall->out.verify_overrun;
761 0 : stats->dedup_drop_cnt = waterfall->out.dedup_duplicate;
762 0 : stats->dedup_total_cnt = stats->verify_total_cnt -
763 0 : waterfall->out.verify_duplicate -
764 0 : waterfall->out.verify_parse -
765 0 : waterfall->out.verify_failed;
766 :
767 0 : fd_topo_tile_t const * pack = &topo->tiles[ fd_topo_find_tile( topo, "pack", 0UL ) ];
768 0 : volatile ulong const * pack_metrics = fd_metrics_tile( pack->metrics );
769 0 : stats->pack_buffer_cnt = pack_metrics[ MIDX( GAUGE, PACK, AVAILABLE_TRANSACTIONS ) ];
770 0 : stats->pack_buffer_capacity = pack->pack.max_pending_transactions;
771 :
772 0 : stats->bank_txn_exec_cnt = waterfall->out.block_fail + waterfall->out.block_success;
773 0 : }
774 :
775 : static void
776 0 : fd_gui_run_boot_progress( fd_gui_t * gui, long now ) {
777 0 : fd_topo_tile_t const * snapct = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "snapct", 0UL ) ];
778 0 : volatile ulong * snapct_metrics = fd_metrics_tile( snapct->metrics );
779 :
780 0 : fd_topo_tile_t const * snapdc = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "snapdc", 0UL ) ];
781 0 : volatile ulong * snapdc_metrics = fd_metrics_tile( snapdc->metrics );
782 :
783 0 : fd_topo_tile_t const * snapin = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "snapin", 0UL ) ];
784 0 : volatile ulong * snapin_metrics = fd_metrics_tile( snapin->metrics );
785 :
786 0 : ulong snapshot_phase = snapct_metrics[ MIDX( GAUGE, SNAPCT, STATE ) ];
787 :
788 : /* state transitions */
789 0 : if( FD_UNLIKELY( gui->summary.slot_caught_up!=ULONG_MAX ) ) {
790 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_RUNNING;
791 0 : } else if( FD_LIKELY( snapshot_phase == FD_SNAPCT_STATE_SHUTDOWN && gui->summary.slots_max_turbine[ 0 ].slot!=ULONG_MAX && gui->summary.slot_completed!=ULONG_MAX ) ) {
792 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_CATCHING_UP;
793 0 : } else if( FD_LIKELY( snapshot_phase==FD_SNAPCT_STATE_READING_FULL_FILE
794 0 : || snapshot_phase==FD_SNAPCT_STATE_FLUSHING_FULL_FILE
795 0 : || snapshot_phase==FD_SNAPCT_STATE_READING_FULL_HTTP
796 0 : || snapshot_phase==FD_SNAPCT_STATE_FLUSHING_FULL_HTTP ) ) {
797 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_LOADING_FULL_SNAPSHOT;
798 0 : } else if( FD_LIKELY( snapshot_phase==FD_SNAPCT_STATE_READING_INCREMENTAL_FILE
799 0 : || snapshot_phase==FD_SNAPCT_STATE_FLUSHING_INCREMENTAL_FILE
800 0 : || snapshot_phase==FD_SNAPCT_STATE_READING_INCREMENTAL_HTTP
801 0 : || snapshot_phase==FD_SNAPCT_STATE_FLUSHING_INCREMENTAL_HTTP ) ) {
802 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_LOADING_INCREMENTAL_SNAPSHOT;
803 0 : }
804 :
805 : /* It's possible for the incremental snapshot phase to be skipped, or
806 : complete before we can sample it. This ensures we always get at
807 : least one pass of the metrics. */
808 0 : if( FD_UNLIKELY( gui->summary.boot_progress.phase==FD_GUI_BOOT_PROGRESS_TYPE_CATCHING_UP
809 0 : && gui->summary.boot_progress.loading_snapshot[ FD_GUI_BOOT_PROGRESS_INCREMENTAL_SNAPSHOT_IDX ].reset_cnt==ULONG_MAX ) ) {
810 0 : gui->summary.boot_progress.phase = FD_GUI_BOOT_PROGRESS_TYPE_LOADING_INCREMENTAL_SNAPSHOT;
811 0 : }
812 :
813 0 : switch ( gui->summary.boot_progress.phase ) {
814 0 : case FD_GUI_BOOT_PROGRESS_TYPE_JOINING_GOSSIP: {
815 0 : gui->summary.boot_progress.joining_gossip_time_nanos = now;
816 0 : break;
817 0 : }
818 0 : case FD_GUI_BOOT_PROGRESS_TYPE_LOADING_FULL_SNAPSHOT:
819 0 : case FD_GUI_BOOT_PROGRESS_TYPE_LOADING_INCREMENTAL_SNAPSHOT: {
820 0 : ulong snapshot_idx = fd_ulong_if( gui->summary.boot_progress.phase==FD_GUI_BOOT_PROGRESS_TYPE_LOADING_FULL_SNAPSHOT, FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, FD_GUI_BOOT_PROGRESS_INCREMENTAL_SNAPSHOT_IDX );
821 0 : ulong _retry_cnt = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapct_metrics[ MIDX( GAUGE, SNAPCT, FULL_DOWNLOAD_RETRIES ) ], snapct_metrics[ MIDX( GAUGE, SNAPCT, INCREMENTAL_DOWNLOAD_RETRIES ) ]);
822 :
823 : /* reset boot state if necessary */
824 0 : if( FD_UNLIKELY( gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].reset_cnt!=_retry_cnt ) ) {
825 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].reset_time_nanos = now;
826 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].reset_cnt = _retry_cnt;
827 0 : }
828 :
829 0 : ulong _total_bytes = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapct_metrics[ MIDX( GAUGE, SNAPCT, FULL_BYTES_TOTAL ) ], snapct_metrics[ MIDX( GAUGE, SNAPCT, INCREMENTAL_BYTES_TOTAL ) ] );
830 0 : ulong _read_bytes = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapct_metrics[ MIDX( GAUGE, SNAPCT, FULL_BYTES_READ ) ], snapct_metrics[ MIDX( GAUGE, SNAPCT, INCREMENTAL_BYTES_READ ) ] );
831 0 : ulong _decompress_decompressed_bytes = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapdc_metrics[ MIDX( GAUGE, SNAPDC, FULL_DECOMPRESSED_BYTES_WRITTEN ) ], snapdc_metrics[ MIDX( GAUGE, SNAPDC, INCREMENTAL_DECOMPRESSED_BYTES_WRITTEN ) ] );
832 0 : ulong _decompress_compressed_bytes = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapdc_metrics[ MIDX( GAUGE, SNAPDC, FULL_COMPRESSED_BYTES_READ ) ], snapdc_metrics[ MIDX( GAUGE, SNAPDC, INCREMENTAL_COMPRESSED_BYTES_READ ) ] );
833 0 : ulong _insert_bytes = fd_ulong_if( snapshot_idx==FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, snapin_metrics[ MIDX( GAUGE, SNAPIN, FULL_BYTES_READ ) ], snapin_metrics[ MIDX( GAUGE, SNAPIN, INCREMENTAL_BYTES_READ ) ] );
834 0 : ulong _insert_accounts = snapin_metrics[ MIDX( GAUGE, SNAPIN, ACCOUNTS_LOADED ) ];
835 :
836 : /* metadata */
837 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].total_bytes_compressed = _total_bytes;
838 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].sample_time_nanos = now;
839 :
840 : /* read stage */
841 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].read_bytes_compressed = _read_bytes;
842 :
843 : /* decompress stage */
844 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].decompress_bytes_compressed = _decompress_compressed_bytes;
845 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].decompress_bytes_decompressed = _decompress_decompressed_bytes;
846 :
847 : /* insert stage */
848 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].insert_bytes_decompressed = _insert_bytes;
849 :
850 : /* Use the latest compression ratio to estimate decompressed size */
851 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].insert_accounts_current = _insert_accounts;
852 :
853 0 : break;
854 0 : }
855 0 : case FD_GUI_BOOT_PROGRESS_TYPE_CATCHING_UP: {
856 0 : gui->summary.boot_progress.catching_up_time_nanos = now;
857 0 : break;
858 0 : }
859 0 : case FD_GUI_BOOT_PROGRESS_TYPE_RUNNING: break;
860 0 : default: FD_LOG_ERR(( "unknown boot progress phase: %d", gui->summary.boot_progress.phase ));
861 0 : }
862 0 : }
863 :
864 : static inline int
865 0 : fd_gui_ephemeral_slots_contains( fd_gui_ephemeral_slot_t * slots, ulong slots_sz, ulong slot ) {
866 0 : for( ulong i=0UL; i<slots_sz; i++ ) {
867 0 : if( FD_UNLIKELY( slots[ i ].slot==ULONG_MAX ) ) break;
868 0 : if( FD_UNLIKELY( slots[ i ].slot==slot ) ) return 1;
869 0 : }
870 0 : return 0;
871 0 : }
872 :
873 : #define SORT_NAME fd_gui_ephemeral_slot_sort
874 0 : #define SORT_KEY_T fd_gui_ephemeral_slot_t
875 0 : #define SORT_BEFORE(a,b) fd_int_if( (a).slot==ULONG_MAX, 0, fd_int_if( (b).slot==ULONG_MAX, 1, fd_int_if( (a).slot==(b).slot, (a).timestamp_arrival_nanos>(b).timestamp_arrival_nanos, (a).slot>(b).slot ) ) )
876 : #include "../../util/tmpl/fd_sort.c"
877 :
878 : static inline void
879 0 : fd_gui_try_insert_ephemeral_slot( fd_gui_ephemeral_slot_t * slots, ulong slots_sz, ulong slot, long now ) {
880 0 : int already_present = 0;
881 0 : for( ulong i=0UL; i<slots_sz; i++ ) {
882 : /* evict any slots older than 4.8 seconds */
883 0 : if( FD_UNLIKELY( slots[ i ].slot!=ULONG_MAX && now-slots[ i ].timestamp_arrival_nanos>4800000000L ) ) {
884 0 : slots[ i ].slot = ULONG_MAX;
885 0 : continue;
886 0 : }
887 :
888 : /* if we've already seen this slot, just update the timestamp */
889 0 : if( FD_UNLIKELY( slots[ i ].slot==slot ) ) {
890 0 : slots[ i ].timestamp_arrival_nanos = now;
891 0 : already_present = 1;
892 0 : }
893 0 : }
894 0 : if( FD_LIKELY( already_present ) ) return;
895 :
896 : /* Insert the new slot number, evicting a smaller slot if necessary */
897 0 : slots[ slots_sz ].timestamp_arrival_nanos = now;
898 0 : slots[ slots_sz ].slot = slot;
899 0 : fd_gui_ephemeral_slot_sort_insert( slots, slots_sz+1UL );
900 0 : }
901 :
902 : static inline void
903 0 : fd_gui_try_insert_run_length_slot( ulong * slots, ulong capacity, ulong * slots_sz, ulong slot ) {
904 : /* catch up history is run-length encoded */
905 0 : ulong range_idx = fd_sort_up_ulong_split( slots, *slots_sz, slot );
906 0 : if( FD_UNLIKELY( range_idx<(*slots_sz)-1UL && range_idx%2UL==0UL && slots[ range_idx ]<=slot && slots[ range_idx+1UL ]>=slot ) ) return;
907 0 : if( FD_UNLIKELY( range_idx<(*slots_sz) && range_idx>0UL && range_idx%2UL==1UL && slots[ range_idx-1UL ]<=slot && slots[ range_idx ]>=slot ) ) return;
908 :
909 0 : slots[ (*slots_sz)++ ] = slot;
910 0 : slots[ (*slots_sz)++ ] = slot;
911 :
912 0 : fd_sort_up_ulong_insert( slots, (*slots_sz) );
913 :
914 : /* colesce ranges */
915 0 : ulong removed = 0UL;
916 0 : for( ulong i=1UL; i<(*slots_sz)-1UL; i+=2 ) {
917 0 : if( FD_UNLIKELY( slots[ i ]+1UL==slots[ i+1UL ] ) ) {
918 0 : slots[ i ] = ULONG_MAX;
919 0 : slots[ i+1UL ] = ULONG_MAX;
920 0 : removed += 2;
921 0 : }
922 0 : }
923 :
924 0 : if( FD_UNLIKELY( (*slots_sz)>=removed+capacity-2UL && (*slots_sz)>=4UL ) ) {
925 : /* We are at capacity, start coalescing earlier intervals. */
926 0 : slots[ 1 ] = ULONG_MAX;
927 0 : slots[ 2 ] = ULONG_MAX;
928 0 : removed += 2;
929 0 : }
930 :
931 0 : fd_sort_up_ulong_insert( slots, (*slots_sz) );
932 0 : (*slots_sz) -= removed;
933 0 : }
934 :
935 : void
936 0 : fd_gui_handle_repair_slot( fd_gui_t * gui, ulong slot, long now ) {
937 0 : int was_sent = fd_gui_ephemeral_slots_contains( gui->summary.slots_max_repair, FD_GUI_REPAIR_SLOT_HISTORY_SZ, slot );
938 0 : fd_gui_try_insert_ephemeral_slot( gui->summary.slots_max_repair, FD_GUI_REPAIR_SLOT_HISTORY_SZ, slot, now );
939 :
940 0 : if( FD_UNLIKELY( !was_sent && slot!=gui->summary.slot_repair ) ) {
941 0 : gui->summary.slot_repair = slot;
942 :
943 0 : fd_gui_printf_repair_slot( gui );
944 0 : fd_http_server_ws_broadcast( gui->http );
945 :
946 0 : if( FD_UNLIKELY( gui->summary.slot_caught_up==ULONG_MAX ) ) fd_gui_try_insert_run_length_slot( gui->summary.catch_up_repair, FD_GUI_REPAIR_CATCH_UP_HISTORY_SZ, &gui->summary.catch_up_repair_sz, slot );
947 0 : }
948 0 : }
949 :
950 : void
951 0 : fd_gui_handle_repair_request( fd_gui_t * gui, ulong slot, ulong shred_idx, long now ) {
952 0 : fd_gui_slot_staged_shred_event_t * recv_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
953 0 : gui->shreds.staged_tail++;
954 0 : recv_event->timestamp = now;
955 0 : recv_event->shred_idx = (ushort)shred_idx;
956 0 : recv_event->slot = slot;
957 0 : recv_event->event = FD_GUI_SLOT_SHRED_REPAIR_REQUEST;
958 0 : }
959 :
960 : int
961 0 : fd_gui_poll( fd_gui_t * gui, long now ) {
962 0 : if( FD_LIKELY( now>gui->next_sample_400millis ) ) {
963 0 : fd_gui_estimated_tps_snap( gui );
964 0 : fd_gui_printf_estimated_tps( gui );
965 0 : fd_http_server_ws_broadcast( gui->http );
966 :
967 0 : gui->next_sample_400millis += 400L*1000L*1000L;
968 0 : return 1;
969 0 : }
970 :
971 0 : if( FD_LIKELY( now>gui->next_sample_100millis ) ) {
972 0 : fd_gui_txn_waterfall_snap( gui, gui->summary.txn_waterfall_current );
973 0 : fd_gui_printf_live_txn_waterfall( gui, gui->summary.txn_waterfall_reference, gui->summary.txn_waterfall_current, 0UL /* TODO: REAL NEXT LEADER SLOT */ );
974 0 : fd_http_server_ws_broadcast( gui->http );
975 :
976 0 : fd_gui_network_stats_snap( gui, gui->summary.network_stats_current );
977 0 : fd_gui_printf_live_network_metrics( gui, gui->summary.network_stats_current );
978 0 : fd_http_server_ws_broadcast( gui->http );
979 :
980 0 : *gui->summary.tile_stats_reference = *gui->summary.tile_stats_current;
981 0 : fd_gui_tile_stats_snap( gui, gui->summary.txn_waterfall_current, gui->summary.tile_stats_current, now );
982 0 : fd_gui_printf_live_tile_stats( gui, gui->summary.tile_stats_reference, gui->summary.tile_stats_current );
983 0 : fd_http_server_ws_broadcast( gui->http );
984 :
985 0 : if( FD_UNLIKELY( gui->summary.is_full_client && gui->summary.boot_progress.phase!=FD_GUI_BOOT_PROGRESS_TYPE_RUNNING ) ) {
986 0 : fd_gui_run_boot_progress( gui, now );
987 0 : fd_gui_printf_boot_progress( gui );
988 0 : fd_http_server_ws_broadcast( gui->http );
989 0 : }
990 :
991 0 : gui->next_sample_100millis += 100L*1000L*1000L;
992 0 : return 1;
993 0 : }
994 :
995 0 : if( FD_LIKELY( now>gui->next_sample_50millis ) ) {
996 0 : if( FD_LIKELY( gui->summary.is_full_client && gui->shreds.staged_next_broadcast<gui->shreds.staged_tail ) ) {
997 0 : fd_gui_printf_shred_updates( gui );
998 0 : fd_http_server_ws_broadcast( gui->http );
999 0 : gui->shreds.staged_next_broadcast = gui->shreds.staged_tail;
1000 0 : }
1001 :
1002 : /* We get the repair slot from the sampled metric after catching up
1003 : and from incoming shred data before catchup. This makes the
1004 : catchup progress bar look complete while also keeping the
1005 : overview slots vis correct. TODO: do this properly using frags
1006 : sent over a link */
1007 0 : if( FD_LIKELY( gui->summary.slot_caught_up!=ULONG_MAX ) ) {
1008 0 : fd_topo_tile_t * repair = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "repair", 0UL ) ];
1009 0 : volatile ulong const * repair_metrics = fd_metrics_tile( repair->metrics );
1010 0 : ulong slot = repair_metrics[ MIDX( COUNTER, REPAIR, REPAIRED_SLOTS ) ];
1011 0 : fd_gui_handle_repair_slot( gui, slot, now );
1012 0 : }
1013 :
1014 0 : gui->next_sample_50millis += 50L*1000L*1000L;
1015 0 : return 1;
1016 0 : }
1017 :
1018 0 : if( FD_LIKELY( now>gui->next_sample_25millis ) ) {
1019 0 : fd_gui_tile_timers_snap( gui );
1020 :
1021 0 : fd_gui_printf_live_tile_timers( gui );
1022 0 : fd_http_server_ws_broadcast( gui->http );
1023 :
1024 0 : fd_gui_printf_live_tile_metrics( gui );
1025 0 : fd_http_server_ws_broadcast( gui->http );
1026 :
1027 0 : gui->next_sample_25millis += (long)(25*1000L*1000L);
1028 0 : return 1;
1029 0 : }
1030 :
1031 :
1032 0 : if( FD_LIKELY( now>gui->next_sample_10millis ) ) {
1033 0 : fd_gui_scheduler_counts_snap( gui, now );
1034 :
1035 0 : fd_gui_printf_server_time_nanos( gui, now );
1036 0 : fd_http_server_ws_broadcast( gui->http );
1037 :
1038 0 : gui->next_sample_10millis += 10L*1000L*1000L;
1039 0 : return 1;
1040 0 : }
1041 :
1042 0 : return 0;
1043 0 : }
1044 :
1045 : static void
1046 : fd_gui_handle_gossip_update( fd_gui_t * gui,
1047 0 : uchar const * msg ) {
1048 : /* `gui->gossip.peer_cnt` is guaranteed to be in [0, FD_GUI_MAX_PEER_CNT], because
1049 : `peer_cnt` is FD_TEST-ed to be less than or equal FD_GUI_MAX_PEER_CNT.
1050 : For every new peer that is added an existing peer will be removed or was still free.
1051 : And adding a new peer is done at most `peer_cnt` times. */
1052 0 : ulong const * header = (ulong const *)fd_type_pun_const( msg );
1053 0 : ulong peer_cnt = header[ 0 ];
1054 :
1055 0 : FD_TEST( peer_cnt<=FD_GUI_MAX_PEER_CNT );
1056 :
1057 0 : ulong added_cnt = 0UL;
1058 0 : ulong added[ FD_GUI_MAX_PEER_CNT ] = {0};
1059 :
1060 0 : ulong update_cnt = 0UL;
1061 0 : ulong updated[ FD_GUI_MAX_PEER_CNT ] = {0};
1062 :
1063 0 : ulong removed_cnt = 0UL;
1064 0 : fd_pubkey_t removed[ FD_GUI_MAX_PEER_CNT ] = {0};
1065 :
1066 0 : uchar const * data = (uchar const *)(header+1UL);
1067 0 : for( ulong i=0UL; i<gui->gossip.peer_cnt; i++ ) {
1068 0 : int found = 0;
1069 0 : for( ulong j=0UL; j<peer_cnt; j++ ) {
1070 0 : if( FD_UNLIKELY( !memcmp( gui->gossip.peers[ i ].pubkey, data+j*(58UL+12UL*6UL), 32UL ) ) ) {
1071 0 : found = 1;
1072 0 : break;
1073 0 : }
1074 0 : }
1075 :
1076 0 : if( FD_UNLIKELY( !found ) ) {
1077 0 : fd_memcpy( removed[ removed_cnt++ ].uc, gui->gossip.peers[ i ].pubkey->uc, 32UL );
1078 0 : if( FD_LIKELY( i+1UL!=gui->gossip.peer_cnt ) ) {
1079 0 : gui->gossip.peers[ i ] = gui->gossip.peers[ gui->gossip.peer_cnt-1UL ];
1080 0 : i--;
1081 0 : }
1082 0 : gui->gossip.peer_cnt--;
1083 0 : }
1084 0 : }
1085 :
1086 0 : ulong before_peer_cnt = gui->gossip.peer_cnt;
1087 0 : for( ulong i=0UL; i<peer_cnt; i++ ) {
1088 0 : int found = 0;
1089 0 : ulong found_idx = 0;
1090 0 : for( ulong j=0UL; j<gui->gossip.peer_cnt; j++ ) {
1091 0 : if( FD_UNLIKELY( !memcmp( gui->gossip.peers[ j ].pubkey, data+i*(58UL+12UL*6UL), 32UL ) ) ) {
1092 0 : found_idx = j;
1093 0 : found = 1;
1094 0 : break;
1095 0 : }
1096 0 : }
1097 :
1098 0 : if( FD_UNLIKELY( !found ) ) {
1099 0 : fd_memcpy( gui->gossip.peers[ gui->gossip.peer_cnt ].pubkey->uc, data+i*(58UL+12UL*6UL), 32UL );
1100 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].wallclock = *(ulong const *)(data+i*(58UL+12UL*6UL)+32UL);
1101 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].shred_version = *(ushort const *)(data+i*(58UL+12UL*6UL)+40UL);
1102 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].has_version = *(data+i*(58UL+12UL*6UL)+42UL);
1103 0 : if( FD_LIKELY( gui->gossip.peers[ gui->gossip.peer_cnt ].has_version ) ) {
1104 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.major = *(ushort const *)(data+i*(58UL+12UL*6UL)+43UL);
1105 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.minor = *(ushort const *)(data+i*(58UL+12UL*6UL)+45UL);
1106 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.patch = *(ushort const *)(data+i*(58UL+12UL*6UL)+47UL);
1107 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.has_commit = *(data+i*(58UL+12UL*6UL)+49UL);
1108 0 : if( FD_LIKELY( gui->gossip.peers[ gui->gossip.peer_cnt ].version.has_commit ) ) {
1109 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.commit = *(uint const *)(data+i*(58UL+12UL*6UL)+50UL);
1110 0 : }
1111 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].version.feature_set = *(uint const *)(data+i*(58UL+12UL*6UL)+54UL);
1112 0 : }
1113 :
1114 0 : for( ulong j=0UL; j<12UL; j++ ) {
1115 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].sockets[ j ].ipv4 = *(uint const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL);
1116 0 : gui->gossip.peers[ gui->gossip.peer_cnt ].sockets[ j ].port = *(ushort const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL+4UL);
1117 0 : }
1118 :
1119 0 : gui->gossip.peer_cnt++;
1120 0 : } else {
1121 0 : int peer_updated = gui->gossip.peers[ found_idx ].shred_version!=*(ushort const *)(data+i*(58UL+12UL*6UL)+40UL) ||
1122 : // gui->gossip.peers[ found_idx ].wallclock!=*(ulong const *)(data+i*(58UL+12UL*6UL)+32UL) ||
1123 0 : gui->gossip.peers[ found_idx ].has_version!=*(data+i*(58UL+12UL*6UL)+42UL);
1124 :
1125 0 : if( FD_LIKELY( !peer_updated && gui->gossip.peers[ found_idx ].has_version ) ) {
1126 0 : peer_updated = gui->gossip.peers[ found_idx ].version.major!=*(ushort const *)(data+i*(58UL+12UL*6UL)+43UL) ||
1127 0 : gui->gossip.peers[ found_idx ].version.minor!=*(ushort const *)(data+i*(58UL+12UL*6UL)+45UL) ||
1128 0 : gui->gossip.peers[ found_idx ].version.patch!=*(ushort const *)(data+i*(58UL+12UL*6UL)+47UL) ||
1129 0 : gui->gossip.peers[ found_idx ].version.has_commit!=*(data+i*(58UL+12UL*6UL)+49UL) ||
1130 0 : (gui->gossip.peers[ found_idx ].version.has_commit && gui->gossip.peers[ found_idx ].version.commit!=*(uint const *)(data+i*(58UL+12UL*6UL)+50UL)) ||
1131 0 : gui->gossip.peers[ found_idx ].version.feature_set!=*(uint const *)(data+i*(58UL+12UL*6UL)+54UL);
1132 0 : }
1133 :
1134 0 : if( FD_LIKELY( !peer_updated ) ) {
1135 0 : for( ulong j=0UL; j<12UL; j++ ) {
1136 0 : peer_updated = gui->gossip.peers[ found_idx ].sockets[ j ].ipv4!=*(uint const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL) ||
1137 0 : gui->gossip.peers[ found_idx ].sockets[ j ].port!=*(ushort const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL+4UL);
1138 0 : if( FD_LIKELY( peer_updated ) ) break;
1139 0 : }
1140 0 : }
1141 :
1142 0 : if( FD_UNLIKELY( peer_updated ) ) {
1143 0 : updated[ update_cnt++ ] = found_idx;
1144 0 : gui->gossip.peers[ found_idx ].shred_version = *(ushort const *)(data+i*(58UL+12UL*6UL)+40UL);
1145 0 : gui->gossip.peers[ found_idx ].wallclock = *(ulong const *)(data+i*(58UL+12UL*6UL)+32UL);
1146 0 : gui->gossip.peers[ found_idx ].has_version = *(data+i*(58UL+12UL*6UL)+42UL);
1147 0 : if( FD_LIKELY( gui->gossip.peers[ found_idx ].has_version ) ) {
1148 0 : gui->gossip.peers[ found_idx ].version.major = *(ushort const *)(data+i*(58UL+12UL*6UL)+43UL);
1149 0 : gui->gossip.peers[ found_idx ].version.minor = *(ushort const *)(data+i*(58UL+12UL*6UL)+45UL);
1150 0 : gui->gossip.peers[ found_idx ].version.patch = *(ushort const *)(data+i*(58UL+12UL*6UL)+47UL);
1151 0 : gui->gossip.peers[ found_idx ].version.has_commit = *(data+i*(58UL+12UL*6UL)+49UL);
1152 0 : if( FD_LIKELY( gui->gossip.peers[ found_idx ].version.has_commit ) ) {
1153 0 : gui->gossip.peers[ found_idx ].version.commit = *(uint const *)(data+i*(58UL+12UL*6UL)+50UL);
1154 0 : }
1155 0 : gui->gossip.peers[ found_idx ].version.feature_set = *(uint const *)(data+i*(58UL+12UL*6UL)+54UL);
1156 0 : }
1157 :
1158 0 : for( ulong j=0UL; j<12UL; j++ ) {
1159 0 : gui->gossip.peers[ found_idx ].sockets[ j ].ipv4 = *(uint const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL);
1160 0 : gui->gossip.peers[ found_idx ].sockets[ j ].port = *(ushort const *)(data+i*(58UL+12UL*6UL)+58UL+j*6UL+4UL);
1161 0 : }
1162 0 : }
1163 0 : }
1164 0 : }
1165 :
1166 0 : added_cnt = gui->gossip.peer_cnt - before_peer_cnt;
1167 0 : for( ulong i=before_peer_cnt; i<gui->gossip.peer_cnt; i++ ) added[ i-before_peer_cnt ] = i;
1168 :
1169 0 : fd_gui_printf_peers_gossip_update( gui, updated, update_cnt, removed, removed_cnt, added, added_cnt );
1170 0 : fd_http_server_ws_broadcast( gui->http );
1171 0 : }
1172 :
1173 : static void
1174 : fd_gui_handle_vote_account_update( fd_gui_t * gui,
1175 0 : uchar const * msg ) {
1176 : /* See fd_gui_handle_gossip_update for why `gui->vote_account.vote_account_cnt`
1177 : is guaranteed to be in [0, FD_GUI_MAX_PEER_CNT]. */
1178 0 : ulong const * header = (ulong const *)fd_type_pun_const( msg );
1179 0 : ulong peer_cnt = header[ 0 ];
1180 :
1181 0 : FD_TEST( peer_cnt<=FD_GUI_MAX_PEER_CNT );
1182 :
1183 0 : ulong added_cnt = 0UL;
1184 0 : ulong added[ FD_GUI_MAX_PEER_CNT ] = {0};
1185 :
1186 0 : ulong update_cnt = 0UL;
1187 0 : ulong updated[ FD_GUI_MAX_PEER_CNT ] = {0};
1188 :
1189 0 : ulong removed_cnt = 0UL;
1190 0 : fd_pubkey_t removed[ FD_GUI_MAX_PEER_CNT ] = {0};
1191 :
1192 0 : uchar const * data = (uchar const *)(header+1UL);
1193 0 : for( ulong i=0UL; i<gui->vote_account.vote_account_cnt; i++ ) {
1194 0 : int found = 0;
1195 0 : for( ulong j=0UL; j<peer_cnt; j++ ) {
1196 0 : if( FD_UNLIKELY( !memcmp( gui->vote_account.vote_accounts[ i ].vote_account, data+j*112UL, 32UL ) ) ) {
1197 0 : found = 1;
1198 0 : break;
1199 0 : }
1200 0 : }
1201 :
1202 0 : if( FD_UNLIKELY( !found ) ) {
1203 0 : fd_memcpy( removed[ removed_cnt++ ].uc, gui->vote_account.vote_accounts[ i ].vote_account->uc, 32UL );
1204 0 : if( FD_LIKELY( i+1UL!=gui->vote_account.vote_account_cnt ) ) {
1205 0 : gui->vote_account.vote_accounts[ i ] = gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt-1UL ];
1206 0 : i--;
1207 0 : }
1208 0 : gui->vote_account.vote_account_cnt--;
1209 0 : }
1210 0 : }
1211 :
1212 0 : ulong before_peer_cnt = gui->vote_account.vote_account_cnt;
1213 0 : for( ulong i=0UL; i<peer_cnt; i++ ) {
1214 0 : int found = 0;
1215 0 : ulong found_idx;
1216 0 : for( ulong j=0UL; j<gui->vote_account.vote_account_cnt; j++ ) {
1217 0 : if( FD_UNLIKELY( !memcmp( gui->vote_account.vote_accounts[ j ].vote_account, data+i*112UL, 32UL ) ) ) {
1218 0 : found_idx = j;
1219 0 : found = 1;
1220 0 : break;
1221 0 : }
1222 0 : }
1223 :
1224 0 : if( FD_UNLIKELY( !found ) ) {
1225 0 : fd_memcpy( gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].vote_account->uc, data+i*112UL, 32UL );
1226 0 : fd_memcpy( gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].pubkey->uc, data+i*112UL+32UL, 32UL );
1227 :
1228 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].activated_stake = *(ulong const *)(data+i*112UL+64UL);
1229 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].last_vote = *(ulong const *)(data+i*112UL+72UL);
1230 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].root_slot = *(ulong const *)(data+i*112UL+80UL);
1231 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].epoch_credits = *(ulong const *)(data+i*112UL+88UL);
1232 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].commission = *(data+i*112UL+96UL);
1233 0 : gui->vote_account.vote_accounts[ gui->vote_account.vote_account_cnt ].delinquent = *(data+i*112UL+97UL);
1234 :
1235 0 : gui->vote_account.vote_account_cnt++;
1236 0 : } else {
1237 0 : int peer_updated =
1238 0 : memcmp( gui->vote_account.vote_accounts[ found_idx ].pubkey->uc, data+i*112UL+32UL, 32UL ) ||
1239 0 : gui->vote_account.vote_accounts[ found_idx ].activated_stake != *(ulong const *)(data+i*112UL+64UL) ||
1240 : // gui->vote_account.vote_accounts[ found_idx ].last_vote != *(ulong const *)(data+i*112UL+72UL) ||
1241 : // gui->vote_account.vote_accounts[ found_idx ].root_slot != *(ulong const *)(data+i*112UL+80UL) ||
1242 : // gui->vote_account.vote_accounts[ found_idx ].epoch_credits != *(ulong const *)(data+i*112UL+88UL) ||
1243 0 : gui->vote_account.vote_accounts[ found_idx ].commission != *(data+i*112UL+96UL) ||
1244 0 : gui->vote_account.vote_accounts[ found_idx ].delinquent != *(data+i*112UL+97UL);
1245 :
1246 0 : if( FD_UNLIKELY( peer_updated ) ) {
1247 0 : updated[ update_cnt++ ] = found_idx;
1248 :
1249 0 : fd_memcpy( gui->vote_account.vote_accounts[ found_idx ].pubkey->uc, data+i*112UL+32UL, 32UL );
1250 0 : gui->vote_account.vote_accounts[ found_idx ].activated_stake = *(ulong const *)(data+i*112UL+64UL);
1251 0 : gui->vote_account.vote_accounts[ found_idx ].last_vote = *(ulong const *)(data+i*112UL+72UL);
1252 0 : gui->vote_account.vote_accounts[ found_idx ].root_slot = *(ulong const *)(data+i*112UL+80UL);
1253 0 : gui->vote_account.vote_accounts[ found_idx ].epoch_credits = *(ulong const *)(data+i*112UL+88UL);
1254 0 : gui->vote_account.vote_accounts[ found_idx ].commission = *(data+i*112UL+96UL);
1255 0 : gui->vote_account.vote_accounts[ found_idx ].delinquent = *(data+i*112UL+97UL);
1256 0 : }
1257 0 : }
1258 0 : }
1259 :
1260 0 : added_cnt = gui->vote_account.vote_account_cnt - before_peer_cnt;
1261 0 : for( ulong i=before_peer_cnt; i<gui->vote_account.vote_account_cnt; i++ ) added[ i-before_peer_cnt ] = i;
1262 :
1263 0 : fd_gui_printf_peers_vote_account_update( gui, updated, update_cnt, removed, removed_cnt, added, added_cnt );
1264 0 : fd_http_server_ws_broadcast( gui->http );
1265 0 : }
1266 :
1267 : static void
1268 : fd_gui_handle_validator_info_update( fd_gui_t * gui,
1269 0 : uchar const * msg ) {
1270 0 : if( FD_UNLIKELY( gui->validator_info.info_cnt == FD_GUI_MAX_PEER_CNT ) ) {
1271 0 : FD_LOG_DEBUG(("validator info cnt exceeds 40200 %lu, ignoring additional entries", gui->validator_info.info_cnt ));
1272 0 : return;
1273 0 : }
1274 0 : uchar const * data = (uchar const *)fd_type_pun_const( msg );
1275 :
1276 0 : ulong added_cnt = 0UL;
1277 0 : ulong added[ 1 ] = {0};
1278 :
1279 0 : ulong update_cnt = 0UL;
1280 0 : ulong updated[ 1 ] = {0};
1281 :
1282 0 : ulong removed_cnt = 0UL;
1283 : /* Unlike gossip or vote account updates, validator info messages come
1284 : in as info is discovered, and may contain as little as 1 validator
1285 : per message. Therefore, it doesn't make sense to use the remove
1286 : mechanism. */
1287 :
1288 0 : ulong before_peer_cnt = gui->validator_info.info_cnt;
1289 0 : int found = 0;
1290 0 : ulong found_idx;
1291 0 : for( ulong j=0UL; j<gui->validator_info.info_cnt; j++ ) {
1292 0 : if( FD_UNLIKELY( !memcmp( gui->validator_info.info[ j ].pubkey, data, 32UL ) ) ) {
1293 0 : found_idx = j;
1294 0 : found = 1;
1295 0 : break;
1296 0 : }
1297 0 : }
1298 :
1299 0 : if( FD_UNLIKELY( !found ) ) {
1300 0 : fd_memcpy( gui->validator_info.info[ gui->validator_info.info_cnt ].pubkey->uc, data, 32UL );
1301 :
1302 0 : strncpy( gui->validator_info.info[ gui->validator_info.info_cnt ].name, (char const *)(data+32UL), 64 );
1303 0 : gui->validator_info.info[ gui->validator_info.info_cnt ].name[ 63 ] = '\0';
1304 :
1305 0 : strncpy( gui->validator_info.info[ gui->validator_info.info_cnt ].website, (char const *)(data+96UL), 128 );
1306 0 : gui->validator_info.info[ gui->validator_info.info_cnt ].website[ 127 ] = '\0';
1307 :
1308 0 : strncpy( gui->validator_info.info[ gui->validator_info.info_cnt ].details, (char const *)(data+224UL), 256 );
1309 0 : gui->validator_info.info[ gui->validator_info.info_cnt ].details[ 255 ] = '\0';
1310 :
1311 0 : strncpy( gui->validator_info.info[ gui->validator_info.info_cnt ].icon_uri, (char const *)(data+480UL), 128 );
1312 0 : gui->validator_info.info[ gui->validator_info.info_cnt ].icon_uri[ 127 ] = '\0';
1313 :
1314 0 : gui->validator_info.info_cnt++;
1315 0 : } else {
1316 0 : int peer_updated =
1317 0 : memcmp( gui->validator_info.info[ found_idx ].pubkey->uc, data, 32UL ) ||
1318 0 : strncmp( gui->validator_info.info[ found_idx ].name, (char const *)(data+32UL), 64 ) ||
1319 0 : strncmp( gui->validator_info.info[ found_idx ].website, (char const *)(data+96UL), 128 ) ||
1320 0 : strncmp( gui->validator_info.info[ found_idx ].details, (char const *)(data+224UL), 256 ) ||
1321 0 : strncmp( gui->validator_info.info[ found_idx ].icon_uri, (char const *)(data+480UL), 128 );
1322 :
1323 0 : if( FD_UNLIKELY( peer_updated ) ) {
1324 0 : updated[ update_cnt++ ] = found_idx;
1325 :
1326 0 : fd_memcpy( gui->validator_info.info[ found_idx ].pubkey->uc, data, 32UL );
1327 :
1328 0 : strncpy( gui->validator_info.info[ found_idx ].name, (char const *)(data+32UL), 64 );
1329 0 : gui->validator_info.info[ found_idx ].name[ 63 ] = '\0';
1330 :
1331 0 : strncpy( gui->validator_info.info[ found_idx ].website, (char const *)(data+96UL), 128 );
1332 0 : gui->validator_info.info[ found_idx ].website[ 127 ] = '\0';
1333 :
1334 0 : strncpy( gui->validator_info.info[ found_idx ].details, (char const *)(data+224UL), 256 );
1335 0 : gui->validator_info.info[ found_idx ].details[ 255 ] = '\0';
1336 :
1337 0 : strncpy( gui->validator_info.info[ found_idx ].icon_uri, (char const *)(data+480UL), 128 );
1338 0 : gui->validator_info.info[ found_idx ].icon_uri[ 127 ] = '\0';
1339 0 : }
1340 0 : }
1341 :
1342 0 : added_cnt = gui->validator_info.info_cnt - before_peer_cnt;
1343 0 : for( ulong i=before_peer_cnt; i<gui->validator_info.info_cnt; i++ ) added[ i-before_peer_cnt ] = i;
1344 :
1345 0 : fd_gui_printf_peers_validator_info_update( gui, updated, update_cnt, NULL, removed_cnt, added, added_cnt );
1346 0 : fd_http_server_ws_broadcast( gui->http );
1347 0 : }
1348 :
1349 : int
1350 : fd_gui_request_slot( fd_gui_t * gui,
1351 : ulong ws_conn_id,
1352 : ulong request_id,
1353 0 : cJSON const * params ) {
1354 0 : const cJSON * slot_param = cJSON_GetObjectItemCaseSensitive( params, "slot" );
1355 0 : if( FD_UNLIKELY( !cJSON_IsNumber( slot_param ) ) ) return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1356 :
1357 0 : ulong _slot = slot_param->valueulong;
1358 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, _slot );
1359 0 : if( FD_UNLIKELY( !slot ) ) {
1360 0 : fd_gui_printf_null_query_response( gui->http, "slot", "query", request_id );
1361 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1362 0 : return 0;
1363 0 : }
1364 :
1365 0 : fd_gui_printf_slot_request( gui, _slot, request_id );
1366 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1367 0 : return 0;
1368 0 : }
1369 :
1370 : int
1371 : fd_gui_request_slot_transactions( fd_gui_t * gui,
1372 : ulong ws_conn_id,
1373 : ulong request_id,
1374 0 : cJSON const * params ) {
1375 0 : const cJSON * slot_param = cJSON_GetObjectItemCaseSensitive( params, "slot" );
1376 0 : if( FD_UNLIKELY( !cJSON_IsNumber( slot_param ) ) ) return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1377 :
1378 0 : ulong _slot = slot_param->valueulong;
1379 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, _slot );
1380 0 : if( FD_UNLIKELY( !slot ) ) {
1381 0 : fd_gui_printf_null_query_response( gui->http, "slot", "query", request_id );
1382 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1383 0 : return 0;
1384 0 : }
1385 :
1386 0 : fd_gui_printf_slot_transactions_request( gui, _slot, request_id );
1387 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1388 0 : return 0;
1389 0 : }
1390 :
1391 : int
1392 : fd_gui_request_slot_detailed( fd_gui_t * gui,
1393 : ulong ws_conn_id,
1394 : ulong request_id,
1395 0 : cJSON const * params ) {
1396 0 : const cJSON * slot_param = cJSON_GetObjectItemCaseSensitive( params, "slot" );
1397 0 : if( FD_UNLIKELY( !cJSON_IsNumber( slot_param ) ) ) return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1398 :
1399 0 : ulong _slot = slot_param->valueulong;
1400 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, _slot );
1401 0 : if( FD_UNLIKELY( !slot ) ) {
1402 0 : fd_gui_printf_null_query_response( gui->http, "slot", "query", request_id );
1403 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1404 0 : return 0;
1405 0 : }
1406 :
1407 0 : fd_gui_printf_slot_request_detailed( gui, _slot, request_id );
1408 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1409 0 : return 0;
1410 0 : }
1411 :
1412 : static inline ulong
1413 0 : fd_gui_slot_duration( fd_gui_t const * gui, fd_gui_slot_t const * cur ) {
1414 0 : fd_gui_slot_t const * prev = fd_gui_get_slot_const( gui, cur->slot-1UL );
1415 0 : if( FD_UNLIKELY( !prev ||
1416 0 : prev->skipped ||
1417 0 : prev->completed_time == LONG_MAX ||
1418 0 : prev->slot != (cur->slot - 1UL) ||
1419 0 : cur->skipped ||
1420 0 : cur->completed_time == LONG_MAX ) ) return ULONG_MAX;
1421 :
1422 0 : return (ulong)(cur->completed_time - prev->completed_time);
1423 0 : }
1424 :
1425 : /* All rankings are initialized / reset to ULONG_MAX. These sentinels
1426 : sort AFTER non-sentinel ranking entries. Equal slots are sorted by
1427 : oldest slot AFTER. Otherwise sort by value according to ranking
1428 : type. */
1429 : #define SORT_NAME fd_gui_slot_ranking_sort
1430 0 : #define SORT_KEY_T fd_gui_slot_ranking_t
1431 0 : #define SORT_BEFORE(a,b) fd_int_if( (a).slot==ULONG_MAX, 0, fd_int_if( (b).slot==ULONG_MAX, 1, fd_int_if( (a).value==(b).value, (a).slot>(b).slot, fd_int_if( (a).type==FD_GUI_SLOT_RANKING_TYPE_DESC, (a).value>(b).value, (a).value<(b).value ) ) ) )
1432 : #include "../../util/tmpl/fd_sort.c"
1433 :
1434 : static inline void
1435 : fd_gui_try_insert_ranking( fd_gui_t * gui,
1436 : fd_gui_slot_rankings_t * rankings,
1437 0 : fd_gui_slot_t const * slot ) {
1438 : /* Rankings are inserted into an extra slot at the end of the ranking
1439 : array, then the array is sorted. */
1440 0 : #define TRY_INSERT_SLOT( ranking_name, ranking_slot, ranking_value ) \
1441 0 : do { \
1442 0 : rankings->FD_CONCAT2(largest_, ranking_name) [ FD_GUI_SLOT_RANKINGS_SZ ] = (fd_gui_slot_ranking_t){ .slot = (ranking_slot), .value = (ranking_value), .type = FD_GUI_SLOT_RANKING_TYPE_DESC }; \
1443 0 : fd_gui_slot_ranking_sort_insert( rankings->FD_CONCAT2(largest_, ranking_name), FD_GUI_SLOT_RANKINGS_SZ+1UL ); \
1444 0 : rankings->FD_CONCAT2(smallest_, ranking_name)[ FD_GUI_SLOT_RANKINGS_SZ ] = (fd_gui_slot_ranking_t){ .slot = (ranking_slot), .value = (ranking_value), .type = FD_GUI_SLOT_RANKING_TYPE_ASC }; \
1445 0 : fd_gui_slot_ranking_sort_insert( rankings->FD_CONCAT2(smallest_, ranking_name), FD_GUI_SLOT_RANKINGS_SZ+1UL ); \
1446 0 : } while (0)
1447 :
1448 0 : if( slot->skipped ) {
1449 0 : TRY_INSERT_SLOT( skipped, slot->slot, slot->slot );
1450 0 : return;
1451 0 : }
1452 :
1453 0 : ulong dur = fd_gui_slot_duration( gui, slot );
1454 0 : if( FD_LIKELY( dur!=ULONG_MAX ) ) TRY_INSERT_SLOT( duration, slot->slot, dur );
1455 0 : TRY_INSERT_SLOT( tips, slot->slot, slot->tips );
1456 0 : TRY_INSERT_SLOT( fees, slot->slot, slot->priority_fee + slot->transaction_fee );
1457 0 : TRY_INSERT_SLOT( rewards, slot->slot, slot->tips + slot->priority_fee + slot->transaction_fee );
1458 0 : TRY_INSERT_SLOT( rewards_per_cu, slot->slot, slot->compute_units==0UL ? 0UL : (slot->tips + slot->priority_fee + slot->transaction_fee) / slot->compute_units );
1459 0 : TRY_INSERT_SLOT( compute_units, slot->slot, slot->compute_units );
1460 0 : #undef TRY_INSERT_SLOT
1461 0 : }
1462 :
1463 : static inline ulong
1464 0 : fd_gui_current_epoch_idx( fd_gui_t * gui ) {
1465 0 : ulong epoch_idx = ULONG_MAX;
1466 0 : ulong epoch = ULONG_MAX;
1467 0 : for( ulong i = 0UL; i<2UL; i++ ) {
1468 0 : if( FD_LIKELY( gui->epoch.has_epoch[ i ] ) ) {
1469 : /* the "current" epoch is the smallest */
1470 0 : if( FD_LIKELY( gui->epoch.epochs[ i ].epoch<epoch ) ) {
1471 0 : epoch = gui->epoch.epochs[ i ].epoch;
1472 0 : epoch_idx = i;
1473 0 : }
1474 0 : }
1475 0 : }
1476 0 : return epoch_idx;
1477 0 : }
1478 :
1479 : static void
1480 0 : fd_gui_update_slot_rankings( fd_gui_t * gui ) {
1481 0 : ulong first_replay_slot = ULONG_MAX;
1482 0 : if( FD_LIKELY( gui->summary.is_full_client ) ) {
1483 0 : ulong slot_caught_up = gui->summary.slot_caught_up;
1484 0 : ulong slot_incremental = gui->summary.boot_progress.loading_snapshot[ FD_GUI_BOOT_PROGRESS_INCREMENTAL_SNAPSHOT_IDX ].slot;
1485 0 : ulong slot_full = gui->summary.boot_progress.loading_snapshot[ FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX ].slot;
1486 0 : first_replay_slot = fd_ulong_if( slot_caught_up!=ULONG_MAX, fd_ulong_if( slot_incremental!=ULONG_MAX, slot_incremental+1UL, fd_ulong_if( slot_full!=ULONG_MAX, slot_full+1UL, ULONG_MAX ) ), ULONG_MAX );
1487 0 : } else {
1488 0 : first_replay_slot = gui->summary.startup_progress.startup_ledger_max_slot;
1489 0 : }
1490 0 : if( FD_UNLIKELY( first_replay_slot==ULONG_MAX ) ) return;
1491 0 : if( FD_UNLIKELY( gui->summary.slot_rooted ==ULONG_MAX ) ) return;
1492 :
1493 0 : ulong epoch_idx = fd_gui_current_epoch_idx( gui );
1494 0 : if( FD_UNLIKELY( epoch_idx==ULONG_MAX ) ) return;
1495 :
1496 : /* No new slots since the last update */
1497 0 : if( FD_UNLIKELY( gui->epoch.epochs[ epoch_idx ].rankings_slot>gui->summary.slot_rooted ) ) return;
1498 :
1499 : /* Slots before first_replay_slot are unavailable. */
1500 0 : gui->epoch.epochs[ epoch_idx ].rankings_slot = fd_ulong_max( gui->epoch.epochs[ epoch_idx ].rankings_slot, first_replay_slot );
1501 :
1502 : /* Update the rankings. Only look through slots we haven't already. */
1503 0 : for( ulong s = gui->summary.slot_rooted; s>=gui->epoch.epochs[ epoch_idx ].rankings_slot; s--) {
1504 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, s );
1505 0 : if( FD_UNLIKELY( !slot ) ) break;
1506 :
1507 0 : fd_gui_try_insert_ranking( gui, gui->epoch.epochs[ epoch_idx ].rankings, slot );
1508 0 : if( FD_UNLIKELY( slot->mine ) ) fd_gui_try_insert_ranking( gui, gui->epoch.epochs[ epoch_idx ].my_rankings, slot );
1509 0 : }
1510 :
1511 0 : gui->epoch.epochs[ epoch_idx ].rankings_slot = gui->summary.slot_rooted + 1UL;
1512 0 : }
1513 :
1514 : int
1515 : fd_gui_request_slot_rankings( fd_gui_t * gui,
1516 : ulong ws_conn_id,
1517 : ulong request_id,
1518 0 : cJSON const * params ) {
1519 0 : const cJSON * slot_param = cJSON_GetObjectItemCaseSensitive( params, "mine" );
1520 0 : if( FD_UNLIKELY( !cJSON_IsBool( slot_param ) ) ) return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1521 :
1522 0 : int mine = !!(slot_param->type & cJSON_True);
1523 0 : fd_gui_update_slot_rankings( gui );
1524 0 : fd_gui_printf_slot_rankings_request( gui, request_id, mine );
1525 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1526 0 : return 0;
1527 0 : }
1528 :
1529 : int
1530 : fd_gui_request_slot_shreds( fd_gui_t * gui,
1531 : ulong ws_conn_id,
1532 : ulong request_id,
1533 0 : cJSON const * params ) {
1534 0 : const cJSON * slot_param = cJSON_GetObjectItemCaseSensitive( params, "slot" );
1535 0 : if( FD_UNLIKELY( !cJSON_IsNumber( slot_param ) ) ) return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1536 :
1537 0 : ulong _slot = slot_param->valueulong;
1538 :
1539 0 : fd_gui_slot_t const * slot = fd_gui_get_slot( gui, _slot );
1540 0 : if( FD_UNLIKELY( !slot || gui->shreds.history_tail > slot->shreds.end_offset + FD_GUI_SHREDS_HISTORY_SZ ) ) {
1541 0 : fd_gui_printf_null_query_response( gui->http, "slot", "query_shreds", request_id );
1542 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1543 0 : return 0;
1544 0 : }
1545 :
1546 0 : fd_gui_printf_slot_query_shreds( gui, _slot, request_id );
1547 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1548 0 : return 0;
1549 0 : }
1550 :
1551 : int
1552 : fd_gui_ws_message( fd_gui_t * gui,
1553 : ulong ws_conn_id,
1554 : uchar const * data,
1555 0 : ulong data_len ) {
1556 : /* TODO: cJSON allocates, might fail SIGSYS due to brk(2)...
1557 : switch off this (or use wksp allocator) */
1558 0 : const char * parse_end;
1559 0 : cJSON * json = cJSON_ParseWithLengthOpts( (char *)data, data_len, &parse_end, 0 );
1560 0 : if( FD_UNLIKELY( !json ) ) {
1561 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1562 0 : }
1563 :
1564 0 : const cJSON * node = cJSON_GetObjectItemCaseSensitive( json, "id" );
1565 0 : if( FD_UNLIKELY( !cJSON_IsNumber( node ) ) ) {
1566 0 : cJSON_Delete( json );
1567 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1568 0 : }
1569 0 : ulong id = node->valueulong;
1570 :
1571 0 : const cJSON * topic = cJSON_GetObjectItemCaseSensitive( json, "topic" );
1572 0 : if( FD_UNLIKELY( !cJSON_IsString( topic ) || topic->valuestring==NULL ) ) {
1573 0 : cJSON_Delete( json );
1574 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1575 0 : }
1576 :
1577 0 : const cJSON * key = cJSON_GetObjectItemCaseSensitive( json, "key" );
1578 0 : if( FD_UNLIKELY( !cJSON_IsString( key ) || key->valuestring==NULL ) ) {
1579 0 : cJSON_Delete( json );
1580 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1581 0 : }
1582 :
1583 0 : if( FD_LIKELY( !strcmp( topic->valuestring, "slot" ) && !strcmp( key->valuestring, "query" ) ) ) {
1584 0 : const cJSON * params = cJSON_GetObjectItemCaseSensitive( json, "params" );
1585 0 : if( FD_UNLIKELY( !cJSON_IsObject( params ) ) ) {
1586 0 : cJSON_Delete( json );
1587 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1588 0 : }
1589 :
1590 0 : int result = fd_gui_request_slot( gui, ws_conn_id, id, params );
1591 0 : cJSON_Delete( json );
1592 0 : return result;
1593 0 : } else if( FD_LIKELY( !strcmp( topic->valuestring, "slot" ) && !strcmp( key->valuestring, "query_detailed" ) ) ) {
1594 0 : const cJSON * params = cJSON_GetObjectItemCaseSensitive( json, "params" );
1595 0 : if( FD_UNLIKELY( !cJSON_IsObject( params ) ) ) {
1596 0 : cJSON_Delete( json );
1597 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1598 0 : }
1599 :
1600 0 : int result = fd_gui_request_slot_detailed( gui, ws_conn_id, id, params );
1601 0 : cJSON_Delete( json );
1602 0 : return result;
1603 0 : } else if( FD_LIKELY( !strcmp( topic->valuestring, "slot" ) && !strcmp( key->valuestring, "query_transactions" ) ) ) {
1604 0 : const cJSON * params = cJSON_GetObjectItemCaseSensitive( json, "params" );
1605 0 : if( FD_UNLIKELY( !cJSON_IsObject( params ) ) ) {
1606 0 : cJSON_Delete( json );
1607 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1608 0 : }
1609 :
1610 0 : int result = fd_gui_request_slot_transactions( gui, ws_conn_id, id, params );
1611 0 : cJSON_Delete( json );
1612 0 : return result;
1613 0 : } else if( FD_LIKELY( !strcmp( topic->valuestring, "slot" ) && !strcmp( key->valuestring, "query_rankings" ) ) ) {
1614 0 : const cJSON * params = cJSON_GetObjectItemCaseSensitive( json, "params" );
1615 0 : if( FD_UNLIKELY( !cJSON_IsObject( params ) ) ) {
1616 0 : cJSON_Delete( json );
1617 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_BAD_REQUEST;
1618 0 : }
1619 :
1620 0 : int result = fd_gui_request_slot_rankings( gui, ws_conn_id, id, params );
1621 0 : cJSON_Delete( json );
1622 0 : return result;
1623 0 : } else if( FD_LIKELY( !strcmp( topic->valuestring, "summary" ) && !strcmp( key->valuestring, "ping" ) ) ) {
1624 0 : fd_gui_printf_summary_ping( gui, id );
1625 0 : FD_TEST( !fd_http_server_ws_send( gui->http, ws_conn_id ) );
1626 :
1627 0 : cJSON_Delete( json );
1628 0 : return 0;
1629 0 : }
1630 :
1631 0 : cJSON_Delete( json );
1632 0 : return FD_HTTP_SERVER_CONNECTION_CLOSE_UNKNOWN_METHOD;
1633 0 : }
1634 :
1635 : static fd_gui_slot_t *
1636 : fd_gui_clear_slot( fd_gui_t * gui,
1637 : ulong _slot,
1638 0 : ulong _parent_slot ) {
1639 0 : fd_gui_slot_t * slot = gui->slots[ _slot % FD_GUI_SLOTS_CNT ];
1640 :
1641 0 : int mine = 0;
1642 0 : ulong epoch_idx = 0UL;
1643 0 : for( ulong i=0UL; i<2UL; i++) {
1644 0 : if( FD_UNLIKELY( !gui->epoch.has_epoch[ i ] ) ) continue;
1645 0 : if( FD_LIKELY( _slot>=gui->epoch.epochs[ i ].start_slot && _slot<=gui->epoch.epochs[ i ].end_slot ) ) {
1646 0 : fd_pubkey_t const * slot_leader = fd_epoch_leaders_get( gui->epoch.epochs[ i ].lsched, _slot );
1647 0 : mine = !memcmp( slot_leader->uc, gui->summary.identity_key->uc, 32UL );
1648 0 : epoch_idx = i;
1649 0 : break;
1650 0 : }
1651 0 : }
1652 :
1653 0 : slot->slot = _slot;
1654 0 : slot->parent_slot = _parent_slot;
1655 0 : slot->vote_slot = ULONG_MAX;
1656 0 : slot->vote_latency = UCHAR_MAX;
1657 0 : slot->reset_slot = ULONG_MAX;
1658 0 : slot->max_compute_units = UINT_MAX;
1659 0 : slot->completed_time = LONG_MAX;
1660 0 : slot->mine = mine;
1661 0 : slot->skipped = 0;
1662 0 : slot->must_republish = 1;
1663 0 : slot->level = FD_GUI_SLOT_LEVEL_INCOMPLETE;
1664 0 : slot->total_txn_cnt = UINT_MAX;
1665 0 : slot->vote_txn_cnt = UINT_MAX;
1666 0 : slot->failed_txn_cnt = UINT_MAX;
1667 0 : slot->nonvote_failed_txn_cnt = UINT_MAX;
1668 0 : slot->compute_units = UINT_MAX;
1669 0 : slot->transaction_fee = ULONG_MAX;
1670 0 : slot->priority_fee = ULONG_MAX;
1671 0 : slot->tips = ULONG_MAX;
1672 0 : slot->shred_cnt = UINT_MAX;
1673 0 : slot->shreds.start_offset = ULONG_MAX;
1674 0 : slot->shreds.end_offset = ULONG_MAX;
1675 :
1676 0 : if( FD_LIKELY( slot->mine ) ) {
1677 : /* All slots start off not skipped, until we see it get off the reset
1678 : chain. */
1679 0 : gui->epoch.epochs[ epoch_idx ].my_total_slots++;
1680 :
1681 0 : slot->leader_history_idx = gui->leader_slots_cnt++;
1682 0 : fd_gui_leader_slot_t * lslot = gui->leader_slots[ slot->leader_history_idx % FD_GUI_LEADER_CNT ];
1683 :
1684 0 : lslot->slot = _slot;
1685 0 : memset( lslot->block_hash.uc, 0, sizeof(fd_hash_t) );
1686 0 : lslot->leader_start_time = LONG_MAX;
1687 0 : lslot->leader_end_time = LONG_MAX;
1688 0 : lslot->tile_timers_sample_cnt = 0UL;
1689 0 : lslot->scheduler_counts_sample_cnt = 0UL;
1690 0 : lslot->txs.microblocks_upper_bound = USHORT_MAX;
1691 0 : lslot->txs.begin_microblocks = 0U;
1692 0 : lslot->txs.end_microblocks = 0U;
1693 0 : lslot->txs.start_offset = ULONG_MAX;
1694 0 : lslot->txs.end_offset = ULONG_MAX;
1695 0 : lslot->unbecame_leader = 0;
1696 0 : }
1697 :
1698 0 : if( FD_UNLIKELY( !_slot ) ) {
1699 : /* Slot 0 is always rooted */
1700 0 : slot->level = FD_GUI_SLOT_LEVEL_ROOTED;
1701 0 : }
1702 :
1703 0 : return slot;
1704 0 : }
1705 :
1706 : void
1707 : fd_gui_handle_leader_schedule( fd_gui_t * gui,
1708 : fd_stake_weight_msg_t const * leader_schedule,
1709 0 : long now ) {
1710 0 : FD_TEST( leader_schedule->staked_cnt<=MAX_STAKED_LEADERS );
1711 0 : FD_TEST( leader_schedule->slot_cnt<=MAX_SLOTS_PER_EPOCH );
1712 :
1713 0 : ulong idx = leader_schedule->epoch % 2UL;
1714 0 : gui->epoch.has_epoch[ idx ] = 1;
1715 :
1716 0 : gui->epoch.epochs[ idx ].epoch = leader_schedule->epoch;
1717 0 : gui->epoch.epochs[ idx ].start_slot = leader_schedule->start_slot;
1718 0 : gui->epoch.epochs[ idx ].end_slot = leader_schedule->start_slot + leader_schedule->slot_cnt - 1; // end_slot is inclusive.
1719 0 : gui->epoch.epochs[ idx ].excluded_stake = leader_schedule->excluded_stake;
1720 0 : gui->epoch.epochs[ idx ].my_total_slots = 0UL;
1721 0 : gui->epoch.epochs[ idx ].my_skipped_slots = 0UL;
1722 :
1723 0 : memset( gui->epoch.epochs[ idx ].rankings, (int)(UINT_MAX), sizeof(gui->epoch.epochs[ idx ].rankings) );
1724 0 : memset( gui->epoch.epochs[ idx ].my_rankings, (int)(UINT_MAX), sizeof(gui->epoch.epochs[ idx ].my_rankings) );
1725 :
1726 0 : gui->epoch.epochs[ idx ].rankings_slot = leader_schedule->start_slot;
1727 :
1728 0 : fd_vote_stake_weight_t const * stake_weights = leader_schedule->weights;
1729 0 : fd_memcpy( gui->epoch.epochs[ idx ].stakes, stake_weights, leader_schedule->staked_cnt*sizeof(fd_vote_stake_weight_t) );
1730 :
1731 0 : fd_epoch_leaders_delete( fd_epoch_leaders_leave( gui->epoch.epochs[ idx ].lsched ) );
1732 0 : gui->epoch.epochs[idx].lsched = fd_epoch_leaders_join( fd_epoch_leaders_new( gui->epoch.epochs[ idx ]._lsched,
1733 0 : leader_schedule->epoch,
1734 0 : gui->epoch.epochs[ idx ].start_slot,
1735 0 : leader_schedule->slot_cnt,
1736 0 : leader_schedule->staked_cnt,
1737 0 : gui->epoch.epochs[ idx ].stakes,
1738 0 : leader_schedule->excluded_stake,
1739 0 : leader_schedule->vote_keyed_lsched ) );
1740 :
1741 0 : if( FD_UNLIKELY( leader_schedule->start_slot==0UL ) ) {
1742 0 : gui->epoch.epochs[ 0 ].start_time = now;
1743 0 : } else {
1744 0 : gui->epoch.epochs[ idx ].start_time = LONG_MAX;
1745 :
1746 0 : for( ulong i=0UL; i<fd_ulong_min( leader_schedule->start_slot-1UL, FD_GUI_SLOTS_CNT ); i++ ) {
1747 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, leader_schedule->start_slot-i );
1748 0 : if( FD_UNLIKELY( !slot ) ) break;
1749 0 : else if( FD_UNLIKELY( slot->skipped ) ) continue;
1750 :
1751 0 : gui->epoch.epochs[ idx ].start_time = slot->completed_time;
1752 0 : break;
1753 0 : }
1754 0 : }
1755 :
1756 0 : fd_gui_printf_epoch( gui, idx );
1757 0 : fd_http_server_ws_broadcast( gui->http );
1758 0 : }
1759 :
1760 : void
1761 : fd_gui_handle_epoch_info( fd_gui_t * gui,
1762 : fd_epoch_info_msg_t const * epoch_info,
1763 0 : long now ) {
1764 0 : FD_TEST( epoch_info->staked_cnt<=MAX_STAKED_LEADERS );
1765 0 : FD_TEST( epoch_info->slot_cnt<=MAX_SLOTS_PER_EPOCH );
1766 :
1767 0 : ulong idx = epoch_info->epoch % 2UL;
1768 0 : gui->epoch.has_epoch[ idx ] = 1;
1769 :
1770 0 : gui->epoch.epochs[ idx ].epoch = epoch_info->epoch;
1771 0 : gui->epoch.epochs[ idx ].start_slot = epoch_info->start_slot;
1772 0 : gui->epoch.epochs[ idx ].end_slot = epoch_info->start_slot + epoch_info->slot_cnt - 1; // end_slot is inclusive.
1773 0 : gui->epoch.epochs[ idx ].excluded_stake = epoch_info->excluded_stake;
1774 0 : gui->epoch.epochs[ idx ].my_total_slots = 0UL;
1775 0 : gui->epoch.epochs[ idx ].my_skipped_slots = 0UL;
1776 :
1777 0 : memset( gui->epoch.epochs[ idx ].rankings, (int)(UINT_MAX), sizeof(gui->epoch.epochs[ idx ].rankings) );
1778 0 : memset( gui->epoch.epochs[ idx ].my_rankings, (int)(UINT_MAX), sizeof(gui->epoch.epochs[ idx ].my_rankings) );
1779 :
1780 0 : gui->epoch.epochs[ idx ].rankings_slot = epoch_info->start_slot;
1781 :
1782 0 : fd_vote_stake_weight_t const * stake_weights = epoch_info->weights;
1783 0 : fd_memcpy( gui->epoch.epochs[ idx ].stakes, stake_weights, epoch_info->staked_cnt*sizeof(fd_vote_stake_weight_t) );
1784 :
1785 0 : fd_epoch_leaders_delete( fd_epoch_leaders_leave( gui->epoch.epochs[ idx ].lsched ) );
1786 0 : gui->epoch.epochs[idx].lsched = fd_epoch_leaders_join( fd_epoch_leaders_new( gui->epoch.epochs[ idx ]._lsched,
1787 0 : epoch_info->epoch,
1788 0 : gui->epoch.epochs[ idx ].start_slot,
1789 0 : epoch_info->slot_cnt,
1790 0 : epoch_info->staked_cnt,
1791 0 : gui->epoch.epochs[ idx ].stakes,
1792 0 : epoch_info->excluded_stake,
1793 0 : epoch_info->vote_keyed_lsched ) );
1794 :
1795 0 : if( FD_UNLIKELY( epoch_info->start_slot==0UL ) ) {
1796 0 : gui->epoch.epochs[ 0 ].start_time = now;
1797 0 : } else {
1798 0 : gui->epoch.epochs[ idx ].start_time = LONG_MAX;
1799 :
1800 0 : for( ulong i=0UL; i<fd_ulong_min( epoch_info->start_slot-1UL, FD_GUI_SLOTS_CNT ); i++ ) {
1801 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, epoch_info->start_slot-i );
1802 0 : if( FD_UNLIKELY( !slot ) ) break;
1803 0 : else if( FD_UNLIKELY( slot->skipped ) ) continue;
1804 :
1805 0 : gui->epoch.epochs[ idx ].start_time = slot->completed_time;
1806 0 : break;
1807 0 : }
1808 0 : }
1809 :
1810 0 : fd_gui_printf_epoch( gui, idx );
1811 0 : fd_http_server_ws_broadcast( gui->http );
1812 0 : }
1813 :
1814 : static void
1815 : fd_gui_handle_slot_start( fd_gui_t * gui,
1816 : ulong _slot,
1817 : ulong parent_slot,
1818 0 : long now ) {
1819 0 : FD_TEST( gui->leader_slot==ULONG_MAX );
1820 0 : gui->leader_slot = _slot;
1821 :
1822 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
1823 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, parent_slot );
1824 :
1825 0 : fd_gui_tile_timers_snap( gui );
1826 0 : gui->summary.tile_timers_snap_idx_slot_start = (gui->summary.tile_timers_snap_idx+(FD_GUI_TILE_TIMER_SNAP_CNT-1UL))%FD_GUI_TILE_TIMER_SNAP_CNT;
1827 :
1828 0 : fd_gui_scheduler_counts_snap( gui, now );
1829 0 : gui->summary.scheduler_counts_snap_idx_slot_start = (gui->summary.scheduler_counts_snap_idx+(FD_GUI_SCHEDULER_COUNT_SNAP_CNT-1UL))%FD_GUI_SCHEDULER_COUNT_SNAP_CNT;
1830 :
1831 0 : fd_gui_txn_waterfall_t waterfall[ 1 ];
1832 0 : fd_gui_txn_waterfall_snap( gui, waterfall );
1833 0 : fd_gui_tile_stats_snap( gui, waterfall, slot->tile_stats_begin, now );
1834 0 : }
1835 :
1836 : static void
1837 : fd_gui_handle_slot_end( fd_gui_t * gui,
1838 : ulong _slot,
1839 : ulong _cus_used,
1840 0 : long now ) {
1841 0 : if( FD_UNLIKELY( !gui->summary.is_full_client && gui->leader_slot!=_slot ) ) {
1842 0 : FD_LOG_ERR(( "gui->leader_slot %lu _slot %lu", gui->leader_slot, _slot ));
1843 0 : }
1844 0 : gui->leader_slot = ULONG_MAX;
1845 :
1846 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
1847 0 : if( FD_UNLIKELY( !slot ) ) return;
1848 :
1849 0 : if( FD_UNLIKELY( !gui->summary.is_full_client ) ) slot->compute_units = (uint)_cus_used;
1850 :
1851 0 : fd_gui_tile_timers_snap( gui );
1852 :
1853 0 : fd_gui_scheduler_counts_snap( gui, now );
1854 :
1855 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, _slot );
1856 0 : if( FD_LIKELY( lslot ) ) {
1857 0 : fd_rng_t rng[ 1 ];
1858 0 : fd_rng_new( rng, 0UL, 0UL);
1859 :
1860 0 : #define DOWNSAMPLE( a, a_start, a_end, a_capacity, b, b_sz ) (__extension__({ \
1861 0 : ulong __cnt = 0UL; \
1862 0 : ulong __a_sz = (fd_ulong_if( a_end<a_start, a_end+a_capacity, a_end )-a_start); \
1863 0 : if( FD_UNLIKELY( __a_sz && b_sz ) ) { \
1864 0 : for( ulong a_idx=0UL; a_idx<__a_sz && __cnt<b_sz; a_idx++ ) { \
1865 0 : if( FD_UNLIKELY( fd_rng_float_robust( rng ) > (float)(b_sz-__cnt) / (float)(__a_sz-__cnt) ) ) continue; \
1866 0 : fd_memcpy( b[ __cnt ], a[ ((a_start+a_idx)%a_capacity) ], sizeof(b[ __cnt ]) ); \
1867 0 : __cnt++; \
1868 0 : } \
1869 0 : } \
1870 0 : __cnt; }))
1871 :
1872 0 : lslot->tile_timers_sample_cnt = DOWNSAMPLE(
1873 0 : gui->summary.tile_timers_snap,
1874 0 : gui->summary.tile_timers_snap_idx_slot_start,
1875 0 : gui->summary.tile_timers_snap_idx,
1876 0 : FD_GUI_TILE_TIMER_SNAP_CNT,
1877 0 : lslot->tile_timers,
1878 0 : FD_GUI_TILE_TIMER_LEADER_DOWNSAMPLE_CNT );
1879 :
1880 0 : lslot->scheduler_counts_sample_cnt = DOWNSAMPLE(
1881 0 : gui->summary.scheduler_counts_snap,
1882 0 : gui->summary.scheduler_counts_snap_idx_slot_start,
1883 0 : gui->summary.scheduler_counts_snap_idx,
1884 0 : FD_GUI_SCHEDULER_COUNT_SNAP_CNT,
1885 0 : lslot->scheduler_counts,
1886 0 : FD_GUI_SCHEDULER_COUNT_LEADER_DOWNSAMPLE_CNT );
1887 0 : #undef DOWNSAMPLE
1888 0 : }
1889 :
1890 : /* When a slot ends, snap the state of the waterfall and save it into
1891 : that slot, and also reset the reference counters to the end of the
1892 : slot. */
1893 :
1894 0 : fd_gui_txn_waterfall_snap( gui, slot->waterfall_end );
1895 0 : memcpy( slot->waterfall_begin, gui->summary.txn_waterfall_reference, sizeof(slot->waterfall_begin) );
1896 0 : memcpy( gui->summary.txn_waterfall_reference, slot->waterfall_end, sizeof(gui->summary.txn_waterfall_reference) );
1897 :
1898 0 : fd_gui_tile_stats_snap( gui, slot->waterfall_end, slot->tile_stats_end, now );
1899 0 : }
1900 :
1901 : void
1902 : fd_gui_handle_shred( fd_gui_t * gui,
1903 : ulong slot,
1904 : ulong shred_idx,
1905 : int is_turbine,
1906 0 : long tsorig ) {
1907 0 : int was_sent = fd_gui_ephemeral_slots_contains( gui->summary.slots_max_turbine, FD_GUI_TURBINE_SLOT_HISTORY_SZ, slot );
1908 0 : if( FD_LIKELY( is_turbine ) ) fd_gui_try_insert_ephemeral_slot( gui->summary.slots_max_turbine, FD_GUI_TURBINE_SLOT_HISTORY_SZ, slot, tsorig );
1909 :
1910 : /* If we haven't caught up yet, update repair slot using received
1911 : shreds. This is not technically correct, but close enough and will
1912 : make the progress bar look correct. */
1913 0 : if( FD_UNLIKELY( !is_turbine && gui->summary.slot_caught_up==ULONG_MAX ) ) fd_gui_handle_repair_slot( gui, slot, tsorig );
1914 :
1915 0 : if( FD_UNLIKELY( !was_sent && is_turbine && slot!=gui->summary.slot_turbine ) ) {
1916 0 : gui->summary.slot_turbine = slot;
1917 :
1918 0 : fd_gui_printf_turbine_slot( gui );
1919 0 : fd_http_server_ws_broadcast( gui->http );
1920 :
1921 0 : gui->turbine_slots[ slot % FD_GUI_TURBINE_RECV_TIMESTAMPS ].slot = slot;
1922 0 : gui->turbine_slots[ slot % FD_GUI_TURBINE_RECV_TIMESTAMPS ].timestamp = tsorig;
1923 :
1924 0 : ulong duration_sum = 0UL;
1925 0 : ulong slot_cnt = 0UL;
1926 :
1927 0 : for( ulong i=0UL; i<FD_GUI_TURBINE_RECV_TIMESTAMPS; i++ ) {
1928 0 : fd_gui_turbine_slot_t * cur = &gui->turbine_slots[ i ];
1929 0 : fd_gui_turbine_slot_t * prev = &gui->turbine_slots[ (i+FD_GUI_TURBINE_RECV_TIMESTAMPS-1UL) % FD_GUI_TURBINE_RECV_TIMESTAMPS ];
1930 0 : if( FD_UNLIKELY( cur->slot==ULONG_MAX || prev->slot==ULONG_MAX || cur->slot!=prev->slot+1UL ) ) continue;
1931 :
1932 0 : long slot_duration = cur->timestamp - prev->timestamp;
1933 0 : duration_sum += (ulong)fd_long_max( slot_duration, 0UL );
1934 0 : slot_cnt++;
1935 0 : }
1936 :
1937 0 : if( FD_LIKELY( slot_cnt>0 ) ) {
1938 0 : gui->summary.estimated_slot_duration_nanos = (ulong)(duration_sum / slot_cnt);
1939 0 : fd_gui_printf_estimated_slot_duration_nanos( gui );
1940 0 : fd_http_server_ws_broadcast( gui->http );
1941 0 : }
1942 :
1943 0 : if( FD_UNLIKELY( gui->summary.slot_caught_up==ULONG_MAX ) ) fd_gui_try_insert_run_length_slot( gui->summary.catch_up_turbine, FD_GUI_TURBINE_CATCH_UP_HISTORY_SZ, &gui->summary.catch_up_turbine_sz, slot );
1944 0 : }
1945 :
1946 0 : fd_gui_slot_staged_shred_event_t * recv_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
1947 0 : gui->shreds.staged_tail++;
1948 0 : recv_event->timestamp = tsorig;
1949 0 : recv_event->shred_idx = (ushort)shred_idx;
1950 0 : recv_event->slot = slot;
1951 0 : recv_event->event = fd_uchar_if( is_turbine, FD_GUI_SLOT_SHRED_SHRED_RECEIVED_TURBINE, FD_GUI_SLOT_SHRED_SHRED_RECEIVED_REPAIR );
1952 0 : }
1953 :
1954 : void
1955 : fd_gui_handle_leader_fec( fd_gui_t * gui,
1956 : ulong slot,
1957 : ulong fec_shred_cnt,
1958 : int is_end_of_slot,
1959 0 : long tsorig ) {
1960 0 : for( ulong i=gui->shreds.leader_shred_cnt; i<gui->shreds.leader_shred_cnt+fec_shred_cnt; i++ ) {
1961 0 : fd_gui_slot_staged_shred_event_t * exec_end_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
1962 0 : gui->shreds.staged_tail++;
1963 0 : exec_end_event->timestamp = tsorig;
1964 0 : exec_end_event->shred_idx = (ushort)i;
1965 0 : exec_end_event->slot = slot;
1966 0 : exec_end_event->event = FD_GUI_SLOT_SHRED_SHRED_PUBLISHED;
1967 0 : }
1968 0 : gui->shreds.leader_shred_cnt += fec_shred_cnt;
1969 0 : if( FD_UNLIKELY( is_end_of_slot ) ) gui->shreds.leader_shred_cnt = 0UL;
1970 0 : }
1971 :
1972 : void
1973 : fd_gui_handle_exec_txn_done( fd_gui_t * gui,
1974 : ulong slot,
1975 : ulong start_shred_idx,
1976 : ulong end_shred_idx,
1977 : long tsorig_ns FD_PARAM_UNUSED,
1978 0 : long tspub_ns ) {
1979 0 : for( ulong i = start_shred_idx; i<end_shred_idx; i++ ) {
1980 : /*
1981 : We're leaving this state transition out due to its proximity to
1982 : FD_GUI_SLOT_SHRED_SHRED_REPLAY_EXEC_DONE, but if we ever wanted
1983 : to send this data to the frontend we could.
1984 :
1985 : fd_gui_slot_staged_shred_event_t * exec_start_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
1986 : gui->shreds.staged_tail++;
1987 : exec_start_event->timestamp = tsorig_ns;
1988 : exec_start_event->shred_idx = (ushort)i;
1989 : exec_start_event->slot = slot;
1990 : exec_start_event->event = FD_GUI_SLOT_SHRED_SHRED_REPLAY_EXEC_START;
1991 : */
1992 :
1993 0 : fd_gui_slot_staged_shred_event_t * exec_end_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
1994 0 : gui->shreds.staged_tail++;
1995 0 : exec_end_event->timestamp = tspub_ns;
1996 0 : exec_end_event->shred_idx = (ushort)i;
1997 0 : exec_end_event->slot = slot;
1998 0 : exec_end_event->event = FD_GUI_SLOT_SHRED_SHRED_REPLAY_EXEC_DONE;
1999 0 : }
2000 0 : }
2001 :
2002 : static void
2003 : fd_gui_handle_reset_slot_legacy( fd_gui_t * gui,
2004 : ulong * msg,
2005 0 : long now ) {
2006 0 : ulong last_landed_vote = msg[ 0 ];
2007 :
2008 0 : ulong parent_cnt = msg[ 1 ];
2009 0 : FD_TEST( parent_cnt<4096UL );
2010 :
2011 0 : ulong _slot = msg[ 2 ];
2012 :
2013 0 : for( ulong i=0UL; i<parent_cnt; i++ ) {
2014 0 : ulong parent_slot = msg[2UL+i];
2015 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, parent_slot );
2016 0 : if( FD_UNLIKELY( !slot ) ) {
2017 0 : ulong parent_parent_slot = ULONG_MAX;
2018 0 : if( FD_UNLIKELY( i!=parent_cnt-1UL) ) parent_parent_slot = msg[ 3UL+i ];
2019 0 : fd_gui_clear_slot( gui, parent_slot, parent_parent_slot );
2020 0 : }
2021 0 : }
2022 :
2023 0 : if( FD_UNLIKELY( gui->summary.vote_distance!=_slot-last_landed_vote ) ) {
2024 0 : gui->summary.vote_distance = _slot-last_landed_vote;
2025 0 : fd_gui_printf_vote_distance( gui );
2026 0 : fd_http_server_ws_broadcast( gui->http );
2027 0 : }
2028 :
2029 0 : if( FD_LIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_NON_VOTING ) ) {
2030 0 : if( FD_UNLIKELY( last_landed_vote==ULONG_MAX || (last_landed_vote+150UL)<_slot ) ) {
2031 0 : if( FD_UNLIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_DELINQUENT ) ) {
2032 0 : gui->summary.vote_state = FD_GUI_VOTE_STATE_DELINQUENT;
2033 0 : fd_gui_printf_vote_state( gui );
2034 0 : fd_http_server_ws_broadcast( gui->http );
2035 0 : }
2036 0 : } else {
2037 0 : if( FD_UNLIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_VOTING ) ) {
2038 0 : gui->summary.vote_state = FD_GUI_VOTE_STATE_VOTING;
2039 0 : fd_gui_printf_vote_state( gui );
2040 0 : fd_http_server_ws_broadcast( gui->http );
2041 0 : }
2042 0 : }
2043 0 : }
2044 :
2045 0 : ulong parent_slot_idx = 0UL;
2046 :
2047 0 : int republish_skip_rate[ 2 ] = {0};
2048 :
2049 0 : for( ulong i=0UL; i<fd_ulong_min( _slot+1, FD_GUI_SLOTS_CNT ); i++ ) {
2050 0 : ulong parent_slot = _slot - i;
2051 :
2052 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, parent_slot );
2053 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, parent_slot, ULONG_MAX );
2054 :
2055 : /* The chain of parents may stretch into already rooted slots if
2056 : they haven't been squashed yet, if we reach one of them we can
2057 : just exit, all the information prior to the root is already
2058 : correct. */
2059 :
2060 0 : if( FD_LIKELY( slot->level>=FD_GUI_SLOT_LEVEL_ROOTED ) ) break;
2061 :
2062 0 : int should_republish = slot->must_republish;
2063 0 : slot->must_republish = 0;
2064 :
2065 0 : if( FD_UNLIKELY( parent_slot!=msg[2UL+parent_slot_idx] ) ) {
2066 : /* We are between two parents in the rooted chain, which means
2067 : we were skipped. */
2068 0 : if( FD_UNLIKELY( !slot->skipped ) ) {
2069 0 : slot->skipped = 1;
2070 0 : should_republish = 1;
2071 0 : if( FD_LIKELY( slot->mine ) ) {
2072 0 : for( ulong i=0UL; i<2UL; i++ ) {
2073 0 : if( FD_LIKELY( parent_slot>=gui->epoch.epochs[ i ].start_slot && parent_slot<=gui->epoch.epochs[ i ].end_slot ) ) {
2074 0 : gui->epoch.epochs[ i ].my_skipped_slots++;
2075 0 : republish_skip_rate[ i ] = 1;
2076 0 : break;
2077 0 : }
2078 0 : }
2079 0 : }
2080 0 : }
2081 0 : } else {
2082 : /* Reached the next parent... */
2083 0 : if( FD_UNLIKELY( slot->skipped ) ) {
2084 0 : slot->skipped = 0;
2085 0 : should_republish = 1;
2086 0 : if( FD_LIKELY( slot->mine ) ) {
2087 0 : for( ulong i=0UL; i<2UL; i++ ) {
2088 0 : if( FD_LIKELY( parent_slot>=gui->epoch.epochs[ i ].start_slot && parent_slot<=gui->epoch.epochs[ i ].end_slot ) ) {
2089 0 : gui->epoch.epochs[ i ].my_skipped_slots--;
2090 0 : republish_skip_rate[ i ] = 1;
2091 0 : break;
2092 0 : }
2093 0 : }
2094 0 : }
2095 0 : }
2096 0 : parent_slot_idx++;
2097 0 : }
2098 :
2099 0 : if( FD_LIKELY( should_republish ) ) {
2100 0 : fd_gui_printf_slot( gui, parent_slot );
2101 0 : fd_http_server_ws_broadcast( gui->http );
2102 0 : }
2103 :
2104 : /* We reached the last parent in the chain, everything above this
2105 : must have already been rooted, so we can exit. */
2106 :
2107 0 : if( FD_UNLIKELY( parent_slot_idx>=parent_cnt ) ) break;
2108 0 : }
2109 :
2110 0 : ulong duration_sum = 0UL;
2111 0 : ulong slot_cnt = 0UL;
2112 :
2113 : /* If we've just caught up we should truncate our slot history to avoid including catch-up slots */
2114 0 : int just_caught_up = gui->summary.slot_caught_up!=ULONG_MAX && _slot>gui->summary.slot_caught_up && _slot<gui->summary.slot_caught_up+750UL;
2115 0 : ulong slot_duration_history_sz = fd_ulong_if( just_caught_up, _slot-gui->summary.slot_caught_up, 750UL );
2116 0 : for( ulong i=0UL; i<fd_ulong_min( _slot+1, slot_duration_history_sz ); i++ ) {
2117 0 : ulong parent_slot = _slot - i;
2118 :
2119 0 : fd_gui_slot_t const * slot = fd_gui_get_slot_const( gui, parent_slot );
2120 0 : if( FD_UNLIKELY( !slot) ) break;
2121 0 : if( FD_UNLIKELY( slot->slot!=parent_slot ) ) {
2122 0 : FD_LOG_ERR(( "_slot %lu i %lu we expect _slot-i %lu got slot->slot %lu", _slot, i, _slot-i, slot->slot ));
2123 0 : }
2124 :
2125 0 : ulong slot_duration = fd_gui_slot_duration( gui, slot );
2126 0 : if( FD_LIKELY( slot_duration!=ULONG_MAX ) ) {
2127 0 : duration_sum += slot_duration;
2128 0 : slot_cnt++;
2129 0 : }
2130 0 : }
2131 :
2132 0 : if( FD_LIKELY( slot_cnt>0 ) ) {
2133 0 : gui->summary.estimated_slot_duration_nanos = (ulong)(duration_sum / slot_cnt);
2134 0 : fd_gui_printf_estimated_slot_duration_nanos( gui );
2135 0 : fd_http_server_ws_broadcast( gui->http );
2136 0 : }
2137 :
2138 0 : if( FD_LIKELY( gui->summary.slot_completed==ULONG_MAX || _slot!=gui->summary.slot_completed ) ) {
2139 0 : gui->summary.slot_completed = _slot;
2140 0 : fd_gui_printf_completed_slot( gui );
2141 0 : fd_http_server_ws_broadcast( gui->http );
2142 :
2143 : /* Also update slot_turbine which could be larger than the max
2144 : turbine slot if we are leader */
2145 0 : if( FD_UNLIKELY( gui->summary.slots_max_turbine[ 0 ].slot!=ULONG_MAX && gui->summary.slot_completed!=ULONG_MAX && gui->summary.slot_completed>gui->summary.slots_max_turbine[ 0 ].slot ) ) {
2146 0 : fd_gui_try_insert_ephemeral_slot( gui->summary.slots_max_turbine, FD_GUI_TURBINE_SLOT_HISTORY_SZ, gui->summary.slot_completed, now );
2147 0 : }
2148 :
2149 0 : int slot_turbine_hist_full = gui->summary.slots_max_turbine[ FD_GUI_TURBINE_SLOT_HISTORY_SZ-1UL ].slot!=ULONG_MAX;
2150 0 : if( FD_UNLIKELY( gui->summary.slot_caught_up==ULONG_MAX && slot_turbine_hist_full && gui->summary.slots_max_turbine[ 0 ].slot < (gui->summary.slot_completed + 3UL) ) ) {
2151 0 : gui->summary.slot_caught_up = gui->summary.slot_completed + 4UL;
2152 :
2153 0 : fd_gui_printf_slot_caught_up( gui );
2154 0 : fd_http_server_ws_broadcast( gui->http );
2155 0 : }
2156 0 : }
2157 :
2158 0 : for( ulong i=0UL; i<2UL; i++ ) {
2159 0 : if( FD_LIKELY( republish_skip_rate[ i ] ) ) {
2160 0 : fd_gui_printf_skip_rate( gui, i );
2161 0 : fd_http_server_ws_broadcast( gui->http );
2162 0 : }
2163 0 : }
2164 0 : }
2165 :
2166 : static void
2167 : fd_gui_handle_completed_slot( fd_gui_t * gui,
2168 : ulong * msg,
2169 0 : long now ) {
2170 :
2171 : /* This is the slot used by frontend clients as the "startup slot". In
2172 : certain boot conditions, we don't receive this slot from Agave, so
2173 : we include a bit of a hacky assignment here to make sure it is
2174 : always present. */
2175 0 : if( FD_UNLIKELY( gui->summary.startup_progress.startup_ledger_max_slot==ULONG_MAX ) ) {
2176 0 : gui->summary.startup_progress.startup_ledger_max_slot = msg[ 0 ];
2177 0 : }
2178 :
2179 0 : ulong _slot = msg[ 0 ];
2180 0 : uint total_txn_count = (uint)msg[ 1 ];
2181 0 : uint nonvote_txn_count = (uint)msg[ 2 ];
2182 0 : uint failed_txn_count = (uint)msg[ 3 ];
2183 0 : uint nonvote_failed_txn_count = (uint)msg[ 4 ];
2184 0 : uint compute_units = (uint)msg[ 5 ];
2185 0 : ulong transaction_fee = msg[ 6 ];
2186 0 : ulong priority_fee = msg[ 7 ];
2187 0 : ulong tips = msg[ 8 ];
2188 0 : ulong _parent_slot = msg[ 9 ];
2189 0 : ulong max_compute_units = msg[ 10 ];
2190 :
2191 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
2192 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, _parent_slot );
2193 :
2194 0 : slot->completed_time = now;
2195 0 : slot->parent_slot = _parent_slot;
2196 0 : slot->max_compute_units = (uint)max_compute_units;
2197 0 : if( FD_LIKELY( slot->level<FD_GUI_SLOT_LEVEL_COMPLETED ) ) {
2198 : /* Typically a slot goes from INCOMPLETE to COMPLETED but it can
2199 : happen that it starts higher. One such case is when we
2200 : optimistically confirm a higher slot that skips this one, but
2201 : then later we replay this one anyway to track the bank fork. */
2202 :
2203 0 : if( FD_LIKELY( gui->summary.slot_optimistically_confirmed!=ULONG_MAX && _slot<gui->summary.slot_optimistically_confirmed ) ) {
2204 : /* Cluster might have already optimistically confirmed by the time
2205 : we finish replaying it. */
2206 0 : slot->level = FD_GUI_SLOT_LEVEL_OPTIMISTICALLY_CONFIRMED;
2207 0 : } else {
2208 0 : slot->level = FD_GUI_SLOT_LEVEL_COMPLETED;
2209 0 : }
2210 0 : }
2211 0 : slot->total_txn_cnt = total_txn_count;
2212 0 : slot->vote_txn_cnt = total_txn_count - nonvote_txn_count;
2213 0 : slot->failed_txn_cnt = failed_txn_count;
2214 0 : slot->nonvote_failed_txn_cnt = nonvote_failed_txn_count;
2215 0 : slot->transaction_fee = transaction_fee;
2216 0 : slot->priority_fee = priority_fee;
2217 0 : slot->tips = tips;
2218 :
2219 : /* In Frankendancer, CUs come from our own leader pipeline (the field
2220 : sent from the Agave codepath is zero'd out) */
2221 0 : slot->compute_units = fd_uint_if( !gui->summary.is_full_client && slot->mine, slot->compute_units, compute_units );
2222 :
2223 0 : if( FD_UNLIKELY( gui->epoch.has_epoch[ 0 ] && _slot==gui->epoch.epochs[ 0 ].end_slot ) ) {
2224 0 : gui->epoch.epochs[ 0 ].end_time = slot->completed_time;
2225 0 : } else if( FD_UNLIKELY( gui->epoch.has_epoch[ 1 ] && _slot==gui->epoch.epochs[ 1 ].end_slot ) ) {
2226 0 : gui->epoch.epochs[ 1 ].end_time = slot->completed_time;
2227 0 : }
2228 :
2229 : /* Broadcast new skip rate if one of our slots got completed. */
2230 0 : if( FD_LIKELY( slot->mine ) ) {
2231 0 : for( ulong i=0UL; i<2UL; i++ ) {
2232 0 : if( FD_LIKELY( _slot>=gui->epoch.epochs[ i ].start_slot && _slot<=gui->epoch.epochs[ i ].end_slot ) ) {
2233 0 : fd_gui_printf_skip_rate( gui, i );
2234 0 : fd_http_server_ws_broadcast( gui->http );
2235 0 : break;
2236 0 : }
2237 0 : }
2238 0 : }
2239 0 : }
2240 :
2241 : static void
2242 : fd_gui_handle_rooted_slot_legacy( fd_gui_t * gui,
2243 0 : ulong * msg ) {
2244 0 : ulong _slot = msg[ 0 ];
2245 :
2246 : // FD_LOG_WARNING(( "Got rooted slot %lu", _slot ));
2247 :
2248 : /* Slot 0 is always rooted. No need to iterate all the way back to
2249 : i==_slot */
2250 0 : for( ulong i=0UL; i<fd_ulong_min( _slot, FD_GUI_SLOTS_CNT ); i++ ) {
2251 0 : ulong parent_slot = _slot - i;
2252 :
2253 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, parent_slot );
2254 0 : if( FD_UNLIKELY( !slot ) ) break;
2255 :
2256 0 : if( FD_UNLIKELY( slot->slot!=parent_slot ) ) {
2257 0 : FD_LOG_ERR(( "_slot %lu i %lu we expect parent_slot %lu got slot->slot %lu", _slot, i, parent_slot, slot->slot ));
2258 0 : }
2259 0 : if( FD_UNLIKELY( slot->level>=FD_GUI_SLOT_LEVEL_ROOTED ) ) break;
2260 :
2261 0 : slot->level = FD_GUI_SLOT_LEVEL_ROOTED;
2262 0 : fd_gui_printf_slot( gui, parent_slot );
2263 0 : fd_http_server_ws_broadcast( gui->http );
2264 0 : }
2265 :
2266 0 : gui->summary.slot_rooted = _slot;
2267 0 : fd_gui_printf_root_slot( gui );
2268 0 : fd_http_server_ws_broadcast( gui->http );
2269 0 : }
2270 :
2271 : static void
2272 : fd_gui_handle_optimistically_confirmed_slot( fd_gui_t * gui,
2273 0 : ulong _slot ) {
2274 : /* Slot 0 is always rooted. No need to iterate all the way back to
2275 : i==_slot */
2276 0 : for( ulong i=0UL; i<fd_ulong_min( _slot, FD_GUI_SLOTS_CNT ); i++ ) {
2277 0 : ulong parent_slot = _slot - i;
2278 :
2279 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, parent_slot );
2280 0 : if( FD_UNLIKELY( !slot) ) break;
2281 :
2282 0 : if( FD_UNLIKELY( slot->slot>parent_slot ) ) {
2283 0 : FD_LOG_ERR(( "_slot %lu i %lu we expect parent_slot %lu got slot->slot %lu", _slot, i, parent_slot, slot->slot ));
2284 0 : } else if( FD_UNLIKELY( slot->slot<parent_slot ) ) {
2285 : /* Slot not even replayed yet ... will come out as optimistically confirmed */
2286 0 : continue;
2287 0 : }
2288 0 : if( FD_UNLIKELY( slot->level>=FD_GUI_SLOT_LEVEL_ROOTED ) ) break;
2289 :
2290 0 : if( FD_LIKELY( slot->level<FD_GUI_SLOT_LEVEL_OPTIMISTICALLY_CONFIRMED ) ) {
2291 0 : slot->level = FD_GUI_SLOT_LEVEL_OPTIMISTICALLY_CONFIRMED;
2292 0 : fd_gui_printf_slot( gui, parent_slot );
2293 0 : fd_http_server_ws_broadcast( gui->http );
2294 0 : }
2295 0 : }
2296 :
2297 0 : if( FD_UNLIKELY( gui->summary.slot_optimistically_confirmed!=ULONG_MAX && _slot<gui->summary.slot_optimistically_confirmed ) ) {
2298 : /* Optimistically confirmed slot went backwards ... mark some slots as no
2299 : longer optimistically confirmed. */
2300 0 : for( ulong i=gui->summary.slot_optimistically_confirmed; i>=_slot; i-- ) {
2301 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, i );
2302 0 : if( FD_UNLIKELY( !slot ) ) break;
2303 0 : if( FD_LIKELY( slot->slot==i ) ) {
2304 : /* It's possible for the optimistically confirmed slot to skip
2305 : backwards between two slots that we haven't yet replayed. In
2306 : that case we don't need to change anything, since they will
2307 : get marked properly when they get completed. */
2308 0 : slot->level = FD_GUI_SLOT_LEVEL_COMPLETED;
2309 0 : fd_gui_printf_slot( gui, i );
2310 0 : fd_http_server_ws_broadcast( gui->http );
2311 0 : }
2312 0 : }
2313 0 : }
2314 :
2315 0 : gui->summary.slot_optimistically_confirmed = _slot;
2316 0 : fd_gui_printf_optimistically_confirmed_slot( gui );
2317 0 : fd_http_server_ws_broadcast( gui->http );
2318 0 : }
2319 :
2320 : static void
2321 : fd_gui_handle_balance_update( fd_gui_t * gui,
2322 0 : ulong const * msg ) {
2323 0 : switch( msg[ 0 ] ) {
2324 0 : case 0UL:
2325 0 : gui->summary.identity_account_balance = msg[ 1 ];
2326 0 : fd_gui_printf_identity_balance( gui );
2327 0 : fd_http_server_ws_broadcast( gui->http );
2328 0 : break;
2329 0 : case 1UL:
2330 0 : gui->summary.vote_account_balance = msg[ 1 ];
2331 0 : fd_gui_printf_vote_balance( gui );
2332 0 : fd_http_server_ws_broadcast( gui->http );
2333 0 : break;
2334 0 : default:
2335 0 : FD_LOG_ERR(( "balance: unknown account type: %lu", msg[ 0 ] ));
2336 0 : }
2337 0 : }
2338 :
2339 : static void
2340 : fd_gui_handle_start_progress( fd_gui_t * gui,
2341 0 : uchar const * msg ) {
2342 0 : uchar type = msg[ 0 ];
2343 :
2344 0 : switch (type) {
2345 0 : case 0:
2346 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_INITIALIZING;
2347 0 : FD_LOG_INFO(( "progress: initializing" ));
2348 0 : break;
2349 0 : case 1: {
2350 0 : char const * snapshot_type;
2351 0 : if( FD_UNLIKELY( gui->summary.startup_progress.startup_got_full_snapshot ) ) {
2352 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_SEARCHING_FOR_INCREMENTAL_SNAPSHOT;
2353 0 : snapshot_type = "incremental";
2354 0 : } else {
2355 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_SEARCHING_FOR_FULL_SNAPSHOT;
2356 0 : snapshot_type = "full";
2357 0 : }
2358 0 : FD_LOG_INFO(( "progress: searching for %s snapshot", snapshot_type ));
2359 0 : break;
2360 0 : }
2361 0 : case 2: {
2362 0 : uchar is_full_snapshot = msg[ 1 ];
2363 0 : if( FD_LIKELY( is_full_snapshot ) ) {
2364 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_DOWNLOADING_FULL_SNAPSHOT;
2365 0 : gui->summary.startup_progress.startup_full_snapshot_slot = *((ulong *)(msg + 2));
2366 0 : gui->summary.startup_progress.startup_full_snapshot_peer_ip_addr = *((uint *)(msg + 10));
2367 0 : gui->summary.startup_progress.startup_full_snapshot_peer_port = *((ushort *)(msg + 14));
2368 0 : gui->summary.startup_progress.startup_full_snapshot_total_bytes = *((ulong *)(msg + 16));
2369 0 : gui->summary.startup_progress.startup_full_snapshot_current_bytes = *((ulong *)(msg + 24));
2370 0 : gui->summary.startup_progress.startup_full_snapshot_elapsed_secs = *((double *)(msg + 32));
2371 0 : gui->summary.startup_progress.startup_full_snapshot_remaining_secs = *((double *)(msg + 40));
2372 0 : gui->summary.startup_progress.startup_full_snapshot_throughput = *((double *)(msg + 48));
2373 0 : FD_LOG_INFO(( "progress: downloading full snapshot: slot=%lu", gui->summary.startup_progress.startup_full_snapshot_slot ));
2374 0 : } else {
2375 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_DOWNLOADING_INCREMENTAL_SNAPSHOT;
2376 0 : gui->summary.startup_progress.startup_incremental_snapshot_slot = *((ulong *)(msg + 2));
2377 0 : gui->summary.startup_progress.startup_incremental_snapshot_peer_ip_addr = *((uint *)(msg + 10));
2378 0 : gui->summary.startup_progress.startup_incremental_snapshot_peer_port = *((ushort *)(msg + 14));
2379 0 : gui->summary.startup_progress.startup_incremental_snapshot_total_bytes = *((ulong *)(msg + 16));
2380 0 : gui->summary.startup_progress.startup_incremental_snapshot_current_bytes = *((ulong *)(msg + 24));
2381 0 : gui->summary.startup_progress.startup_incremental_snapshot_elapsed_secs = *((double *)(msg + 32));
2382 0 : gui->summary.startup_progress.startup_incremental_snapshot_remaining_secs = *((double *)(msg + 40));
2383 0 : gui->summary.startup_progress.startup_incremental_snapshot_throughput = *((double *)(msg + 48));
2384 0 : FD_LOG_INFO(( "progress: downloading incremental snapshot: slot=%lu", gui->summary.startup_progress.startup_incremental_snapshot_slot ));
2385 0 : }
2386 0 : break;
2387 0 : }
2388 0 : case 3: {
2389 0 : gui->summary.startup_progress.startup_got_full_snapshot = 1;
2390 0 : break;
2391 0 : }
2392 0 : case 4:
2393 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_CLEANING_BLOCK_STORE;
2394 0 : FD_LOG_INFO(( "progress: cleaning block store" ));
2395 0 : break;
2396 0 : case 5:
2397 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_CLEANING_ACCOUNTS;
2398 0 : FD_LOG_INFO(( "progress: cleaning accounts" ));
2399 0 : break;
2400 0 : case 6:
2401 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_LOADING_LEDGER;
2402 0 : FD_LOG_INFO(( "progress: loading ledger" ));
2403 0 : break;
2404 0 : case 7: {
2405 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_PROCESSING_LEDGER;
2406 0 : gui->summary.startup_progress.startup_ledger_slot = fd_ulong_load_8( msg + 1 );
2407 0 : gui->summary.startup_progress.startup_ledger_max_slot = fd_ulong_load_8( msg + 9 );
2408 0 : FD_LOG_INFO(( "progress: processing ledger: slot=%lu, max_slot=%lu", gui->summary.startup_progress.startup_ledger_slot, gui->summary.startup_progress.startup_ledger_max_slot ));
2409 0 : break;
2410 0 : }
2411 0 : case 8:
2412 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_STARTING_SERVICES;
2413 0 : FD_LOG_INFO(( "progress: starting services" ));
2414 0 : break;
2415 0 : case 9:
2416 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_HALTED;
2417 0 : FD_LOG_INFO(( "progress: halted" ));
2418 0 : break;
2419 0 : case 10: {
2420 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_WAITING_FOR_SUPERMAJORITY;
2421 0 : gui->summary.startup_progress.startup_waiting_for_supermajority_slot = fd_ulong_load_8( msg + 1 );
2422 0 : gui->summary.startup_progress.startup_waiting_for_supermajority_stake_pct = fd_ulong_load_8( msg + 9 );
2423 0 : FD_LOG_INFO(( "progress: waiting for supermajority: slot=%lu, gossip_stake_percent=%lu", gui->summary.startup_progress.startup_waiting_for_supermajority_slot, gui->summary.startup_progress.startup_waiting_for_supermajority_stake_pct ));
2424 0 : break;
2425 0 : }
2426 0 : case 11:
2427 0 : gui->summary.startup_progress.phase = FD_GUI_START_PROGRESS_TYPE_RUNNING;
2428 0 : FD_LOG_INFO(( "progress: running" ));
2429 0 : break;
2430 0 : default:
2431 0 : FD_LOG_ERR(( "progress: unknown type: %u", type ));
2432 0 : }
2433 :
2434 0 : fd_gui_printf_startup_progress( gui );
2435 0 : fd_http_server_ws_broadcast( gui->http );
2436 0 : }
2437 :
2438 : void
2439 : fd_gui_handle_genesis_hash( fd_gui_t * gui,
2440 0 : uchar const * msg ) {
2441 0 : FD_BASE58_ENCODE_32_BYTES(msg, hash_cstr);
2442 0 : ulong cluster = fd_genesis_cluster_identify(hash_cstr);
2443 0 : char const * cluster_name = fd_genesis_cluster_name(cluster);
2444 :
2445 0 : if( FD_LIKELY( strcmp( gui->summary.cluster, cluster_name ) ) ) {
2446 0 : gui->summary.cluster = fd_genesis_cluster_name(cluster);
2447 0 : fd_gui_printf_cluster( gui );
2448 0 : fd_http_server_ws_broadcast( gui->http );
2449 0 : }
2450 0 : }
2451 :
2452 : static void
2453 : fd_gui_handle_block_engine_update( fd_gui_t * gui,
2454 0 : uchar const * msg ) {
2455 0 : fd_plugin_msg_block_engine_update_t const * update = (fd_plugin_msg_block_engine_update_t const *)msg;
2456 :
2457 0 : gui->block_engine.has_block_engine = 1;
2458 :
2459 : /* copy strings and ensure null termination within bounds */
2460 0 : FD_TEST( fd_cstr_nlen( update->name, sizeof(gui->block_engine.name ) ) < sizeof(gui->block_engine.name ) );
2461 0 : FD_TEST( fd_cstr_nlen( update->url, sizeof(gui->block_engine.url ) ) < sizeof(gui->block_engine.url ) );
2462 0 : FD_TEST( fd_cstr_nlen( update->ip_cstr, sizeof(gui->block_engine.ip_cstr) ) < sizeof(gui->block_engine.ip_cstr) );
2463 0 : ulong name_len = fd_cstr_nlen( update->name, sizeof(gui->block_engine.name ) );
2464 0 : ulong url_len = fd_cstr_nlen( update->url, sizeof(gui->block_engine.url ) );
2465 0 : ulong ip_cstr_len = fd_cstr_nlen( update->ip_cstr, sizeof(gui->block_engine.ip_cstr) );
2466 0 : fd_memcpy( gui->block_engine.name, update->name, name_len+1UL );
2467 0 : fd_memcpy( gui->block_engine.url, update->url, url_len+1UL );
2468 0 : fd_memcpy( gui->block_engine.ip_cstr, update->ip_cstr, ip_cstr_len+1UL );
2469 :
2470 0 : gui->block_engine.status = update->status;
2471 :
2472 0 : fd_gui_printf_block_engine( gui );
2473 0 : fd_http_server_ws_broadcast( gui->http );
2474 0 : }
2475 :
2476 : void
2477 : fd_gui_handle_snapshot_update( fd_gui_t * gui,
2478 0 : fd_snapct_update_t const * msg ) {
2479 0 : FD_TEST( msg && fd_cstr_nlen( msg->read_path, 1 ) );
2480 :
2481 0 : ulong snapshot_idx = fd_ulong_if( msg->type==FD_SNAPCT_SNAPSHOT_TYPE_FULL, FD_GUI_BOOT_PROGRESS_FULL_SNAPSHOT_IDX, FD_GUI_BOOT_PROGRESS_INCREMENTAL_SNAPSHOT_IDX );
2482 :
2483 0 : char const * filename = strrchr(msg->read_path, '/');
2484 :
2485 : /* Skip the '/' */
2486 0 : if( FD_UNLIKELY( filename ) ) filename++;
2487 :
2488 0 : if (msg->type == FD_SNAPCT_SNAPSHOT_TYPE_INCREMENTAL) {
2489 0 : ulong slot1, slot2;
2490 0 : if ( FD_LIKELY( sscanf( filename, "incremental-snapshot-%lu-%lu-", &slot1, &slot2 )==2 ) )
2491 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].slot = slot2;
2492 0 : else FD_LOG_ERR(("failed to scan filename: %s parsed from %s", filename, msg->read_path ));
2493 0 : } else if (msg->type == FD_SNAPCT_SNAPSHOT_TYPE_FULL) {
2494 0 : ulong slot1;
2495 0 : if ( FD_LIKELY( sscanf( filename, "snapshot-%lu-", &slot1 )==1 ) )
2496 0 : gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].slot = slot1;
2497 0 : else FD_LOG_ERR(("failed to scan filename: %s parsed from %s", filename, msg->read_path ));
2498 0 : }
2499 0 : fd_cstr_printf_check( gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].read_path, sizeof(gui->summary.boot_progress.loading_snapshot[ snapshot_idx ].read_path), NULL, "%s", msg->read_path );
2500 0 : }
2501 :
2502 : static void
2503 0 : fd_gui_handle_reset_slot( fd_gui_t * gui, ulong reset_slot, long now ) {
2504 0 : FD_TEST( reset_slot!=ULONG_MAX );
2505 :
2506 : /* reset_slot has not changed */
2507 0 : if( FD_UNLIKELY( gui->summary.slot_completed!=ULONG_MAX && reset_slot==gui->summary.slot_completed ) ) return;
2508 :
2509 0 : ulong prev_slot_completed = gui->summary.slot_completed;
2510 0 : gui->summary.slot_completed = reset_slot;
2511 :
2512 0 : if( FD_LIKELY( fd_gui_get_slot( gui, gui->summary.slot_completed ) ) ) {
2513 0 : fd_gui_printf_slot( gui, gui->summary.slot_completed );
2514 0 : fd_http_server_ws_broadcast( gui->http );
2515 0 : }
2516 :
2517 0 : fd_gui_printf_completed_slot( gui );
2518 0 : fd_http_server_ws_broadcast( gui->http );
2519 :
2520 : /* Also update slot_turbine which could be larger than the max
2521 : turbine slot if we are leader */
2522 0 : if( FD_UNLIKELY( gui->summary.slots_max_turbine[ 0 ].slot!=ULONG_MAX && gui->summary.slot_completed > gui->summary.slots_max_turbine[ 0 ].slot ) ) {
2523 0 : fd_gui_try_insert_ephemeral_slot( gui->summary.slots_max_turbine, FD_GUI_TURBINE_SLOT_HISTORY_SZ, gui->summary.slot_completed, now );
2524 0 : }
2525 :
2526 0 : int slot_turbine_hist_full = gui->summary.slots_max_turbine[ FD_GUI_TURBINE_SLOT_HISTORY_SZ-1UL ].slot!=ULONG_MAX;
2527 0 : if( FD_UNLIKELY( gui->summary.slot_caught_up==ULONG_MAX && slot_turbine_hist_full && gui->summary.slots_max_turbine[ 0 ].slot < (gui->summary.slot_completed + 3UL) ) ) {
2528 0 : gui->summary.slot_caught_up = gui->summary.slot_completed + 4UL;
2529 :
2530 0 : fd_gui_printf_slot_caught_up( gui );
2531 0 : fd_http_server_ws_broadcast( gui->http );
2532 0 : }
2533 :
2534 : /* ensure a history exists */
2535 0 : if( FD_UNLIKELY( prev_slot_completed==ULONG_MAX || gui->summary.slot_rooted==ULONG_MAX ) ) return;
2536 :
2537 : /* slot complete received out of order on the same fork? */
2538 0 : FD_TEST( fd_gui_slot_is_ancestor( gui, prev_slot_completed, gui->summary.slot_completed ) || !fd_gui_slot_is_ancestor( gui, gui->summary.slot_completed, prev_slot_completed ) );
2539 :
2540 : /* fork switch: we need to "undo" the previous fork */
2541 0 : int republish_skip_rate[ 2 ] = {0};
2542 0 : if( FD_UNLIKELY( !fd_gui_slot_is_ancestor( gui, prev_slot_completed, gui->summary.slot_completed ) ) ) {
2543 : /* The handling for skipped slot on a fork switch is tricky. We
2544 : want to rebate back any slots that were skipped but are no
2545 : longer. We also need to make sure we count skipped slots
2546 : towards the correct epoch. */
2547 0 : for( ulong i=fd_ulong_max( gui->summary.slot_completed, prev_slot_completed); i>gui->summary.slot_rooted; i-- ) {
2548 :
2549 0 : int is_skipped_on_old_fork = i<=prev_slot_completed && fd_gui_is_skipped_on_fork( gui, gui->summary.slot_rooted, prev_slot_completed, i );
2550 0 : int is_skipped_on_new_fork = i<=gui->summary.slot_completed && fd_gui_is_skipped_on_fork( gui, gui->summary.slot_rooted, gui->summary.slot_completed, i );
2551 :
2552 0 : if( FD_LIKELY( is_skipped_on_old_fork && !is_skipped_on_new_fork ) ) {
2553 0 : fd_gui_slot_t * skipped = fd_gui_get_slot( gui, i );
2554 0 : if( FD_LIKELY( !skipped ) ) {
2555 0 : fd_gui_slot_t * p = fd_gui_get_parent_slot_on_fork( gui, prev_slot_completed, i );
2556 0 : skipped = fd_gui_clear_slot( gui, i, p ? p->slot : ULONG_MAX );
2557 0 : }
2558 :
2559 0 : skipped->skipped = 0;
2560 0 : fd_gui_printf_slot( gui, skipped->slot );
2561 0 : fd_http_server_ws_broadcast( gui->http );
2562 0 : skipped->must_republish = 0;
2563 :
2564 0 : if( FD_LIKELY( skipped->mine ) ) {
2565 0 : for( ulong i=0UL; i<2UL; i++ ) {
2566 0 : if( FD_LIKELY( i>=gui->epoch.epochs[ i ].start_slot && i<=gui->epoch.epochs[ i ].end_slot ) ) {
2567 0 : gui->epoch.epochs[ i ].my_skipped_slots--;
2568 0 : republish_skip_rate[ i ] = 1;
2569 0 : break;
2570 0 : }
2571 0 : }
2572 0 : }
2573 0 : }
2574 :
2575 0 : if( FD_LIKELY( !is_skipped_on_old_fork && is_skipped_on_new_fork ) ) {
2576 0 : fd_gui_slot_t * skipped = fd_gui_get_slot( gui, i );
2577 0 : if( FD_LIKELY( !skipped ) ) {
2578 0 : fd_gui_slot_t * p = fd_gui_get_parent_slot_on_fork( gui, prev_slot_completed, i );
2579 0 : skipped = fd_gui_clear_slot( gui, i, p ? p->slot : ULONG_MAX );
2580 0 : }
2581 :
2582 0 : skipped->skipped = 1;
2583 0 : fd_gui_printf_slot( gui, skipped->slot );
2584 0 : fd_http_server_ws_broadcast( gui->http );
2585 0 : skipped->must_republish = 0;
2586 :
2587 0 : if( FD_LIKELY( skipped->mine ) ) {
2588 0 : for( ulong i=0UL; i<2UL; i++ ) {
2589 0 : if( FD_LIKELY( i>=gui->epoch.epochs[ i ].start_slot && i<=gui->epoch.epochs[ i ].end_slot ) ) {
2590 0 : gui->epoch.epochs[ i ].my_skipped_slots++;
2591 0 : republish_skip_rate[ i ] = 1;
2592 0 : break;
2593 0 : }
2594 0 : }
2595 0 : }
2596 0 : }
2597 0 : }
2598 0 : } else {
2599 : /* publish new skipped slots */
2600 0 : fd_gui_slot_t * s = fd_gui_get_slot( gui, gui->summary.slot_completed );
2601 0 : while( s && s->slot>=prev_slot_completed ) {
2602 0 : fd_gui_slot_t * p = fd_gui_get_slot( gui, s->parent_slot );
2603 0 : if( FD_UNLIKELY( !p ) ) break;
2604 0 : for( ulong i=p->slot+1; i<s->slot; i++ ) {
2605 0 : fd_gui_slot_t * skipped = fd_gui_get_slot( gui, i );
2606 0 : if( FD_LIKELY( !skipped ) ) {
2607 0 : fd_gui_slot_t * p = fd_gui_get_parent_slot_on_fork( gui, gui->summary.slot_completed, i );
2608 0 : skipped = fd_gui_clear_slot( gui, i, p ? p->slot : ULONG_MAX );
2609 0 : }
2610 0 : skipped->skipped = 1;
2611 0 : fd_gui_printf_slot( gui, skipped->slot );
2612 0 : fd_http_server_ws_broadcast( gui->http );
2613 0 : skipped->must_republish = 0;
2614 0 : if( FD_LIKELY( skipped->mine ) ) {
2615 0 : for( ulong i=0UL; i<2UL; i++ ) {
2616 0 : if( FD_LIKELY( i>=gui->epoch.epochs[ i ].start_slot && i<=gui->epoch.epochs[ i ].end_slot ) ) {
2617 0 : gui->epoch.epochs[ i ].my_skipped_slots++;
2618 0 : republish_skip_rate[ i ] = 1;
2619 0 : break;
2620 0 : }
2621 0 : }
2622 0 : }
2623 0 : }
2624 0 : s = p;
2625 0 : }
2626 0 : }
2627 :
2628 0 : for( ulong i=0UL; i<2UL; i++ ) {
2629 0 : if( FD_LIKELY( republish_skip_rate[ i ] ) ) {
2630 0 : fd_gui_printf_skip_rate( gui, i );
2631 0 : fd_http_server_ws_broadcast( gui->http );
2632 0 : }
2633 0 : }
2634 0 : }
2635 :
2636 : #define SORT_NAME fd_gui_slot_staged_shred_event_evict_sort
2637 : #define SORT_KEY_T fd_gui_slot_staged_shred_event_t
2638 : #define SORT_BEFORE(a,b) (__extension__({ (void)(b); (a).slot==ULONG_MAX; }))
2639 : #include "../../util/tmpl/fd_sort.c"
2640 :
2641 : #define SORT_NAME fd_gui_slot_staged_shred_event_slot_sort
2642 0 : #define SORT_KEY_T fd_gui_slot_staged_shred_event_t
2643 0 : #define SORT_BEFORE(a,b) ((a).slot<(b).slot)
2644 : #include "../../util/tmpl/fd_sort.c"
2645 :
2646 : static void
2647 0 : fd_gui_handle_rooted_slot( fd_gui_t * gui, ulong root_slot ) {
2648 0 : ulong epoch_idx = fd_gui_current_epoch_idx( gui );
2649 0 : ulong epoch_start = gui->epoch.epochs[ epoch_idx ].start_slot;
2650 0 : ulong epoch_end = gui->epoch.epochs[ epoch_idx ].end_slot;
2651 :
2652 : /* Epoch boundary */
2653 0 : if( FD_UNLIKELY( gui->summary.late_votes_sz && epoch_idx!=ULONG_MAX && ( epoch_start>gui->summary.late_votes[ 0 ] || epoch_end<gui->summary.late_votes[ 0 ] ) ) ) {
2654 0 : gui->summary.late_votes_sz = 0;
2655 0 : }
2656 :
2657 : /* Epoch boundary or startup -- backfill history */
2658 0 : if( FD_UNLIKELY( epoch_idx!=ULONG_MAX && gui->summary.late_votes_sz==0UL ) ) {
2659 0 : for( ulong s=epoch_start; s<fd_ulong_min( root_slot, epoch_start+FD_GUI_SLOTS_CNT ); s++ ) {
2660 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, s );
2661 0 : if( FD_UNLIKELY( !slot || slot->level<FD_GUI_SLOT_LEVEL_ROOTED ) ) break;
2662 :
2663 0 : int in_current_epoch = epoch_idx!=ULONG_MAX && epoch_start<=s && epoch_end>=s;
2664 0 : if( FD_UNLIKELY( in_current_epoch && ( ( !slot->skipped && slot->vote_latency==UCHAR_MAX ) || ( slot->vote_latency!=UCHAR_MAX && slot->vote_latency>1UL ) ) ) ) {
2665 0 : fd_gui_try_insert_run_length_slot( gui->summary.late_votes, MAX_SLOTS_PER_EPOCH, &gui->summary.late_votes_sz, s );
2666 0 : }
2667 0 : }
2668 0 : }
2669 :
2670 : /* start at the new root and move backwards towards the old root,
2671 : rooting everything in-between */
2672 0 : for( ulong i=0UL; i<fd_ulong_min( root_slot, FD_GUI_SLOTS_CNT ); i++ ) {
2673 0 : ulong parent_slot = root_slot - i;
2674 :
2675 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, parent_slot );
2676 0 : if( FD_UNLIKELY( !slot ) ) break;
2677 :
2678 0 : if( FD_UNLIKELY( slot->slot!=parent_slot ) ) {
2679 0 : FD_LOG_ERR(( "_slot %lu i %lu we expect parent_slot %lu got slot->slot %lu", root_slot, i, parent_slot, slot->slot ));
2680 0 : }
2681 :
2682 0 : int in_current_epoch = epoch_idx!=ULONG_MAX && epoch_start<=slot->slot && epoch_end>=slot->slot;
2683 0 : if( FD_UNLIKELY( in_current_epoch && ( ( !slot->skipped && slot->vote_latency==UCHAR_MAX ) || ( slot->vote_latency!=UCHAR_MAX && slot->vote_latency>1UL ) ) ) ) {
2684 0 : fd_gui_try_insert_run_length_slot( gui->summary.late_votes, MAX_SLOTS_PER_EPOCH, &gui->summary.late_votes_sz, slot->slot );
2685 0 : }
2686 :
2687 0 : if( FD_UNLIKELY( slot->level>=FD_GUI_SLOT_LEVEL_ROOTED ) ) break;
2688 :
2689 : /* change notarization levels and rebroadcast */
2690 0 : slot->level = FD_GUI_SLOT_LEVEL_ROOTED;
2691 0 : fd_gui_printf_slot( gui, parent_slot );
2692 0 : fd_http_server_ws_broadcast( gui->http );
2693 0 : }
2694 :
2695 : /* archive root shred events. We want to avoid n^2 iteration here
2696 : since it can significantly slow things down. Instead, we copy
2697 : over all rooted shreds to a scratch space, stable sort by slot,
2698 : copy the sorted arrays to the shred history. */
2699 0 : ulong archive_cnt = 0UL;
2700 0 : ulong kept_cnt = 0UL;
2701 0 : ulong kept_before_next_cnt = 0UL;
2702 :
2703 0 : for( ulong i=gui->shreds.staged_head; i<gui->shreds.staged_tail; i++ ) {
2704 0 : fd_gui_slot_staged_shred_event_t const * src = &gui->shreds.staged[ i % FD_GUI_SHREDS_STAGING_SZ ];
2705 :
2706 0 : if( FD_UNLIKELY( gui->shreds.history_slot!=ULONG_MAX && src->slot<=gui->shreds.history_slot ) ) continue;
2707 :
2708 0 : if( FD_UNLIKELY( src->slot<=root_slot ) ) {
2709 0 : gui->shreds._staged_scratch[ archive_cnt++ ] = *src;
2710 0 : continue;
2711 0 : }
2712 :
2713 : /* The entries from the staging area are evicted by setting their
2714 : slot field to ULONG MAX, then sorting the staging area.
2715 :
2716 : IMPORTANT: this sort needs to be stable since we always keep
2717 : valid un-broadcast events at the end of the ring buffer */
2718 0 : if( FD_UNLIKELY( i<gui->shreds.staged_next_broadcast ) ) kept_before_next_cnt++;
2719 0 : gui->shreds._staged_scratch2[ kept_cnt++ ] = *src;
2720 0 : }
2721 :
2722 : /* copy shred events to archive */
2723 0 : for( ulong j=0UL; j<kept_cnt; j++ ) gui->shreds.staged[ (gui->shreds.staged_head + j) % FD_GUI_SHREDS_STAGING_SZ ] = gui->shreds._staged_scratch2[ j ];
2724 0 : gui->shreds.staged_tail = gui->shreds.staged_head + kept_cnt;
2725 : /* Remap next_broadcast to preserve continuity after compaction */
2726 0 : gui->shreds.staged_next_broadcast = gui->shreds.staged_head + kept_before_next_cnt;
2727 :
2728 : /* sort scratch by slot increasing */
2729 0 : if( FD_LIKELY( archive_cnt ) ) {
2730 0 : fd_gui_slot_staged_shred_event_slot_sort_stable( gui->shreds._staged_scratch, archive_cnt, gui->shreds._staged_scratch2 );
2731 :
2732 0 : for( ulong i=0UL; i<archive_cnt; i++ ) {
2733 0 : if( FD_UNLIKELY( gui->shreds._staged_scratch[ i ].slot!=gui->shreds.history_slot ) ) {
2734 0 : fd_gui_slot_t * prev_slot = fd_gui_get_slot( gui, gui->shreds.history_slot );
2735 0 : if( FD_LIKELY( prev_slot ) ) prev_slot->shreds.end_offset = gui->shreds.history_tail;
2736 :
2737 0 : gui->shreds.history_slot = gui->shreds._staged_scratch[ i ].slot;
2738 :
2739 0 : fd_gui_slot_t * next_slot = fd_gui_get_slot( gui, gui->shreds.history_slot );
2740 0 : if( FD_LIKELY( next_slot ) ) next_slot->shreds.start_offset = gui->shreds.history_tail;
2741 0 : }
2742 :
2743 0 : gui->shreds.history[ gui->shreds.history_tail % FD_GUI_SHREDS_HISTORY_SZ ].timestamp = gui->shreds._staged_scratch[ i ].timestamp;
2744 0 : gui->shreds.history[ gui->shreds.history_tail % FD_GUI_SHREDS_HISTORY_SZ ].shred_idx = gui->shreds._staged_scratch[ i ].shred_idx;
2745 0 : gui->shreds.history[ gui->shreds.history_tail % FD_GUI_SHREDS_HISTORY_SZ ].event = gui->shreds._staged_scratch[ i ].event;
2746 :
2747 0 : gui->shreds.history_tail++;
2748 0 : }
2749 0 : }
2750 :
2751 0 : gui->summary.slot_rooted = root_slot;
2752 0 : fd_gui_printf_root_slot( gui );
2753 0 : fd_http_server_ws_broadcast( gui->http );
2754 0 : }
2755 :
2756 : void
2757 : fd_gui_handle_notarization_update( fd_gui_t * gui,
2758 0 : fd_tower_slot_confirmed_t const * notar ) {
2759 0 : if( FD_UNLIKELY( notar->slot!=ULONG_MAX && gui->summary.slot_optimistically_confirmed!=notar->slot && notar->kind==FD_TOWER_SLOT_CONFIRMED_CLUSTER ) ) {
2760 0 : fd_gui_handle_optimistically_confirmed_slot( gui, notar->slot );
2761 0 : }
2762 0 : }
2763 :
2764 : static inline void
2765 0 : try_publish_vote_status( fd_gui_t * gui, ulong _slot ) {
2766 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
2767 :
2768 : /* For unstaked nodes, slot->vote_slot will always be ULONG_MAX */
2769 0 : if( FD_UNLIKELY( !slot || slot->vote_slot==ULONG_MAX || slot->reset_slot==ULONG_MAX ) ) return;
2770 :
2771 0 : ulong vote_distance = slot->reset_slot-slot->vote_slot;
2772 0 : if( FD_LIKELY( vote_distance<FD_GUI_SLOTS_CNT ) ) {
2773 0 : for( ulong s=slot->vote_slot; s<slot->reset_slot; s++ ) {
2774 0 : fd_gui_slot_t * cur = fd_gui_get_slot( gui, s );
2775 0 : if( FD_UNLIKELY( cur && cur->skipped ) ) vote_distance--;
2776 0 : }
2777 0 : }
2778 :
2779 0 : if( FD_UNLIKELY( gui->summary.vote_distance!=vote_distance ) ) {
2780 0 : gui->summary.vote_distance = vote_distance;
2781 0 : fd_gui_printf_vote_distance( gui );
2782 0 : fd_http_server_ws_broadcast( gui->http );
2783 0 : }
2784 :
2785 0 : if( FD_LIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_NON_VOTING ) ) {
2786 0 : if( FD_UNLIKELY( slot->vote_slot==ULONG_MAX || vote_distance>150UL ) ) {
2787 0 : if( FD_UNLIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_DELINQUENT ) ) {
2788 0 : gui->summary.vote_state = FD_GUI_VOTE_STATE_DELINQUENT;
2789 0 : fd_gui_printf_vote_state( gui );
2790 0 : fd_http_server_ws_broadcast( gui->http );
2791 0 : }
2792 0 : } else {
2793 0 : if( FD_UNLIKELY( gui->summary.vote_state!=FD_GUI_VOTE_STATE_VOTING ) ) {
2794 0 : gui->summary.vote_state = FD_GUI_VOTE_STATE_VOTING;
2795 0 : fd_gui_printf_vote_state( gui );
2796 0 : fd_http_server_ws_broadcast( gui->http );
2797 0 : }
2798 0 : }
2799 0 : }
2800 0 : }
2801 :
2802 : /* fd_gui_handle_tower_update handles updates from the tower tile, which
2803 : manages consensus related fork switching, rooting, slot confirmation. */
2804 : void
2805 : fd_gui_handle_tower_update( fd_gui_t * gui,
2806 : fd_tower_slot_done_t const * tower,
2807 0 : long now ) {
2808 0 : (void)now;
2809 :
2810 0 : if( FD_UNLIKELY( tower->active_fork_cnt!=gui->summary.active_fork_cnt ) ) {
2811 0 : gui->summary.active_fork_cnt = tower->active_fork_cnt;
2812 0 : fd_gui_printf_active_fork_cnt( gui );
2813 0 : fd_http_server_ws_broadcast( gui->http );
2814 0 : }
2815 :
2816 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, tower->replay_slot );
2817 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, tower->replay_slot, ULONG_MAX );
2818 0 : slot->reset_slot = tower->reset_slot;
2819 :
2820 0 : try_publish_vote_status( gui, tower->replay_slot );
2821 :
2822 0 : if( FD_LIKELY( gui->summary.slot_reset!=tower->reset_slot ) ) {
2823 0 : gui->summary.slot_reset = tower->reset_slot;
2824 0 : fd_gui_printf_reset_slot( gui );
2825 0 : fd_http_server_ws_broadcast( gui->http );
2826 0 : }
2827 :
2828 0 : if( FD_UNLIKELY( tower->vote_acct_bal!=ULONG_MAX && gui->summary.vote_account_balance!=tower->vote_acct_bal ) ) {
2829 0 : gui->summary.vote_account_balance = tower->vote_acct_bal;
2830 0 : fd_gui_printf_vote_balance( gui );
2831 0 : fd_http_server_ws_broadcast( gui->http );
2832 0 : }
2833 :
2834 : /* update slot history vote latencies with new votes */
2835 0 : for( ulong i=0UL; i<tower->tower_cnt; i++ ) {
2836 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, tower->tower[ i ].slot );
2837 0 : if( FD_UNLIKELY( slot && slot->vote_latency!=tower->tower[ i ].latency ) ) {
2838 0 : slot->vote_latency = tower->tower[ i ].latency;
2839 0 : fd_gui_printf_slot( gui, slot->slot );
2840 0 : fd_http_server_ws_broadcast( gui->http );
2841 0 : }
2842 0 : if( FD_UNLIKELY( i+1UL>=tower->tower_cnt ) ) break;
2843 0 : for( ulong s=tower->tower[ i ].slot+1UL; s<tower->tower[ i+1 ].slot; s++ ) {
2844 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, s );
2845 0 : if( FD_LIKELY( slot && slot->vote_latency!=UCHAR_MAX ) ) {
2846 0 : slot->vote_latency = UCHAR_MAX;
2847 0 : fd_gui_printf_slot( gui, slot->slot );
2848 0 : fd_http_server_ws_broadcast( gui->http );
2849 0 : }
2850 0 : }
2851 0 : }
2852 0 : }
2853 :
2854 : void
2855 : fd_gui_handle_replay_update( fd_gui_t * gui,
2856 : fd_gui_slot_completed_t * slot_completed,
2857 : fd_hash_t const * block_hash,
2858 : ulong vote_slot,
2859 : ulong storage_slot,
2860 : ulong rooted_slot,
2861 : ulong identity_balance,
2862 0 : long now ) {
2863 0 : (void)now;
2864 :
2865 0 : if( FD_LIKELY( rooted_slot!=ULONG_MAX && gui->summary.slot_rooted!=rooted_slot ) ) {
2866 0 : fd_gui_handle_rooted_slot( gui, rooted_slot );
2867 0 : }
2868 :
2869 0 : if( FD_LIKELY( gui->summary.slot_storage!=storage_slot ) ) {
2870 0 : gui->summary.slot_storage = storage_slot;
2871 0 : fd_gui_printf_storage_slot( gui );
2872 0 : fd_http_server_ws_broadcast( gui->http );
2873 0 : }
2874 :
2875 0 : if( FD_UNLIKELY( identity_balance!=ULONG_MAX && gui->summary.identity_account_balance!=identity_balance ) ) {
2876 0 : gui->summary.identity_account_balance = identity_balance;
2877 :
2878 0 : fd_gui_printf_identity_balance( gui );
2879 0 : fd_http_server_ws_broadcast( gui->http );
2880 0 : }
2881 :
2882 0 : if( FD_UNLIKELY( gui->summary.boot_progress.catching_up_first_replay_slot==ULONG_MAX ) ) {
2883 0 : gui->summary.boot_progress.catching_up_first_replay_slot = slot_completed->slot;
2884 0 : }
2885 :
2886 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, slot_completed->slot );
2887 0 : if( FD_UNLIKELY( slot ) ) {
2888 : /* Its possible that this slot was labeled as skipped by another
2889 : consensus fork at some point in the past. In this case no need to
2890 : clear it, but we should update parent_slot */
2891 0 : slot->parent_slot = slot_completed->parent_slot;
2892 0 : } else {
2893 0 : slot = fd_gui_clear_slot( gui, slot_completed->slot, slot_completed->parent_slot );
2894 0 : }
2895 :
2896 0 : if( FD_UNLIKELY( slot->mine ) ) {
2897 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, slot->slot );
2898 0 : if( FD_LIKELY( lslot ) ) fd_memcpy( lslot->block_hash.uc, block_hash->uc, sizeof(fd_hash_t) );
2899 0 : }
2900 :
2901 0 : slot->completed_time = slot_completed->completed_time;
2902 0 : slot->parent_slot = slot_completed->parent_slot;
2903 0 : slot->max_compute_units = fd_uint_if( slot_completed->max_compute_units==UINT_MAX, slot->max_compute_units, slot_completed->max_compute_units );
2904 0 : if( FD_LIKELY( slot->level<FD_GUI_SLOT_LEVEL_COMPLETED ) ) {
2905 : /* Typically a slot goes from INCOMPLETE to COMPLETED but it can
2906 : happen that it starts higher. One such case is when we
2907 : optimistically confirm a higher slot that skips this one, but
2908 : then later we replay this one anyway to track the bank fork. */
2909 :
2910 0 : if( FD_LIKELY( gui->summary.slot_optimistically_confirmed!=ULONG_MAX && slot->slot<gui->summary.slot_optimistically_confirmed ) ) {
2911 : /* Cluster might have already optimistically confirmed by the time
2912 : we finish replaying it. */
2913 0 : slot->level = FD_GUI_SLOT_LEVEL_OPTIMISTICALLY_CONFIRMED;
2914 0 : } else {
2915 0 : slot->level = FD_GUI_SLOT_LEVEL_COMPLETED;
2916 0 : }
2917 0 : }
2918 0 : slot->total_txn_cnt = slot_completed->total_txn_cnt;
2919 0 : slot->vote_txn_cnt = slot_completed->vote_txn_cnt;
2920 0 : slot->failed_txn_cnt = slot_completed->failed_txn_cnt;
2921 0 : slot->nonvote_failed_txn_cnt = slot_completed->nonvote_failed_txn_cnt;
2922 0 : slot->transaction_fee = slot_completed->transaction_fee;
2923 0 : slot->priority_fee = slot_completed->priority_fee;
2924 0 : slot->tips = slot_completed->tips;
2925 0 : slot->compute_units = slot_completed->compute_units;
2926 0 : slot->shred_cnt = slot_completed->shred_cnt;
2927 0 : slot->vote_slot = vote_slot;
2928 :
2929 0 : try_publish_vote_status( gui, slot_completed->slot );
2930 :
2931 0 : if( FD_UNLIKELY( gui->epoch.has_epoch[ 0 ] && slot->slot==gui->epoch.epochs[ 0 ].end_slot ) ) {
2932 0 : gui->epoch.epochs[ 0 ].end_time = slot->completed_time;
2933 0 : } else if( FD_UNLIKELY( gui->epoch.has_epoch[ 1 ] && slot->slot==gui->epoch.epochs[ 1 ].end_slot ) ) {
2934 0 : gui->epoch.epochs[ 1 ].end_time = slot->completed_time;
2935 0 : }
2936 :
2937 : /* Broadcast new skip rate if one of our slots got completed. */
2938 0 : if( FD_LIKELY( slot->mine ) ) {
2939 0 : for( ulong i=0UL; i<2UL; i++ ) {
2940 0 : if( FD_LIKELY( slot->slot>=gui->epoch.epochs[ i ].start_slot && slot->slot<=gui->epoch.epochs[ i ].end_slot ) ) {
2941 0 : fd_gui_printf_skip_rate( gui, i );
2942 0 : fd_http_server_ws_broadcast( gui->http );
2943 0 : break;
2944 0 : }
2945 0 : }
2946 0 : }
2947 :
2948 : /* We'll treat the latest slot_complete from replay as the reset slot.
2949 : We get an explicit reset_slot from tower, but that message may come
2950 : in before we get the slot_complete from replay. */
2951 0 : if( FD_UNLIKELY( gui->summary.slot_completed!=slot->slot ) ) {
2952 0 : fd_gui_handle_reset_slot( gui, slot->slot, now );
2953 0 : }
2954 :
2955 : /* Add a "slot complete" event for all of the shreds in this slot */
2956 0 : if( FD_UNLIKELY( slot->shred_cnt > FD_GUI_MAX_SHREDS_PER_BLOCK ) ) FD_LOG_ERR(( "unexpected shred_cnt=%lu", (ulong)slot->shred_cnt ));
2957 0 : fd_gui_slot_staged_shred_event_t * slot_complete_event = &gui->shreds.staged[ gui->shreds.staged_tail % FD_GUI_SHREDS_STAGING_SZ ];
2958 0 : gui->shreds.staged_tail++;
2959 0 : slot_complete_event->event = FD_GUI_SLOT_SHRED_SHRED_SLOT_COMPLETE;
2960 0 : slot_complete_event->timestamp = slot_completed->completed_time;
2961 0 : slot_complete_event->shred_idx = USHORT_MAX;
2962 0 : slot_complete_event->slot = slot->slot;
2963 :
2964 : /* addresses racey behavior if we just sample at 400ms */
2965 0 : if( FD_LIKELY( gui->summary.slot_caught_up!=ULONG_MAX ) ) {
2966 0 : fd_topo_tile_t * repair = &gui->topo->tiles[ fd_topo_find_tile( gui->topo, "repair", 0UL ) ];
2967 0 : volatile ulong const * repair_metrics = fd_metrics_tile( repair->metrics );
2968 0 : ulong slot = repair_metrics[ MIDX( COUNTER, REPAIR, REPAIRED_SLOTS ) ];
2969 0 : fd_gui_handle_repair_slot( gui, slot, now );
2970 0 : }
2971 0 : }
2972 :
2973 : void
2974 : fd_gui_plugin_message( fd_gui_t * gui,
2975 : ulong plugin_msg,
2976 : uchar const * msg,
2977 0 : long now ) {
2978 :
2979 0 : switch( plugin_msg ) {
2980 0 : case FD_PLUGIN_MSG_SLOT_ROOTED:
2981 0 : fd_gui_handle_rooted_slot_legacy( gui, (ulong *)msg );
2982 0 : break;
2983 0 : case FD_PLUGIN_MSG_SLOT_OPTIMISTICALLY_CONFIRMED:
2984 0 : fd_gui_handle_optimistically_confirmed_slot( gui, ((ulong *)msg)[0] );
2985 0 : break;
2986 0 : case FD_PLUGIN_MSG_SLOT_COMPLETED: {
2987 0 : fd_gui_handle_completed_slot( gui, (ulong *)msg, now );
2988 0 : break;
2989 0 : }
2990 0 : case FD_PLUGIN_MSG_LEADER_SCHEDULE: {
2991 0 : FD_STATIC_ASSERT( sizeof(fd_stake_weight_msg_t)==6*sizeof(ulong), "new fields breaks things" );
2992 0 : fd_gui_handle_leader_schedule( gui, (fd_stake_weight_msg_t *)msg, now );
2993 0 : break;
2994 0 : }
2995 0 : case FD_PLUGIN_MSG_SLOT_START: {
2996 0 : ulong slot = ((ulong *)msg)[ 0 ];
2997 0 : ulong parent_slot = ((ulong *)msg)[ 1 ];
2998 0 : fd_gui_handle_slot_start( gui, slot, parent_slot, now );
2999 0 : break;
3000 0 : }
3001 0 : case FD_PLUGIN_MSG_SLOT_END: {
3002 0 : ulong slot = ((ulong *)msg)[ 0 ];
3003 0 : ulong cus_used = ((ulong *)msg)[ 1 ];
3004 0 : fd_gui_handle_slot_end( gui, slot, cus_used, now );
3005 0 : break;
3006 0 : }
3007 0 : case FD_PLUGIN_MSG_GOSSIP_UPDATE: {
3008 0 : fd_gui_handle_gossip_update( gui, msg );
3009 0 : break;
3010 0 : }
3011 0 : case FD_PLUGIN_MSG_VOTE_ACCOUNT_UPDATE: {
3012 0 : fd_gui_handle_vote_account_update( gui, msg );
3013 0 : break;
3014 0 : }
3015 0 : case FD_PLUGIN_MSG_VALIDATOR_INFO: {
3016 0 : fd_gui_handle_validator_info_update( gui, msg );
3017 0 : break;
3018 0 : }
3019 0 : case FD_PLUGIN_MSG_SLOT_RESET: {
3020 0 : fd_gui_handle_reset_slot_legacy( gui, (ulong *)msg, now );
3021 0 : break;
3022 0 : }
3023 0 : case FD_PLUGIN_MSG_BALANCE: {
3024 0 : fd_gui_handle_balance_update( gui, (ulong *)msg );
3025 0 : break;
3026 0 : }
3027 0 : case FD_PLUGIN_MSG_START_PROGRESS: {
3028 0 : fd_gui_handle_start_progress( gui, msg );
3029 0 : break;
3030 0 : }
3031 0 : case FD_PLUGIN_MSG_GENESIS_HASH_KNOWN: {
3032 0 : fd_gui_handle_genesis_hash( gui, msg );
3033 0 : break;
3034 0 : }
3035 0 : case FD_PLUGIN_MSG_BLOCK_ENGINE_UPDATE: {
3036 0 : fd_gui_handle_block_engine_update( gui, msg );
3037 0 : break;
3038 0 : }
3039 0 : default:
3040 0 : FD_LOG_ERR(( "Unhandled plugin msg: 0x%lx", plugin_msg ));
3041 0 : break;
3042 0 : }
3043 0 : }
3044 :
3045 : void
3046 : fd_gui_became_leader( fd_gui_t * gui,
3047 : ulong _slot,
3048 : long start_time_nanos,
3049 : long end_time_nanos,
3050 : ulong max_compute_units,
3051 0 : ulong max_microblocks ) {
3052 0 : if( FD_LIKELY( gui->summary.is_full_client && gui->leader_slot!=ULONG_MAX ) ) {
3053 : /* stop sampling for other leader slot in progress */
3054 0 : fd_gui_handle_slot_end( gui, gui->leader_slot, ULONG_MAX, start_time_nanos );
3055 0 : }
3056 :
3057 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
3058 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, ULONG_MAX );
3059 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, _slot );
3060 0 : if( FD_UNLIKELY( !lslot ) ) return;
3061 :
3062 0 : slot->max_compute_units = (uint)max_compute_units;
3063 0 : lslot->leader_start_time = fd_long_if( lslot->leader_start_time==LONG_MAX, start_time_nanos, lslot->leader_start_time );
3064 0 : lslot->leader_end_time = end_time_nanos;
3065 0 : if( FD_LIKELY( lslot->txs.microblocks_upper_bound==USHORT_MAX ) ) lslot->txs.microblocks_upper_bound = (ushort)max_microblocks;
3066 :
3067 0 : if( FD_UNLIKELY( gui->summary.is_full_client ) ) fd_gui_handle_slot_start( gui, slot->slot, slot->parent_slot, start_time_nanos );
3068 0 : }
3069 :
3070 : void
3071 : fd_gui_unbecame_leader( fd_gui_t * gui,
3072 : ulong _slot,
3073 : fd_done_packing_t const * done_packing,
3074 0 : long now ) {
3075 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
3076 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, ULONG_MAX );
3077 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, _slot );
3078 0 : if( FD_LIKELY( !lslot ) ) return;
3079 0 : lslot->txs.microblocks_upper_bound = (uint)done_packing->microblocks_in_slot;
3080 0 : fd_memcpy( lslot->scheduler_stats, done_packing, sizeof(fd_done_packing_t) );
3081 :
3082 : /* fd_gui_handle_slot_end may have already been called in response to
3083 : a "became_leader" message for a subseqeunt slot. */
3084 0 : if( FD_UNLIKELY( gui->summary.is_full_client && gui->leader_slot==_slot ) ) fd_gui_handle_slot_end( gui, slot->slot, ULONG_MAX, now );
3085 :
3086 0 : lslot->unbecame_leader = 1;
3087 0 : }
3088 :
3089 : void
3090 : fd_gui_microblock_execution_begin( fd_gui_t * gui,
3091 : long now,
3092 : ulong _slot,
3093 : fd_txn_e_t * txns,
3094 : ulong txn_cnt,
3095 : uint microblock_idx,
3096 0 : ulong pack_txn_idx ) {
3097 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
3098 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, ULONG_MAX );
3099 :
3100 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, _slot );
3101 0 : if( FD_UNLIKELY( !lslot ) ) return;
3102 :
3103 0 : lslot->leader_start_time = fd_long_if( lslot->leader_start_time==LONG_MAX, now, lslot->leader_start_time );
3104 :
3105 0 : if( FD_UNLIKELY( lslot->txs.start_offset==ULONG_MAX ) ) lslot->txs.start_offset = pack_txn_idx;
3106 0 : else lslot->txs.start_offset = fd_ulong_min( lslot->txs.start_offset, pack_txn_idx );
3107 :
3108 0 : gui->pack_txn_idx = fd_ulong_max( gui->pack_txn_idx, pack_txn_idx+txn_cnt-1UL );
3109 :
3110 0 : for( ulong i=0UL; i<txn_cnt; i++ ) {
3111 0 : fd_txn_p_t * txn_payload = txns[ i ].txnp;
3112 0 : fd_txn_t * txn = TXN( txn_payload );
3113 :
3114 0 : ulong sig_rewards = FD_PACK_FEE_PER_SIGNATURE * txn->signature_cnt;
3115 0 : ulong priority_rewards = ULONG_MAX;
3116 0 : ulong requested_execution_cus = ULONG_MAX;
3117 0 : ulong precompile_sigs = ULONG_MAX;
3118 0 : ulong requested_loaded_accounts_data_cost = ULONG_MAX;
3119 0 : uint _flags;
3120 0 : ulong cost_estimate = fd_pack_compute_cost( txn, txn_payload->payload, &_flags, &requested_execution_cus, &priority_rewards, &precompile_sigs, &requested_loaded_accounts_data_cost );
3121 0 : sig_rewards += FD_PACK_FEE_PER_SIGNATURE * precompile_sigs;
3122 0 : sig_rewards = sig_rewards * FD_PACK_TXN_FEE_BURN_PCT / 100UL;
3123 :
3124 0 : fd_gui_txn_t * txn_entry = gui->txs[ (pack_txn_idx + i)%FD_GUI_TXN_HISTORY_SZ ];
3125 0 : fd_memcpy(txn_entry->signature, txn_payload->payload + txn->signature_off, FD_SHA512_HASH_SZ);
3126 0 : txn_entry->timestamp_arrival_nanos = txn_payload->scheduler_arrival_time_nanos;
3127 0 : txn_entry->compute_units_requested = cost_estimate & 0x1FFFFFU;
3128 0 : txn_entry->priority_fee = priority_rewards;
3129 0 : txn_entry->transaction_fee = sig_rewards;
3130 0 : txn_entry->timestamp_delta_start_nanos = (int)(now - lslot->leader_start_time);
3131 0 : txn_entry->source_ipv4 = txn_payload->source_ipv4;
3132 0 : txn_entry->source_tpu = txn_payload->source_tpu;
3133 0 : txn_entry->microblock_idx = microblock_idx;
3134 0 : txn_entry->flags |= (uchar)FD_GUI_TXN_FLAGS_STARTED;
3135 0 : txn_entry->flags &= (uchar)(~(uchar)(FD_GUI_TXN_FLAGS_IS_SIMPLE_VOTE | FD_GUI_TXN_FLAGS_FROM_BUNDLE));
3136 0 : txn_entry->flags |= (uchar)fd_uint_if(txn_payload->flags & FD_TXN_P_FLAGS_IS_SIMPLE_VOTE, FD_GUI_TXN_FLAGS_IS_SIMPLE_VOTE, 0U);
3137 0 : txn_entry->flags |= (uchar)fd_uint_if((txn_payload->flags & FD_TXN_P_FLAGS_BUNDLE) || (txn_payload->flags & FD_TXN_P_FLAGS_INITIALIZER_BUNDLE), FD_GUI_TXN_FLAGS_FROM_BUNDLE, 0U);
3138 0 : }
3139 :
3140 : /* At the moment, bank publishes at most 1 transaction per microblock,
3141 : even if it received microblocks with multiple transactions
3142 : (i.e. a bundle). This means that we need to calculate microblock
3143 : count here based on the transaction count. */
3144 0 : lslot->txs.begin_microblocks += (uint)txn_cnt;
3145 0 : }
3146 :
3147 : void
3148 : fd_gui_microblock_execution_end( fd_gui_t * gui,
3149 : long now,
3150 : ulong bank_idx,
3151 : ulong _slot,
3152 : ulong txn_cnt,
3153 : fd_txn_p_t * txns,
3154 : ulong pack_txn_idx,
3155 : uchar txn_start_pct,
3156 : uchar txn_load_end_pct,
3157 : uchar txn_end_pct,
3158 : uchar txn_preload_end_pct,
3159 0 : ulong tips ) {
3160 0 : if( FD_UNLIKELY( 1UL!=txn_cnt ) ) FD_LOG_ERR(( "gui expects 1 txn per microblock from bank, found %lu", txn_cnt ));
3161 :
3162 0 : fd_gui_slot_t * slot = fd_gui_get_slot( gui, _slot );
3163 0 : if( FD_UNLIKELY( !slot ) ) slot = fd_gui_clear_slot( gui, _slot, ULONG_MAX );
3164 :
3165 0 : fd_gui_leader_slot_t * lslot = fd_gui_get_leader_slot( gui, _slot );
3166 0 : if( FD_UNLIKELY( !lslot ) ) return;
3167 :
3168 0 : lslot->leader_start_time = fd_long_if( lslot->leader_start_time==LONG_MAX, now, lslot->leader_start_time );
3169 :
3170 0 : if( FD_UNLIKELY( lslot->txs.end_offset==ULONG_MAX ) ) lslot->txs.end_offset = pack_txn_idx + txn_cnt;
3171 0 : else lslot->txs.end_offset = fd_ulong_max( lslot->txs.end_offset, pack_txn_idx+txn_cnt );
3172 :
3173 0 : gui->pack_txn_idx = fd_ulong_max( gui->pack_txn_idx, pack_txn_idx+txn_cnt-1UL );
3174 :
3175 0 : for( ulong i=0UL; i<txn_cnt; i++ ) {
3176 0 : fd_txn_p_t * txn_p = &txns[ i ];
3177 :
3178 0 : fd_gui_txn_t * txn_entry = gui->txs[ (pack_txn_idx + i)%FD_GUI_TXN_HISTORY_SZ ];
3179 0 : txn_entry->bank_idx = bank_idx & 0x3FU;
3180 0 : txn_entry->compute_units_consumed = txn_p->execle_cu.actual_consumed_cus & 0x1FFFFFU;
3181 0 : txn_entry->error_code = (txn_p->flags >> 24) & 0x3FU;
3182 0 : txn_entry->timestamp_delta_end_nanos = (int)(now - lslot->leader_start_time);
3183 0 : txn_entry->txn_start_pct = txn_start_pct;
3184 0 : txn_entry->txn_load_end_pct = txn_load_end_pct;
3185 0 : txn_entry->txn_end_pct = txn_end_pct;
3186 0 : txn_entry->txn_preload_end_pct = txn_preload_end_pct;
3187 0 : txn_entry->tips = tips;
3188 0 : txn_entry->flags |= (uchar)FD_GUI_TXN_FLAGS_ENDED;
3189 0 : txn_entry->flags &= (uchar)(~(uchar)FD_GUI_TXN_FLAGS_LANDED_IN_BLOCK);
3190 0 : txn_entry->flags |= (uchar)fd_uint_if(txn_p->flags & FD_TXN_P_FLAGS_EXECUTE_SUCCESS, FD_GUI_TXN_FLAGS_LANDED_IN_BLOCK, 0U);
3191 0 : }
3192 :
3193 0 : lslot->txs.end_microblocks = lslot->txs.end_microblocks + (uint)txn_cnt;
3194 0 : }
|