342 lines
9.2 KiB
C++
342 lines
9.2 KiB
C++
/* ----------------------------------------------------------------------
|
|
LAMMPS - Large-scale Atomic/Molecular Massively Parallel Simulator
|
|
http://lammps.sandia.gov, Sandia National Laboratories
|
|
Steve Plimpton, sjplimp@sandia.gov
|
|
|
|
Copyright (2003) Sandia Corporation. Under the terms of Contract
|
|
DE-AC04-94AL85000 with Sandia Corporation, the U.S. Government retains
|
|
certain rights in this software. This software is distributed under
|
|
the GNU General Public License.
|
|
|
|
See the README file in the top-level LAMMPS directory.
|
|
------------------------------------------------------------------------- */
|
|
|
|
/* ----------------------------------------------------------------------
|
|
Contributing author: Rene Halver (JSC)
|
|
------------------------------------------------------------------------- */
|
|
|
|
#include <cstdio>
|
|
#include <cstring>
|
|
#include <cstdlib>
|
|
#include "scafacos.h"
|
|
#include "atom.h"
|
|
#include "comm.h"
|
|
#include "domain.h"
|
|
#include "force.h"
|
|
#include "memory.h"
|
|
#include "error.h"
|
|
|
|
// ScaFaCoS library
|
|
|
|
#include <string>
|
|
#include <sstream>
|
|
#include "fcs.h"
|
|
|
|
using namespace LAMMPS_NS;
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
Scafacos::Scafacos(LAMMPS *lmp, int narg, char **arg) : KSpace(lmp, narg, arg)
|
|
{
|
|
if (narg != 2) error->all(FLERR,"Illegal scafacos command");
|
|
|
|
int n = strlen(arg[0]) + 1;
|
|
method = new char[n];
|
|
strcpy(method,arg[0]);
|
|
tolerance = force->numeric(FLERR,arg[1]);
|
|
|
|
// optional ScaFaCoS library setting defaults
|
|
|
|
tolerance_type = FCS_TOLERANCE_TYPE_FIELD;
|
|
|
|
// initializations
|
|
|
|
me = comm->me;
|
|
initialized = 0;
|
|
|
|
maxatom = 0;
|
|
epot = NULL;
|
|
efield = NULL;
|
|
}
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
Scafacos::~Scafacos()
|
|
{
|
|
delete [] method;
|
|
|
|
memory->destroy(epot);
|
|
memory->destroy(efield);
|
|
|
|
// RENE: any clean-up/shut-down call to ScaFaCoS needed?
|
|
}
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
void Scafacos::init()
|
|
{
|
|
// error checks
|
|
|
|
if (!atom->q_flag) error->all(FLERR,"Kspace style requires atom attribute q");
|
|
|
|
if (domain->dimension == 2)
|
|
error->all(FLERR,"Cannot use ScaFaCoS with 2d simulation");
|
|
|
|
if (domain->triclinic)
|
|
error->all(FLERR,"Cannot use ScaFaCoS with triclinic domain yet");
|
|
|
|
if (atom->natoms > INT_MAX && sizeof(fcs_int) != 8)
|
|
error->all(FLERR,"Scafacos atom count exceeds 2B");
|
|
|
|
if (atom->molecular > 0)
|
|
error->all(FLERR,"Cannot use Scafacos with molecular charged systems yet");
|
|
|
|
// one-time initialization of ScaFaCoS
|
|
|
|
scale = 1.0;
|
|
qqrd2e = force->qqrd2e;
|
|
|
|
if (!initialized) {
|
|
result = fcs_init(&fcs,method,world);
|
|
check_result(result);
|
|
|
|
setup_handle();
|
|
|
|
result = fcs_set_tolerance(fcs,tolerance_type,tolerance);
|
|
check_result(result);
|
|
|
|
if (me == 0) fcs_print_parameters(fcs);
|
|
|
|
double **x = atom->x;
|
|
double *q = atom->q;
|
|
int nlocal = atom->nlocal;
|
|
|
|
result = fcs_tune(fcs,nlocal,&x[0][0],q);
|
|
}
|
|
|
|
initialized = 1;
|
|
}
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
void Scafacos::setup() {}
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
void Scafacos::compute(int eflag, int vflag)
|
|
{
|
|
double **x = atom->x;
|
|
double *q = atom->q;
|
|
int nlocal = atom->nlocal;
|
|
|
|
// RENE: why is scale needed?
|
|
|
|
const double qscale = qqrd2e * scale;
|
|
|
|
if (eflag || vflag) ev_setup(eflag,vflag);
|
|
else eflag_atom = 0;
|
|
|
|
// if simulation box has changed, call fcs_tune()
|
|
|
|
if (box_has_changed()) {
|
|
setup_handle();
|
|
result = fcs_tune(fcs,nlocal,&x[0][0],q);
|
|
check_result(result);
|
|
}
|
|
|
|
// grow epot & efield if necessary
|
|
|
|
if (nlocal > maxatom) {
|
|
memory->destroy(epot);
|
|
memory->destroy(efield);
|
|
maxatom = atom->nmax;
|
|
memory->create(epot,maxatom,"scafacos:epot");
|
|
memory->create(efield,maxatom,3,"scafacos:efield");
|
|
|
|
}
|
|
|
|
// initialize epot & efield
|
|
// RENE: is this necessary? or does Scafacos just set them
|
|
|
|
for (int i = 0; i < nlocal; i++) {
|
|
epot[i] = 0.0;
|
|
efield[i][0] = efield[i][1] = efield[i][2] = 0.0;
|
|
}
|
|
|
|
// ScaFaCoS calculation of full Coulombics
|
|
|
|
result = fcs_run(fcs,nlocal,&x[0][0],q,&efield[0][0],epot);
|
|
check_result(result);
|
|
|
|
// apply Efield to each particle
|
|
// accumulate total energy
|
|
|
|
double **f = atom->f;
|
|
|
|
double qone;
|
|
double myeng = 0.0;
|
|
|
|
for (int i = 0; i < nlocal; i++) {
|
|
qone = q[i] * qscale;
|
|
f[i][0] += qone * efield[i][0];
|
|
f[i][1] += qone * efield[i][1];
|
|
f[i][2] += qone * efield[i][2];
|
|
myeng += 0.5 * qone * epot[i];
|
|
}
|
|
|
|
if (eflag_atom) {
|
|
for (int i = 0; i < nlocal; i++)
|
|
eatom[i] = qscale * epot[i];
|
|
}
|
|
|
|
MPI_Allreduce(&myeng,&energy,1,MPI_DOUBLE,MPI_SUM,world);
|
|
}
|
|
|
|
/* ---------------------------------------------------------------------- */
|
|
|
|
int Scafacos::modify_param(int narg, char **arg)
|
|
{
|
|
// RENE: add any Scafacos options here you want to expose to LAMMPS
|
|
// syntax: kspace_modify scafacos keyword value1 value2 ...
|
|
// keyword = tolerance
|
|
// value1 = energy, energy_rel, etc
|
|
// everyone of these should have a default, so user doesn't need to set
|
|
|
|
if (strcmp(arg[0],"scafacos") != 0) return 0;
|
|
|
|
if (strcmp(arg[1],"tolerance") == 0) {
|
|
if (narg < 2) error->all(FLERR,"Illegal kspace_modify command");
|
|
if (strcmp(arg[2],"energy") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_ENERGY;
|
|
else if (strcmp(arg[2],"energy_rel") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_ENERGY_REL;
|
|
else if (strcmp(arg[2],"field") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_FIELD;
|
|
else if (strcmp(arg[2],"field_rel") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_FIELD_REL;
|
|
else if (strcmp(arg[2],"potential") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_POTENTIAL;
|
|
else if (strcmp(arg[2],"potential_rel") == 0)
|
|
tolerance_type = FCS_TOLERANCE_TYPE_POTENTIAL_REL;
|
|
else error->all(FLERR,"Illegal kspace_modify command");
|
|
return 3;
|
|
}
|
|
|
|
return 0;
|
|
}
|
|
|
|
/* ----------------------------------------------------------------------
|
|
memory usage of local arrays
|
|
------------------------------------------------------------------------- */
|
|
|
|
double Scafacos::memory_usage()
|
|
{
|
|
double bytes = 0.0;
|
|
bytes += maxatom * sizeof(double);
|
|
bytes += 3*maxatom * sizeof(double);
|
|
return bytes;
|
|
}
|
|
|
|
/* ----------------------------------------------------------------------
|
|
setup of ScaFaCoS handle with common parameters
|
|
------------------------------------------------------------------------- */
|
|
|
|
void Scafacos::setup_handle()
|
|
{
|
|
// store simulation box params
|
|
|
|
old_periodicity[0] = domain->xperiodic;
|
|
old_periodicity[1] = domain->yperiodic;
|
|
old_periodicity[2] = domain->zperiodic;
|
|
|
|
// RENE: what does SCFCS mean by offset?
|
|
// it's an integer flag in LAMMPS, but being stored in a float?
|
|
|
|
old_offset[0] = domain->boundary[0][0];
|
|
old_offset[1] = domain->boundary[1][0];
|
|
old_offset[2] = domain->boundary[2][0];
|
|
|
|
old_box_x[0] = domain->prd[0];
|
|
old_box_x[1] = old_box_x[2] = 0.0;
|
|
old_box_y[1] = domain->prd[1];
|
|
old_box_y[0] = old_box_y[2] = 0.0;
|
|
old_box_z[2] = domain->prd[2];
|
|
old_box_z[1] = old_box_z[0] = 0.0;
|
|
|
|
old_natoms = atom->natoms;
|
|
|
|
// set all required ScaFaCoS params
|
|
|
|
result = fcs_set_box_a(fcs,old_box_x);
|
|
check_result(result);
|
|
|
|
result = fcs_set_box_b(fcs,old_box_y);
|
|
check_result(result);
|
|
|
|
result = fcs_set_box_c(fcs,old_box_z);
|
|
check_result(result);
|
|
|
|
result = fcs_set_box_origin(fcs,old_offset);
|
|
check_result(result);
|
|
|
|
result = fcs_set_periodicity(fcs,old_periodicity);
|
|
check_result(result);
|
|
|
|
result = fcs_set_total_particles(fcs,old_natoms);
|
|
check_result(result);
|
|
|
|
// RENE: disable short-range calculations within LAMMPS
|
|
// not sure what this is doing
|
|
// is this the correct thing to do for now?
|
|
|
|
int near_field_flag = 0;
|
|
result = fcs_set_near_field_flag(fcs,near_field_flag);
|
|
check_result(result);
|
|
}
|
|
|
|
/* ----------------------------------------------------------------------
|
|
check if box parameters changed, requiring a new call to fcs_tune
|
|
------------------------------------------------------------------------- */
|
|
|
|
bool Scafacos::box_has_changed()
|
|
{
|
|
int *periodicity = domain->periodicity;
|
|
double *prd = domain->prd;
|
|
|
|
bool changed =
|
|
(periodicity[0] != old_periodicity[0]) ||
|
|
(periodicity[1] != old_periodicity[1]) ||
|
|
(periodicity[2] != old_periodicity[2]) ||
|
|
(domain->boundary[0][0] != old_offset[0]) ||
|
|
(domain->boundary[1][0] != old_offset[1]) ||
|
|
(domain->boundary[2][0] != old_offset[2]) ||
|
|
(prd[0] != old_box_x[0]) ||
|
|
(prd[1] != old_box_y[1]) ||
|
|
(prd[2] != old_box_z[2]) ||
|
|
(atom->natoms != old_natoms);
|
|
|
|
return changed;
|
|
}
|
|
|
|
/* ----------------------------------------------------------------------
|
|
check ScaFaCoS result for error condition
|
|
------------------------------------------------------------------------- */
|
|
|
|
void Scafacos::check_result(FCSResult result)
|
|
{
|
|
if (!result) return;
|
|
|
|
std::stringstream ss;
|
|
ss << "ScaFaCoS: " << fcs_result_get_function(result) << "\n"
|
|
<< fcs_result_get_message(result) << "\n";
|
|
fcs_result_destroy(result);
|
|
std::string err_msg = ss.str();
|
|
const char *str = err_msg.c_str();
|
|
|
|
// RENE: will all procs have same error?
|
|
// if so, then should call error->all(FLERR,str)
|
|
|
|
error->one(FLERR,str);
|
|
}
|
|
|