X-Git-Url: http://info.iut-bm.univ-fcomte.fr/pub/gitweb/simgrid.git/blobdiff_plain/3c1eda61bc5b0d9c846abd9bb53b0bef26cb2880..ad12e936954df10a0395da3b161e820e07e97f52:/src/smpi/smpi_mpi.c diff --git a/src/smpi/smpi_mpi.c b/src/smpi/smpi_mpi.c index 60bbfd675e..4a5cd8d51d 100644 --- a/src/smpi/smpi_mpi.c +++ b/src/smpi/smpi_mpi.c @@ -1,4 +1,8 @@ -/* $Id$tag */ +/* Copyright (c) 2007, 2008, 2009, 2010. The SimGrid Team. + * All rights reserved. */ + +/* This program is free software; you can redistribute it and/or modify it + * under the terms of the license (GNU LGPL) which comes with this package. */ #include "private.h" #include "smpi_coll_private.h" @@ -12,10 +16,16 @@ XBT_LOG_NEW_DEFAULT_SUBCATEGORY(smpi_mpi, smpi, int MPI_Init(int* argc, char*** argv) { smpi_process_init(argc, argv); smpi_bench_begin(-1, NULL); +#ifdef HAVE_TRACING + TRACE_smpi_init(smpi_process_index()); +#endif return MPI_SUCCESS; } int MPI_Finalize(void) { +#ifdef HAVE_TRACING + TRACE_smpi_finalize(smpi_process_index()); +#endif smpi_bench_end(-1, NULL); smpi_process_destroy(); return MPI_SUCCESS; @@ -767,6 +777,10 @@ int MPI_Irecv(void* buf, int count, MPI_Datatype datatype, int src, int tag, MPI int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int src_traced = smpi_group_rank(smpi_comm_group(comm), src); + TRACE_smpi_ptp_in (rank, src_traced, rank, __FUNCTION__); +#endif smpi_bench_end(rank, "Irecv"); if(request == NULL) { retval = MPI_ERR_ARG; @@ -777,6 +791,10 @@ int MPI_Irecv(void* buf, int count, MPI_Datatype datatype, int src, int tag, MPI retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Irecv"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, src_traced, rank, __FUNCTION__); + (*request)->recv = 1; +#endif return retval; } @@ -784,6 +802,11 @@ int MPI_Isend(void* buf, int count, MPI_Datatype datatype, int dst, int tag, MPI int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int dst_traced = smpi_group_rank(smpi_comm_group(comm), dst); + TRACE_smpi_ptp_in (rank, rank, dst_traced, __FUNCTION__); + TRACE_smpi_send (rank, rank, dst_traced); +#endif smpi_bench_end(rank, "Isend"); if(request == NULL) { retval = MPI_ERR_ARG; @@ -794,6 +817,10 @@ int MPI_Isend(void* buf, int count, MPI_Datatype datatype, int dst, int tag, MPI retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Isend"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, rank, dst_traced, __FUNCTION__); + (*request)->send = 1; +#endif return retval; } @@ -801,6 +828,10 @@ int MPI_Recv(void* buf, int count, MPI_Datatype datatype, int src, int tag, MPI_ int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int src_traced = smpi_group_rank(smpi_comm_group(comm), src); + TRACE_smpi_ptp_in (rank, src_traced, rank, __FUNCTION__); +#endif smpi_bench_end(rank, "Recv"); if (comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -809,6 +840,10 @@ int MPI_Recv(void* buf, int count, MPI_Datatype datatype, int src, int tag, MPI_ retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Recv"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, src_traced, rank, __FUNCTION__); + TRACE_smpi_recv (rank, src_traced, rank); +#endif return retval; } @@ -816,6 +851,11 @@ int MPI_Send(void* buf, int count, MPI_Datatype datatype, int dst, int tag, MPI_ int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int dst_traced = smpi_group_rank(smpi_comm_group(comm), dst); + TRACE_smpi_ptp_in (rank, rank, dst_traced, __FUNCTION__); + TRACE_smpi_send (rank, rank, dst_traced); +#endif smpi_bench_end(rank, "Send"); if (comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -824,6 +864,9 @@ int MPI_Send(void* buf, int count, MPI_Datatype datatype, int dst, int tag, MPI_ retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Send"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, rank, dst_traced, __FUNCTION__); +#endif return retval; } @@ -831,6 +874,13 @@ int MPI_Sendrecv(void* sendbuf, int sendcount, MPI_Datatype sendtype, int dst, i int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int dst_traced = smpi_group_rank(smpi_comm_group(comm), dst); + int src_traced = smpi_group_rank(smpi_comm_group(comm), src); + TRACE_smpi_ptp_in (rank, src_traced, dst_traced, __FUNCTION__); + TRACE_smpi_send (rank, rank, dst_traced); + TRACE_smpi_send (rank, src_traced, rank); +#endif smpi_bench_end(rank, "Sendrecv"); if (comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -841,6 +891,11 @@ int MPI_Sendrecv(void* sendbuf, int sendcount, MPI_Datatype sendtype, int dst, i retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Sendrecv"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, src_traced, dst_traced, __FUNCTION__); + TRACE_smpi_recv (rank, rank, dst_traced); + TRACE_smpi_recv (rank, src_traced, rank); +#endif return retval; } @@ -896,6 +951,13 @@ int MPI_Wait(MPI_Request* request, MPI_Status* status) { ? smpi_comm_rank((*request)->comm) : -1; +#ifdef HAVE_TRACING + MPI_Group group = smpi_comm_group((*request)->comm); + int src_traced = smpi_group_rank (group , (*request)->src); + int dst_traced = smpi_group_rank (group , (*request)->dst); + int is_wait_for_receive = (*request)->recv; + TRACE_smpi_ptp_in (rank, src_traced, dst_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Wait"); if(request == NULL) { retval = MPI_ERR_ARG; @@ -906,12 +968,53 @@ int MPI_Wait(MPI_Request* request, MPI_Status* status) { retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Wait"); +#ifdef HAVE_TRACING + TRACE_smpi_ptp_out (rank, src_traced, dst_traced, __FUNCTION__); + if (is_wait_for_receive){ + TRACE_smpi_recv (rank, src_traced, dst_traced); + } +#endif return retval; } int MPI_Waitany(int count, MPI_Request requests[], int* index, MPI_Status* status) { int retval; +#ifdef HAVE_TRACING + //save requests information for tracing + int i; + xbt_dynar_t srcs = xbt_dynar_new (sizeof(int), xbt_free); + xbt_dynar_t dsts = xbt_dynar_new (sizeof(int), xbt_free); + xbt_dynar_t recvs = xbt_dynar_new (sizeof(int), xbt_free); + for (i = 0; i < count; i++){ + MPI_Request req = requests[i]; //already received requests are no longer valid + if (req){ + int *asrc = xbt_new(int, 1); + int *adst = xbt_new(int, 1); + int *arecv = xbt_new(int, 1); + *asrc = req->src; + *adst = req->dst; + *arecv = req->recv; + xbt_dynar_insert_at (srcs, i, asrc); + xbt_dynar_insert_at (dsts, i, adst); + xbt_dynar_insert_at (recvs, i, arecv); + }else{ + int *t = xbt_new(int, 1); + xbt_dynar_insert_at (srcs, i, t); + xbt_dynar_insert_at (dsts, i, t); + xbt_dynar_insert_at (recvs, i, t); + } + } + + //search for a suitable request to give the rank of current mpi proc + MPI_Request req = NULL; + for (i = 0; i < count && req == NULL; i++) { + req = requests[i]; + } + MPI_Comm comm = (req)->comm; + int rank_traced = smpi_comm_rank(comm); + TRACE_smpi_ptp_in (rank_traced, -1, -1, __FUNCTION__); +#endif smpi_bench_end(-1, NULL); //FIXME if(index == NULL) { retval = MPI_ERR_ARG; @@ -920,13 +1023,72 @@ int MPI_Waitany(int count, MPI_Request requests[], int* index, MPI_Status* statu retval = MPI_SUCCESS; } smpi_bench_begin(-1, NULL); +#ifdef HAVE_TRACING + int src_traced, dst_traced, is_wait_for_receive; + xbt_dynar_get_cpy (srcs, *index, &src_traced); + xbt_dynar_get_cpy (dsts, *index, &dst_traced); + xbt_dynar_get_cpy (recvs, *index, &is_wait_for_receive); + if (is_wait_for_receive){ + TRACE_smpi_recv (rank_traced, src_traced, dst_traced); + } + TRACE_smpi_ptp_out (rank_traced, src_traced, dst_traced, __FUNCTION__); + //clean-up of dynars + xbt_free (srcs); + xbt_free (dsts); + xbt_free (recvs); +#endif return retval; } int MPI_Waitall(int count, MPI_Request requests[], MPI_Status status[]) { + +#ifdef HAVE_TRACING + //save information from requests + int i; + xbt_dynar_t srcs = xbt_dynar_new (sizeof(int), xbt_free); + xbt_dynar_t dsts = xbt_dynar_new (sizeof(int), xbt_free); + xbt_dynar_t recvs = xbt_dynar_new (sizeof(int), xbt_free); + for (i = 0; i < count; i++){ + MPI_Request req = requests[i]; //all req should be valid in Waitall + int *asrc = xbt_new(int, 1); + int *adst = xbt_new(int, 1); + int *arecv = xbt_new(int, 1); + *asrc = req->src; + *adst = req->dst; + *arecv = req->recv; + xbt_dynar_insert_at (srcs, i, asrc); + xbt_dynar_insert_at (dsts, i, adst); + xbt_dynar_insert_at (recvs, i, arecv); + } + +// find my rank inside one of MPI_Comm's of the requests + MPI_Request req = NULL; + for (i = 0; i < count && req == NULL; i++) { + req = requests[i]; + } + MPI_Comm comm = (req)->comm; + int rank_traced = smpi_comm_rank(comm); + TRACE_smpi_ptp_in (rank_traced, -1, -1, __FUNCTION__); +#endif smpi_bench_end(-1, NULL); //FIXME smpi_mpi_waitall(count, requests, status); smpi_bench_begin(-1, NULL); +#ifdef HAVE_TRACING + for (i = 0; i < count; i++){ + int src_traced, dst_traced, is_wait_for_receive; + xbt_dynar_get_cpy (srcs, i, &src_traced); + xbt_dynar_get_cpy (dsts, i, &dst_traced); + xbt_dynar_get_cpy (recvs, i, &is_wait_for_receive); + if (is_wait_for_receive){ + TRACE_smpi_recv (rank_traced, src_traced, dst_traced); + } + } + TRACE_smpi_ptp_out (rank_traced, -1, -1, __FUNCTION__); + //clean-up of dynars + xbt_free (srcs); + xbt_free (dsts); + xbt_free (recvs); +#endif return MPI_SUCCESS; } @@ -948,6 +1110,10 @@ int MPI_Bcast(void* buf, int count, MPI_Datatype datatype, int root, MPI_Comm co int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Bcast"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -956,6 +1122,9 @@ int MPI_Bcast(void* buf, int count, MPI_Datatype datatype, int root, MPI_Comm co retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Bcast"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -963,6 +1132,9 @@ int MPI_Barrier(MPI_Comm comm) { int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Barrier"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -971,6 +1143,9 @@ int MPI_Barrier(MPI_Comm comm) { retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Barrier"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -978,6 +1153,10 @@ int MPI_Gather(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvbu int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Gather"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -988,6 +1167,9 @@ int MPI_Gather(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvbu retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Gather"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -995,6 +1177,10 @@ int MPI_Gatherv(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvb int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Gatherv"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1007,6 +1193,9 @@ int MPI_Gatherv(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvb retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Gatherv"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -1014,6 +1203,9 @@ int MPI_Allgather(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* rec int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Allgather"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1024,6 +1216,9 @@ int MPI_Allgather(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* rec retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Allgather"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1031,6 +1226,9 @@ int MPI_Allgatherv(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* re int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Allgatherv"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1043,6 +1241,9 @@ int MPI_Allgatherv(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* re retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Allgatherv"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1050,6 +1251,10 @@ int MPI_Scatter(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvb int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Scatter"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1060,6 +1265,9 @@ int MPI_Scatter(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recvb retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Scatter"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -1067,6 +1275,10 @@ int MPI_Scatterv(void* sendbuf, int* sendcounts, int* displs, MPI_Datatype sendt int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Scatterv"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1079,6 +1291,9 @@ int MPI_Scatterv(void* sendbuf, int* sendcounts, int* displs, MPI_Datatype sendt retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Scatterv"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -1086,6 +1301,10 @@ int MPI_Reduce(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype, M int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + int root_traced = smpi_group_rank(smpi_comm_group(comm), root); + TRACE_smpi_collective_in (rank, root_traced, __FUNCTION__); +#endif smpi_bench_end(rank, "Reduce"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1096,6 +1315,9 @@ int MPI_Reduce(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype, M retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Reduce"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, root_traced, __FUNCTION__); +#endif return retval; } @@ -1103,6 +1325,9 @@ int MPI_Allreduce(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Allreduce"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1115,6 +1340,9 @@ int MPI_Allreduce(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Allreduce"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1122,6 +1350,9 @@ int MPI_Scan(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype, MPI int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Scan"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1134,6 +1365,9 @@ int MPI_Scan(void* sendbuf, void* recvbuf, int count, MPI_Datatype datatype, MPI retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Scan"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1142,6 +1376,9 @@ int MPI_Reduce_scatter(void* sendbuf, void* recvbuf, int* recvcounts, MPI_Dataty int* displs; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Reduce_scatter"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1167,6 +1404,9 @@ int MPI_Reduce_scatter(void* sendbuf, void* recvbuf, int* recvcounts, MPI_Dataty retval = MPI_SUCCESS; } smpi_bench_begin(rank, "Reduce_scatter"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1174,6 +1414,9 @@ int MPI_Alltoall(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recv int retval, size, sendsize; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Alltoall"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1191,6 +1434,9 @@ int MPI_Alltoall(void* sendbuf, int sendcount, MPI_Datatype sendtype, void* recv } } smpi_bench_begin(rank, "Alltoall"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; } @@ -1198,6 +1444,9 @@ int MPI_Alltoallv(void* sendbuf, int* sendcounts, int* senddisps, MPI_Datatype s int retval; int rank = comm != MPI_COMM_NULL ? smpi_comm_rank(comm) : -1; +#ifdef HAVE_TRACING + TRACE_smpi_collective_in (rank, -1, __FUNCTION__); +#endif smpi_bench_end(rank, "Alltoallv"); if(comm == MPI_COMM_NULL) { retval = MPI_ERR_COMM; @@ -1209,6 +1458,9 @@ int MPI_Alltoallv(void* sendbuf, int* sendcounts, int* senddisps, MPI_Datatype s retval = smpi_coll_basic_alltoallv(sendbuf, sendcounts, senddisps, sendtype, recvbuf, recvcounts, recvdisps, recvtype, comm); } smpi_bench_begin(rank, "Alltoallv"); +#ifdef HAVE_TRACING + TRACE_smpi_collective_out (rank, -1, __FUNCTION__); +#endif return retval; }