283 lines
		
	
	
		
			13 KiB
		
	
	
	
		
			Plaintext
		
	
	
	
	
	
			
		
		
	
	
			283 lines
		
	
	
		
			13 KiB
		
	
	
	
		
			Plaintext
		
	
	
	
	
	
| @node Multi-threaded FFTW, Distributed-memory FFTW with MPI, FFTW Reference, Top
 | |
| @chapter Multi-threaded FFTW
 | |
| 
 | |
| @cindex parallel transform
 | |
| In this chapter we document the parallel FFTW routines for
 | |
| shared-memory parallel hardware.  These routines, which support
 | |
| parallel one- and multi-dimensional transforms of both real and
 | |
| complex data, are the easiest way to take advantage of multiple
 | |
| processors with FFTW.  They work just like the corresponding
 | |
| uniprocessor transform routines, except that you have an extra
 | |
| initialization routine to call, and there is a routine to set the
 | |
| number of threads to employ.  Any program that uses the uniprocessor
 | |
| FFTW can therefore be trivially modified to use the multi-threaded
 | |
| FFTW.
 | |
| 
 | |
| A shared-memory machine is one in which all CPUs can directly access
 | |
| the same main memory, and such machines are now common due to the
 | |
| ubiquity of multi-core CPUs.  FFTW's multi-threading support allows
 | |
| you to utilize these additional CPUs transparently from a single
 | |
| program.  However, this does not necessarily translate into
 | |
| performance gains---when multiple threads/CPUs are employed, there is
 | |
| an overhead required for synchronization that may outweigh the
 | |
| computatational parallelism.  Therefore, you can only benefit from
 | |
| threads if your problem is sufficiently large.
 | |
| @cindex shared-memory
 | |
| @cindex threads
 | |
| 
 | |
| @menu
 | |
| * Installation and Supported Hardware/Software::
 | |
| * Usage of Multi-threaded FFTW::
 | |
| * How Many Threads to Use?::
 | |
| * Thread safety::
 | |
| @end menu
 | |
| 
 | |
| @c ------------------------------------------------------------
 | |
| @node Installation and Supported Hardware/Software, Usage of Multi-threaded FFTW, Multi-threaded FFTW, Multi-threaded FFTW
 | |
| @section Installation and Supported Hardware/Software
 | |
| 
 | |
| All of the FFTW threads code is located in the @code{threads}
 | |
| subdirectory of the FFTW package.  On Unix systems, the FFTW threads
 | |
| libraries and header files can be automatically configured, compiled,
 | |
| and installed along with the uniprocessor FFTW libraries simply by
 | |
| including @code{--enable-threads} in the flags to the @code{configure}
 | |
| script (@pxref{Installation on Unix}), or @code{--enable-openmp} to use
 | |
