Logo AND Algorithmique Numérique Distribuée

Public GIT Repository
+ MPI_Sendrecv()
[simgrid.git] / src / smpi / smpi_global.c
1 #include <stdio.h>
2
3 #include "private.h"
4
5 XBT_LOG_NEW_CATEGORY(smpi, "All SMPI categories");
6
7 XBT_LOG_NEW_DEFAULT_SUBCATEGORY(smpi_kernel, smpi,
8                                 "Logging specific to SMPI (kernel)");
9
10 smpi_global_t smpi_global = NULL;
11
12 void *smpi_request_new(void);
13
14 void *smpi_request_new()
15 {
16   smpi_mpi_request_t request = xbt_new(s_smpi_mpi_request_t, 1);
17
18   request->buf = NULL;
19   request->completed = 0;
20   request->mutex = SIMIX_mutex_init();
21   request->cond = SIMIX_cond_init();
22   request->data = NULL;
23   request->forward = 0;
24
25   return request;
26 }
27
28 void smpi_request_free(void *pointer);
29
30 void smpi_request_free(void *pointer)
31 {
32
33   smpi_mpi_request_t request = pointer;
34
35   SIMIX_cond_destroy(request->cond);
36   SIMIX_mutex_destroy(request->mutex);
37   xbt_free(request);
38
39   return;
40 }
41
42 void smpi_request_reset(void *pointer);
43
44 void smpi_request_reset(void *pointer)
45 {
46   smpi_mpi_request_t request = pointer;
47
48   request->buf = NULL;
49   request->completed = 0;
50   request->consumed = 0;
51   request->data = NULL;
52   request->forward = 0;
53
54   return;
55 }
56
57
58 void *smpi_message_new(void);
59
60 void *smpi_message_new()
61 {
62   smpi_received_message_t message = xbt_new(s_smpi_received_message_t, 1);
63   message->buf = NULL;
64   return message;
65 }
66
67 void smpi_message_free(void *pointer);
68
69 void smpi_message_free(void *pointer)
70 {
71   xbt_free(pointer);
72   return;
73 }
74
75 void smpi_message_reset(void *pointer);
76
77 void smpi_message_reset(void *pointer)
78 {
79   smpi_received_message_t message = pointer;
80   message->buf = NULL;
81   return;
82 }
83
84 int smpi_create_request(void *buf, int count, smpi_mpi_datatype_t datatype,
85                         int src, int dst, int tag,
86                         smpi_mpi_communicator_t comm,
87                         smpi_mpi_request_t * requestptr)
88 {
89   int retval = MPI_SUCCESS;
90
91   smpi_mpi_request_t request = NULL;
92
93   // parameter checking prob belongs in smpi_mpi, but this is less repeat code
94   if (NULL == buf) {
95     retval = MPI_ERR_INTERN;
96   } else if (0 > count) {
97     retval = MPI_ERR_COUNT;
98   } else if (NULL == datatype) {
99     retval = MPI_ERR_TYPE;
100   } else if (MPI_ANY_SOURCE != src && (0 > src || comm->size <= src)) {
101     retval = MPI_ERR_RANK;
102   } else if (0 > dst || comm->size <= dst) {
103     retval = MPI_ERR_RANK;
104   } else if (MPI_ANY_TAG != tag && 0 > tag) {
105     retval = MPI_ERR_TAG;
106   } else if (NULL == comm) {
107     retval = MPI_ERR_COMM;
108   } else if (NULL == requestptr) {
109     retval = MPI_ERR_ARG;
110   } else {
111     request = xbt_mallocator_get(smpi_global->request_mallocator);
112     request->comm = comm;
113     request->src = src;
114     request->dst = dst;
115     request->tag = tag;
116     request->buf = buf;
117     request->datatype = datatype;
118     request->count = count;
119
120     *requestptr = request;
121   }
122   return retval;
123 }
124
125 /* FIXME: understand what they do and put the prototypes in a header file (live in smpi_base.c) */
126 void smpi_mpi_land_func(void *a, void *b, int *length,
127                         MPI_Datatype * datatype);
128 void smpi_mpi_sum_func(void *a, void *b, int *length,
129                        MPI_Datatype * datatype);
130 void smpi_mpi_prod_func(void *a, void *b, int *length,
131                        MPI_Datatype * datatype);
132 void smpi_mpi_min_func(void *a, void *b, int *length,
133                        MPI_Datatype * datatype);
134 void smpi_mpi_max_func(void *a, void *b, int *length,
135                        MPI_Datatype * datatype);
136
137 void smpi_global_init()
138 {
139   int i;
140
141   /* Connect our log channels: that must be done manually under windows */
142 #ifdef XBT_LOG_CONNECT
143   XBT_LOG_CONNECT(smpi_base, smpi);
144   XBT_LOG_CONNECT(smpi_bench, smpi);
145   XBT_LOG_CONNECT(smpi_kernel, smpi);
146   XBT_LOG_CONNECT(smpi_mpi, smpi);
147   XBT_LOG_CONNECT(smpi_receiver, smpi);
148   XBT_LOG_CONNECT(smpi_sender, smpi);
149   XBT_LOG_CONNECT(smpi_util, smpi);
150 #endif
151
152   smpi_global = xbt_new(s_smpi_global_t, 1);
153
154   // mallocators
155   smpi_global->request_mallocator =
156     xbt_mallocator_new(SMPI_REQUEST_MALLOCATOR_SIZE, smpi_request_new,
157                        smpi_request_free, smpi_request_reset);
158   smpi_global->message_mallocator =
159     xbt_mallocator_new(SMPI_MESSAGE_MALLOCATOR_SIZE, smpi_message_new,
160                        smpi_message_free, smpi_message_reset);
161
162   smpi_global->process_count = SIMIX_process_count();
163   DEBUG1("There is %d processes", smpi_global->process_count);
164
165   // sender/receiver processes
166   smpi_global->main_processes =
167     xbt_new(smx_process_t, smpi_global->process_count);
168
169   // timers
170   smpi_global->timer = xbt_os_timer_new();
171   smpi_global->timer_mutex = SIMIX_mutex_init();
172   smpi_global->timer_cond = SIMIX_cond_init();
173
174   smpi_global->do_once_duration_nodes = NULL;
175   smpi_global->do_once_duration = NULL;
176   smpi_global->do_once_mutex = SIMIX_mutex_init();
177
178
179   smpi_mpi_global = xbt_new(s_smpi_mpi_global_t, 1);
180
181   // global communicator
182   smpi_mpi_global->mpi_comm_world = xbt_new(s_smpi_mpi_communicator_t, 1);
183   smpi_mpi_global->mpi_comm_world->size = smpi_global->process_count;
184   smpi_mpi_global->mpi_comm_world->barrier_count = 0;
185   smpi_mpi_global->mpi_comm_world->barrier_mutex = SIMIX_mutex_init();
186   smpi_mpi_global->mpi_comm_world->barrier_cond = SIMIX_cond_init();
187   smpi_mpi_global->mpi_comm_world->rank_to_index_map =
188     xbt_new(int, smpi_global->process_count);
189   smpi_mpi_global->mpi_comm_world->index_to_rank_map =
190     xbt_new(int, smpi_global->process_count);
191   for (i = 0; i < smpi_global->process_count; i++) {
192     smpi_mpi_global->mpi_comm_world->rank_to_index_map[i] = i;
193     smpi_mpi_global->mpi_comm_world->index_to_rank_map[i] = i;
194   }
195
196   // mpi datatypes
197   smpi_mpi_global->mpi_byte = xbt_new(s_smpi_mpi_datatype_t, 1);
198   smpi_mpi_global->mpi_byte->size = (size_t) 1;
199   smpi_mpi_global->mpi_char = xbt_new(s_smpi_mpi_datatype_t, 1);
200   smpi_mpi_global->mpi_char->size = (size_t) 1;
201   smpi_mpi_global->mpi_int = xbt_new(s_smpi_mpi_datatype_t, 1);
202   smpi_mpi_global->mpi_int->size = sizeof(int);
203   smpi_mpi_global->mpi_float = xbt_new(s_smpi_mpi_datatype_t, 1);
204   smpi_mpi_global->mpi_float->size = sizeof(float);
205   smpi_mpi_global->mpi_double = xbt_new(s_smpi_mpi_datatype_t, 1);
206   smpi_mpi_global->mpi_double->size = sizeof(double);
207
208   // mpi operations
209   smpi_mpi_global->mpi_land = xbt_new(s_smpi_mpi_op_t, 1);
210   smpi_mpi_global->mpi_land->func = smpi_mpi_land_func;
211   smpi_mpi_global->mpi_sum = xbt_new(s_smpi_mpi_op_t, 1);
212   smpi_mpi_global->mpi_sum->func = smpi_mpi_sum_func;
213   smpi_mpi_global->mpi_prod = xbt_new(s_smpi_mpi_op_t, 1);
214   smpi_mpi_global->mpi_prod->func = smpi_mpi_prod_func;
215   smpi_mpi_global->mpi_min = xbt_new(s_smpi_mpi_op_t, 1);
216   smpi_mpi_global->mpi_min->func = smpi_mpi_min_func;
217   smpi_mpi_global->mpi_max = xbt_new(s_smpi_mpi_op_t, 1);
218   smpi_mpi_global->mpi_max->func = smpi_mpi_max_func;
219
220 }
221
222 void smpi_global_destroy()
223 {
224   smpi_do_once_duration_node_t curr, next;
225
226   // processes
227   xbt_free(smpi_global->main_processes);
228
229   // mallocators
230   xbt_mallocator_free(smpi_global->request_mallocator);
231   xbt_mallocator_free(smpi_global->message_mallocator);
232
233   xbt_os_timer_free(smpi_global->timer);
234   SIMIX_mutex_destroy(smpi_global->timer_mutex);
235   SIMIX_cond_destroy(smpi_global->timer_cond);
236
237   for (curr = smpi_global->do_once_duration_nodes; NULL != curr; curr = next) {
238     next = curr->next;
239     xbt_free(curr->file);
240     xbt_free(curr);
241   }
242
243   SIMIX_mutex_destroy(smpi_global->do_once_mutex);
244
245   xbt_free(smpi_global);
246   smpi_global = NULL;
247
248   /* free smpi_mpi_global */
249   SIMIX_mutex_destroy(smpi_mpi_global->mpi_comm_world->barrier_mutex);
250   SIMIX_cond_destroy(smpi_mpi_global->mpi_comm_world->barrier_cond);
251   xbt_free(smpi_mpi_global->mpi_comm_world->rank_to_index_map);
252   xbt_free(smpi_mpi_global->mpi_comm_world);
253
254   xbt_free(smpi_mpi_global->mpi_byte);
255   xbt_free(smpi_mpi_global->mpi_char);
256   xbt_free(smpi_mpi_global->mpi_int);
257   xbt_free(smpi_mpi_global->mpi_double);
258   xbt_free(smpi_mpi_global->mpi_float);
259
260   xbt_free(smpi_mpi_global->mpi_land);
261   xbt_free(smpi_mpi_global->mpi_sum);
262   xbt_free(smpi_mpi_global->mpi_prod);
263   xbt_free(smpi_mpi_global->mpi_max);
264   xbt_free(smpi_mpi_global->mpi_min);
265
266   xbt_free(smpi_mpi_global);
267
268 }
269
270 int smpi_process_index()
271 {
272   smpi_process_data_t pdata =
273     (smpi_process_data_t) SIMIX_process_get_data(SIMIX_process_self());
274   return pdata->index;
275 }
276
277 smx_mutex_t smpi_process_mutex()
278 {
279   smpi_process_data_t pdata =
280     (smpi_process_data_t) SIMIX_process_get_data(SIMIX_process_self());
281   return pdata->mutex;
282 }
283
284 smx_cond_t smpi_process_cond()
285 {
286   smpi_process_data_t pdata =
287     (smpi_process_data_t) SIMIX_process_get_data(SIMIX_process_self());
288   return pdata->cond;
289 }
290
291 static void smpi_cfg_cb_host_speed(const char *name, int pos)
292 {
293   smpi_global->reference_speed =
294     xbt_cfg_get_double_at(_surf_cfg_set, name, pos);
295 }
296
297 int smpi_run_simulation(int *argc, char **argv)
298 {
299   smx_action_t action = NULL;
300
301   xbt_fifo_t actions_failed = xbt_fifo_new();
302   xbt_fifo_t actions_done = xbt_fifo_new();
303
304   srand(SMPI_RAND_SEED);
305
306   double default_reference_speed = 20000.0;
307   xbt_cfg_register(&_surf_cfg_set, "reference_speed",
308                    "Power of the host running the simulation (in flop/s). Used to bench the operations.",
309                    xbt_cfgelm_double, &default_reference_speed, 1, 1,
310                    smpi_cfg_cb_host_speed, NULL);
311
312   int default_display_timing = 0;
313   xbt_cfg_register(&_surf_cfg_set, "display_timing",
314                    "Boolean indicating whether we should display the timing after simulation.",
315                    xbt_cfgelm_int, &default_display_timing, 1, 1, NULL, NULL);
316
317   SIMIX_global_init(argc, argv);
318
319
320   // parse the platform file: get the host list
321   SIMIX_create_environment(argv[1]);
322
323   SIMIX_function_register("smpi_simulated_main", smpi_simulated_main);
324   SIMIX_launch_application(argv[2]);
325
326   // must initialize globals between creating environment and launching app....
327   smpi_global_init();
328
329   /* Clean IO before the run */
330   fflush(stdout);
331   fflush(stderr);
332   SIMIX_init();
333
334   while (SIMIX_solve(actions_done, actions_failed) != -1.0) {
335     while ((action = xbt_fifo_pop(actions_failed))) {
336       DEBUG1("** %s failed **", SIMIX_action_get_name(action));
337       SIMIX_action_signal_all(action);
338     }
339     while ((action = xbt_fifo_pop(actions_done))) {
340       DEBUG1("** %s done **", SIMIX_action_get_name(action));
341       SIMIX_action_signal_all(action);
342     }
343   }
344
345   // FIXME: cleanup incomplete
346   xbt_fifo_free(actions_failed);
347   xbt_fifo_free(actions_done);
348
349
350   if (xbt_cfg_get_int(_surf_cfg_set, "display_timing"))
351     INFO1("simulation time %g", SIMIX_get_clock());
352
353   smpi_global_destroy();
354   SIMIX_clean();
355
356   return 0;
357 }