| @uref{http://www.openmp.org,OpenMP} threads.
 | |
| @fpindex configure
 | |
| 
 | |
| 
 | |
| @cindex portability
 | |
| @cindex OpenMP
 | |
| The threads routines require your operating system to have some sort
 | |
| of shared-memory threads support.  Specifically, the FFTW threads
 | |
| package works with POSIX threads (available on most Unix variants,
 | |
| from GNU/Linux to MacOS X) and Win32 threads.  OpenMP threads, which
 | |
| are supported in many common compilers (e.g. gcc) are also supported,
 | |
| and may give better performance on some systems.  (OpenMP threads are
 | |
| also useful if you are employing OpenMP in your own code, in order to
 | |
| minimize conflicts between threading models.)  If you have a
 | |
| shared-memory machine that uses a different threads API, it should be
 | |
| a simple matter of programming to include support for it; see the file
 | |
| @code{threads/threads.c} for more detail.
 | |
| 
 | |
| You can compile FFTW with @emph{both} @code{--enable-threads} and
 | |
| @code{--enable-openmp} at the same time, since they install libraries
 | |
| with different names (@samp{fftw3_threads} and @samp{fftw3_omp}, as
 | |
| described below).  However, your programs may only link to @emph{one}
 | |
| of these two libraries at a time.
 | |
| 
 | |
| Ideally, of course, you should also have multiple processors in order to
 | |
| get any benefit from the threaded transforms.
 | |
| 
 | |
| @c ------------------------------------------------------------
 | |
| @node Usage of Multi-threaded FFTW, How Many Threads to Use?, Installation and Supported Hardware/Software, Multi-threaded FFTW
 | |
| @section Usage of Multi-threaded FFTW
 | |
| 
 | |
| Here, it is assumed that the reader is already familiar with the usage
 | |
| of the uniprocessor FFTW routines, described elsewhere in this manual.
 | |
| We only describe what one has to change in order to use the
 | |
| multi-threaded routines.
 | |
| 
 | |
| @cindex OpenMP
 | |
| First, programs using the parallel complex transforms should be linked
 | |
| with @code{-lfftw3_threads -lfftw3 -lm} on Unix, or @code{-lfftw3_omp
 | |
| -lfftw3 -lm} if you compiled with OpenMP. You will also need to link
 | |
| with whatever library is responsible for threads on your system
 | |
| (e.g. @code{-lpthread} on GNU/Linux) or include whatever compiler flag
 | |
| enables OpenMP (e.g. @code{-fopenmp} with gcc).
 | |
| @cindex linking on Unix
 | |
| 
 | |
| 
 | |
| Second, before calling @emph{any} FFTW routines, you should call the
 | |
| function:
 | |
| 
 | |
| @example
 | |
| int fftw_init_threads(void);
 | |
| @end example
 | |
| @findex fftw_init_threads
 | |
| 
 | |
| This function, which need only be called once, performs any one-time
 | |
| initialization required to use threads on your system.  It returns zero
 | |
| if there was some error (which should not happen under normal
 | |
| circumstances) and a non-zero value otherwise.
 | |
| 
 | |
| Third, before creating a plan that you want to parallelize, you should
 | |
| call:
 | |
| 
 | |
| @example
 | |
| void fftw_plan_with_nthreads(int nthreads);
 | |
| @end example
 | |
| @findex fftw_plan_with_nthreads
 | |
| 
 | |
| The @code{nthreads} argument indicates the number of threads you want
 | |
| FFTW to use (or actually, the maximum number).  All plans subsequently
 | |
| created with any planner routine will use that many threads.  You can
 | |
| call @code{fftw_plan_with_nthreads}, create some plans, call
 | |
| @code{fftw_plan_with_nthreads} again with a different argument, and
 | |
| create some more plans for a new number of threads.  Plans already created
 | |
| before a call to @code{fftw_plan_with_nthreads} are unaffected.  If you
 | |
| pass an @code{nthreads} argument of @code{1} (the default), threads are
 | |
| disabled for subsequent plans.
 | |
| 
 | |
| You can determine the current number of threads that the planner can
 | |
| use by calling:
 | |
| 
 | |
| @example
 | |
| int fftw_planner_nthreads(void);
 | |
| @end example
 | |
| @findex fftw_planner_nthreads
 | |
| 
 | |
| @cindex OpenMP
 | |
| With OpenMP, to configure FFTW to use all of the currently running
 | |
| OpenMP threads (set by @code{omp_set_num_threads(nthreads)} or by the
 | |
| @code{OMP_NUM_THREADS} environment variable), you can do:
 | |
| @code{fftw_plan_with_nthreads(omp_get_max_threads())}. (The @samp{omp_}
 | |
| OpenMP functions are declared via @code{#include <omp.h>}.)
 | |
| 
 | |
| @cindex thread safety
 | |
| Given a plan, you then execute it as usual with
 | |
| @code{fftw_execute(plan)}, and the execution will use the number of
 | |
| threads specified when the plan was created.  When done, you destroy
 | |
| it as usual with @code{fftw_destroy_plan}.  As described in
 | |
| @ref{Thread safety}, plan @emph{execution} is thread-safe, but plan
 | |
| creation and destruction are @emph{not}: you should create/destroy
 | |
| plans only from a single thread, but can safely execute multiple plans
 | |
| in parallel.
 | |
| 
 | |
| There is one additional routine: if you want to get rid of all memory
 | |
| and other resources allocated internally by FFTW, you can call:
 | |
| 
 | |
| @example
 | |
| void fftw_cleanup_threads(void);
 | |
| @end example
 | |
| @findex fftw_cleanup_threads
 | |
| 
 | |
| which is much like the @code{fftw_cleanup()} function except that it
 | |
| also gets rid of threads-related data.  You must @emph{not} execute any
 | |
| previously created plans after calling this function.
 | |
| 
 | |
| We should also mention one other restriction: if you save wisdom from a
 | |
| program using the multi-threaded FFTW, that wisdom @emph{cannot be used}
 | |
| by a program using only the single-threaded FFTW (i.e. not calling
 | |
| @code{fftw_init_threads}).  @xref{Words of Wisdom-Saving Plans}.
 | |
| 
 | |
| Finally, FFTW provides a optional callback interface that allows you to
 | |
| replace its parallel threading backend at runtime:
 | |
| 
 | |
| @example
 | |
| void fftw_threads_set_callback(
 | |
|     void (*parallel_loop)(void *(*work)(void *), char *jobdata, size_t elsize, int njobs, void *data),
 | |
|     void *data);
 | |
| @end example
 | |
| @findex fftw_threads_set_callback
 | |
| 
 | |
| This routine (which is @emph{not} threadsafe and should generally be called before creating
 | |
| any FFTW plans) allows you to provide a function @code{parallel_loop} that executes
 | |
| parallel work for FFTW: it should call the function @code{work(jobdata + elsize*i)} for
 | |
| @code{i} from @code{0} to @code{njobs-1}, possibly in parallel.  (The `data` pointer
 | |
| supplied to @code{fftw_threads_set_callback} is passed through to your @code{parallel_loop}
 | |
| function.)   For example, if you link to an FFTW threads library built to use POSIX threads,
 | |
| but you want it to use OpenMP instead (because you are using OpenMP elsewhere in your program
 | |
| and want to avoid competing threads), you can call @code{fftw_threads_set_callback} with
 | |
| the callback function:
 | |
| 
 | |
| @example
 | |
| void parallel_loop(void *(*work)(char *), char *jobdata, size_t elsize, int njobs, void *data)
 | |
| @{
 | |
| #pragma omp parallel for
 | |
|     for (int i = 0; i < njobs; ++i)
 | |
|         work(jobdata + elsize * i);
 | |
| @}
 | |
| @end example
 | |
| 
 | |
| The same mechanism could be used in order to make FFTW use a threading backend
 | |
| implemented via Intel TBB, Apple GCD, or Cilk, for example.
 | |
| 
 | |
| 
 | |
| @c ------------------------------------------------------------
 | |
| @node How Many Threads to Use?, Thread safety, Usage of Multi-threaded FFTW, Multi-threaded FFTW
 | |
| @section How Many Threads to Use?
 | |
| 
 | |
| @cindex number of threads
 | |
| There is a fair amount of overhead involved in synchronizing threads,
 | |
| so the optimal number of threads to use depends upon the size of the
 | |
| transform as well as on the number of processors you have.
 | |
| 
 | |
| As a general rule, you don't want to use more threads than you have
 | |
| processors.  (Using more threads will work, but there will be extra
 | |
| overhead with no benefit.)  In fact, if the problem size is too small,
 | |
| you may want to use fewer threads than you have processors.
 | |
| 
 | |
| You will have to experiment with your system to see what level of
 | |
| parallelization is best for your problem size.  Typically, the problem
 | |
| will have to involve at least a few thousand data points before threads
 | |
| become beneficial.  If you plan with @code{FFTW_PATIENT}, it will
 | |
| automatically disable threads for sizes that don't benefit from
 | |
| parallelization.
 | |
| @ctindex FFTW_PATIENT
 | |
| 
 | |
| @c ------------------------------------------------------------
 | |
| @node Thread safety,  , How Many Threads to Use?, Multi-threaded FFTW
 | |
| @section Thread safety
 | |
| 
 | |
| @cindex threads
 | |
| @cindex OpenMP
 | |
| @cindex thread safety
 | |
| Users writing multi-threaded programs (including OpenMP) must concern
 | |
| themselves with the @dfn{thread safety} of the libraries they
 | |
| use---that is, whether it is safe to call routines in parallel from
 | |
| multiple threads.  FFTW can be used in such an environment, but some
 | |
| care must be taken because the planner routines share data
 | |
| (e.g. wisdom and trigonometric tables) between calls and plans.
 | |
| 
 | |
| The upshot is that the only thread-safe routine in FFTW is
 | |
| @code{fftw_execute} (and the new-array variants thereof).  All other routines
 | |
| (e.g. the planner) should only be called from one thread at a time.  So,
 | |
| for example, you can wrap a semaphore lock around any calls to the
 | |
| planner; even more simply, you can just create all of your plans from
 | |
| one thread.  We do not think this should be an important restriction
 | |
| (FFTW is designed for the situation where the only performance-sensitive
 | |
| code is the actual execution of the transform), and the benefits of
 | |
| shared data between plans are great.
 | |
| 
 | |
| Note also that, since the plan is not modified by @code{fftw_execute},
 | |
| it is safe to execute the @emph{same plan} in parallel by multiple
 | |
| threads.  However, since a given plan operates by default on a fixed
 | |
| array, you need to use one of the new-array execute functions (@pxref{New-array Execute Functions}) so that different threads compute the transform of different data.
 | |
| 
 | |
| (Users should note that these comments only apply to programs using
 | |
| shared-memory threads or OpenMP.  Parallelism using MPI or forked processes
 | |
| involves a separate address-space and global variables for each process,
 | |
| and is not susceptible to problems of this sort.)
 | |
| 
 | |
| The FFTW planner is intended to be called from a single thread.  If you
 | |
| really must call it from multiple threads, you are expected to grab
 | |
| whatever lock makes sense for your application, with the understanding
 | |
| that you may be holding that lock for a long time, which is undesirable.
 | |
| 
 | |
| Neither strategy works, however, in the following situation.  The
 | |
| ``application'' is structured as a set of ``plugins'' which are unaware
 | |
| of each other, and for whatever reason the ``plugins'' cannot coordinate
 | |
| on grabbing the lock.  (This is not a technical problem, but an
 | |
| organizational one.  The ``plugins'' are written by independent agents,
 | |
| and from the perspective of each plugin's author, each plugin is using
 | |
| FFTW correctly from a single thread.)  To cope with this situation,
 | |
| starting from FFTW-3.3.5, FFTW supports an API to make the planner
 | |
| thread-safe:
 | |
| 
 | |
| @example
 | |
| void fftw_make_planner_thread_safe(void);
 | |
| @end example
 | |
| @findex fftw_make_planner_thread_safe
 | |
| 
 | |
| This call operates by brute force: It just installs a hook that wraps a
 | |
| lock (chosen by us) around all planner calls.  So there is no magic and
 | |
| you get the worst of all worlds.  The planner is still single-threaded,
 | |
| but you cannot choose which lock to use.  The planner still holds the
 | |
| lock for a long time, but you cannot impose a timeout on lock
 | |
| acquisition.  As of FFTW-3.3.5 and FFTW-3.3.6, this call does not work
 | |
| when using OpenMP as threading substrate.  (Suggestions on what to do
 | |
| about this bug are welcome.)  @emph{Do not use
 | |
| @code{fftw_make_planner_thread_safe} unless there is no other choice,}
 | |
| such as in the application/plugin situation.
 | 
