// Copyright (c) 2012-2013 The PPCoin developers
+// Copyright (c) 2013-2015 The Novacoin developers
+// Distributed under the MIT/X11 software license, see the accompanying
+// file COPYING or http://www.opensource.org/licenses/mit-license.php.
// Distributed under the MIT/X11 software license, see the accompanying
// file COPYING or http://www.opensource.org/licenses/mit-license.php.
uint256 hashBlockFrom = blockFrom.GetHash();
- CBigNum bnCoinDayWeight = CBigNum(nValueIn) * GetWeight((int64_t)txPrev.nTime, (int64_t)nTimeTx) / COIN / (24 * 60 * 60);
+ CBigNum bnCoinDayWeight = CBigNum(nValueIn) * GetWeight((int64_t)txPrev.nTime, (int64_t)nTimeTx) / COIN / nOneDay;
targetProofOfStake = (bnCoinDayWeight * bnTargetPerCoinDay).getuint256();
// Calculate hash
return true;
}
-// Precompute hashing state for static part of kernel
-void GetKernelMidstate(uint64_t nStakeModifier, uint32_t nBlockTime, uint32_t nTxOffset, uint32_t nInputTxTime, uint32_t nOut, SHA256_CTX &ctx)
+
+#ifdef USE_ASM
+
+// kernel padding
+static const uint32_t block1_suffix[9] = { 0x80000000, 0, 0, 0, 0, 0, 0, 0, 0x000000e0 };
+static const uint32_t block1_suffix_4way[4 * 9] = {
+ 0x80000000, 0x80000000, 0x80000000, 0x80000000,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0x000000e0, 0x000000e0, 0x000000e0, 0x000000e0
+};
+
+// hash padding
+static const uint32_t block2_suffix[8] = { 0x80000000, 0, 0, 0, 0, 0, 0, 0x00000100 };
+static const uint32_t block2_suffix_4way[4 * 8] = {
+ 0x80000000, 0x80000000, 0x80000000, 0x80000000,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0, 0, 0, 0,
+ 0x00000100, 0x00000100, 0x00000100, 0x00000100
+};
+
+extern "C" int sha256_use_4way();
+extern "C" void sha256_init(uint32_t *state);
+extern "C" void sha256_transform(uint32_t *state, const uint32_t *block, int swap);
+extern "C" void sha256_init_4way(uint32_t *state);
+extern "C" void sha256_transform_4way(uint32_t *state, const uint32_t *block, int swap);
+
+#ifdef USE_SSSE3
+#include <immintrin.h>
+
+extern "C" int sha256_use_ssse3();
+bool fUseSSSE3 = sha256_use_ssse3() != 0;
+
+inline void copyrow_swap32(uint32_t *to, uint32_t *from)
{
- // Build static part of kernel
- CDataStream ssKernel(SER_GETHASH, 0);
- ssKernel << nStakeModifier;
- ssKernel << nBlockTime << nTxOffset << nInputTxTime << nOut;
- CDataStream::const_iterator it = ssKernel.begin();
-
- // Init sha256 context and update it
- // with first 24 bytes of kernel
- SHA256_Init(&ctx);
- SHA256_Update(&ctx, (unsigned char*)&it[0], 8 + 16);
+ if (!fUseSSSE3)
+ {
+ for (int i = 0; i < 4; i++)
+ to[i] = __builtin_bswap32(from[i]);
+ }
+ else
+ {
+ __m128i mask = _mm_set_epi8(12, 13, 14, 15, 8, 9, 10, 11, 4, 5, 6, 7, 0, 1, 2, 3);
+ _mm_storeu_si128((__m128i *)&to[0], _mm_shuffle_epi8(_mm_loadu_si128((__m128i *)&from[0]), mask));
+ }
}
+#else
+inline void copyrow_swap32(uint32_t *to, uint32_t *from)
+{
+ for (int i = 0; i < 4; i++)
+ to[i] = __builtin_bswap32(from[i]);
+}
+#endif
+bool fUse4Way = sha256_use_4way() != 0;
class ScanMidstateWorker
{
public:
ScanMidstateWorker()
{ }
- ScanMidstateWorker(SHA256_CTX ctx, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, std::pair<uint32_t, uint32_t> &SearchInterval)
+ ScanMidstateWorker(unsigned char *kernel, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, uint32_t nIntervalBegin, uint32_t nIntervalEnd)
+ : kernel(kernel), nBits(nBits), nInputTxTime(nInputTxTime), bnValueIn(nValueIn), nIntervalBegin(nIntervalBegin), nIntervalEnd(nIntervalEnd)
{
- workerSolutions = vector<std::pair<uint256,uint32_t> >();
-
- workerCtx = ctx;
- this->nBits = nBits;
- this->nInputTxTime = nInputTxTime;
- this->nValueIn = nValueIn;
- this->SearchInterval = SearchInterval;
+ solutions = vector<std::pair<uint256,uint32_t> >();
}
- void Do()
+ void Do_4way()
{
+ SetThreadPriority(THREAD_PRIORITY_LOWEST);
+
+ // Compute maximum possible target to filter out majority of obviously insufficient hashes
CBigNum bnTargetPerCoinDay;
bnTargetPerCoinDay.SetCompact(nBits);
+ uint256 nMaxTarget = (bnTargetPerCoinDay * bnValueIn * nStakeMaxAge / COIN / nOneDay).getuint256();
+
+ uint32_t state1[4 * 8] __attribute__((aligned(16)));
+ uint32_t state2[4 * 8] __attribute__((aligned(16)));
+ uint32_t blocks1[4 * 16] __attribute__((aligned(16)));
+ uint32_t blocks2[4 * 16] __attribute__((aligned(16)));
+
+ vector<uint32_t> vRow = vector<uint32_t>(4);
+ uint32_t *pnKernel = (uint32_t *) kernel;
+
+ for(int i = 0; i < 7; i++)
+ {
+ fill(vRow.begin(), vRow.end(), pnKernel[i]);
+ copyrow_swap32(&blocks1[i*4], &vRow[0]);
+ }
+
+ memcpy(&blocks1[28], &block1_suffix_4way[0], 36*4); // sha256 padding
+ memcpy(&blocks2[32], &block2_suffix_4way[0], 32*4);
+
+ uint32_t nTimeStamps[4] = {0, 0, 0, 0};
+ uint32_t nHashes[4] = {0, 0, 0, 0};
- // Get maximum possible target to filter out the majority of obviously insufficient hashes
- CBigNum bnMaxTargetPerCoinDay = bnTargetPerCoinDay * CBigNum(nValueIn) * nStakeMaxAge / COIN / (24 * 60 * 60);
- uint256 maxTarget = bnMaxTargetPerCoinDay.getuint256();
+ // Search forward in time from the given timestamp
+ // Stopping search in case of shutting down
+ for (uint32_t nTimeTx=nIntervalBegin, nMaxTarget32 = nMaxTarget.Get32(7); nTimeTx<nIntervalEnd && !fShutdown; nTimeTx +=4)
+ {
+ sha256_init_4way(state1);
+ sha256_init_4way(state2);
+
+ nTimeStamps[0] = nTimeTx;
+ nTimeStamps[1] = nTimeTx+1;
+ nTimeStamps[2] = nTimeTx+2;
+ nTimeStamps[3] = nTimeTx+3;
+
+ copyrow_swap32(&blocks1[24], &nTimeStamps[0]); // Kernel timestamps
+ sha256_transform_4way(&state1[0], &blocks1[0], 0); // first hashing
+ memcpy(&blocks2[0], &state1[0], 128);
+ sha256_transform_4way(&state2[0], &blocks2[0], 0); // second hashing
+ copyrow_swap32(&nHashes[0], &state2[28]);
+
+ for(int nResult = 0; nResult < 4; nResult++)
+ {
+ if (nHashes[nResult] <= nMaxTarget32) // Possible hit
+ {
+ uint256 nHashProofOfStake = 0;
+ uint32_t *pnHashProofOfStake = (uint32_t *) &nHashProofOfStake;
+ for (int i = 0; i < 7; i++)
+ pnHashProofOfStake[i] = __builtin_bswap32(state2[(i*4) + nResult]);
+ pnHashProofOfStake[7] = nHashes[nResult];
+
+ CBigNum bnCoinDayWeight = bnValueIn * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeStamps[nResult]) / COIN / nOneDay;
+ CBigNum bnTargetProofOfStake = bnCoinDayWeight * bnTargetPerCoinDay;
+
+ if (bnTargetProofOfStake >= CBigNum(nHashProofOfStake))
+ solutions.push_back(std::pair<uint256,uint32_t>(nHashProofOfStake, nTimeStamps[nResult]));
+ }
+ }
+ }
+ }
+
+ void Do_generic()
+ {
+ SetThreadPriority(THREAD_PRIORITY_LOWEST);
+
+ // Init new sha256 context and update it
+ // with first 24 bytes of kernel
+ SHA256_CTX workerCtx;
+ SHA256_Init(&workerCtx);
+ SHA256_Update(&workerCtx, kernel, 8 + 16);
SHA256_CTX ctx = workerCtx;
+ // Sha256 result buffer
+ uint32_t hashProofOfStake[8];
+
+ // Compute maximum possible target to filter out majority of obviously insufficient hashes
+ CBigNum bnTargetPerCoinDay;
+ bnTargetPerCoinDay.SetCompact(nBits);
+
+ uint256 nMaxTarget = (bnTargetPerCoinDay * bnValueIn * nStakeMaxAge / COIN / nOneDay).getuint256(),
+ *pnHashProofOfStake = (uint256 *)&hashProofOfStake;
+
// Search forward in time from the given timestamp
// Stopping search in case of shutting down
- for (uint32_t nTimeTx=SearchInterval.first; nTimeTx<SearchInterval.second && !fShutdown; nTimeTx++)
+ for (uint32_t nTimeTx=nIntervalBegin, nMaxTarget32 = nMaxTarget.Get32(7); nTimeTx<nIntervalEnd && !fShutdown; nTimeTx++)
{
// Complete first hashing iteration
uint256 hash1;
ctx = workerCtx;
// Finally, calculate kernel hash
- uint256 hashProofOfStake;
SHA256((unsigned char*)&hash1, sizeof(hashProofOfStake), (unsigned char*)&hashProofOfStake);
+ // Skip if hash doesn't satisfy the maximum target
+ if (hashProofOfStake[7] > nMaxTarget32)
+ continue;
+
+ CBigNum bnCoinDayWeight = bnValueIn * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeTx) / COIN / nOneDay;
+ CBigNum bnTargetProofOfStake = bnCoinDayWeight * bnTargetPerCoinDay;
+
+ if (bnTargetProofOfStake >= CBigNum(*pnHashProofOfStake))
+ solutions.push_back(std::pair<uint256,uint32_t>(*pnHashProofOfStake, nTimeTx));
+ }
+ }
+
+ void Do()
+ {
+ if (fUse4Way)
+ Do_4way();
+ else
+ Do_generic();
+ }
+
+ vector<std::pair<uint256,uint32_t> >& GetSolutions()
+ {
+ return solutions;
+ }
+
+private:
+ std::vector<std::pair<uint256,uint32_t> > solutions;
+
+ uint8_t *kernel;
+ uint32_t nBits;
+ uint32_t nInputTxTime;
+ CBigNum bnValueIn;
+ uint32_t nIntervalBegin;
+ uint32_t nIntervalEnd;
+};
+
+#else
+class ScanMidstateWorker
+{
+public:
+ ScanMidstateWorker()
+ { }
+ ScanMidstateWorker(unsigned char *kernel, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, uint32_t nIntervalBegin, uint32_t nIntervalEnd)
+ : nBits(nBits), nInputTxTime(nInputTxTime), bnValueIn(nValueIn), nIntervalBegin(nIntervalBegin), nIntervalEnd(nIntervalEnd)
+ {
+ // Init new sha256 context and update it
+ // with first 24 bytes of kernel
+ SHA256_Init(&workerCtx);
+ SHA256_Update(&workerCtx, kernel, 8 + 16);
+ solutions = vector<std::pair<uint256,uint32_t> >();
+ }
+
+ void Do()
+ {
+ SetThreadPriority(THREAD_PRIORITY_LOWEST);
+ SHA256_CTX ctx = workerCtx;
+
+ // Sha256 result buffer
+ uint32_t hashProofOfStake[8];
+
+ // Compute maximum possible target to filter out majority of obviously insufficient hashes
+ CBigNum bnTargetPerCoinDay;
+ bnTargetPerCoinDay.SetCompact(nBits);
+
+ uint256 nMaxTarget = (bnTargetPerCoinDay * bnValueIn * nStakeMaxAge / COIN / nOneDay).getuint256(),
+ *pnHashProofOfStake = (uint256 *)&hashProofOfStake;
+
+ // Search forward in time from the given timestamp
+ // Stopping search in case of shutting down
+ for (uint32_t nTimeTx=nIntervalBegin, nMaxTarget32 = nMaxTarget.Get32(7); nTimeTx<nIntervalEnd && !fShutdown; nTimeTx++)
+ {
+ // Complete first hashing iteration
+ uint256 hash1;
+ SHA256_Update(&ctx, (unsigned char*)&nTimeTx, 4);
+ SHA256_Final((unsigned char*)&hash1, &ctx);
+
+ // Restore context
+ ctx = workerCtx;
+
+ // Finally, calculate kernel hash
+ SHA256((unsigned char*)&hash1, sizeof(hashProofOfStake), (unsigned char*)&hashProofOfStake);
// Skip if hash doesn't satisfy the maximum target
- if (hashProofOfStake > maxTarget)
+ if (hashProofOfStake[7] > nMaxTarget32)
continue;
- CBigNum bnCoinDayWeight = CBigNum(nValueIn) * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeTx) / COIN / (24 * 60 * 60);
+ CBigNum bnCoinDayWeight = bnValueIn * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeTx) / COIN / nOneDay;
CBigNum bnTargetProofOfStake = bnCoinDayWeight * bnTargetPerCoinDay;
- if (bnTargetProofOfStake >= CBigNum(hashProofOfStake))
- {
- workerSolutions.push_back(std::pair<uint256,uint32_t>(hashProofOfStake, nTimeTx));
- }
+ if (bnTargetProofOfStake >= CBigNum(*pnHashProofOfStake))
+ solutions.push_back(std::pair<uint256,uint32_t>(*pnHashProofOfStake, nTimeTx));
}
}
- vector<std::pair<uint256,uint32_t> > GetSolutions()
+ vector<std::pair<uint256,uint32_t> >& GetSolutions()
{
- return workerSolutions;
+ return solutions;
}
private:
SHA256_CTX workerCtx;
- std::vector<std::pair<uint256,uint32_t> > workerSolutions;
+ std::vector<std::pair<uint256,uint32_t> > solutions;
uint32_t nBits;
uint32_t nInputTxTime;
- int64_t nValueIn;
- std::pair<uint32_t, uint32_t> SearchInterval;
+ CBigNum bnValueIn;
+ uint32_t nIntervalBegin;
+ uint32_t nIntervalEnd;
};
-// Scan given midstate for solution
-bool ScanMidstateForward(SHA256_CTX &ctx, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, std::pair<uint32_t, uint32_t> &SearchInterval, std::vector<std::pair<uint256, uint32_t> > &solutions)
+#endif
+// Scan given kernel for solution
+bool ScanKernelForward(unsigned char *kernel, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, std::pair<uint32_t, uint32_t> &SearchInterval, std::vector<std::pair<uint256, uint32_t> > &solutions)
{
// TODO: custom threads amount
- uint32_t nBegin = SearchInterval.first;
- uint32_t nEnd = SearchInterval.second;
- uint32_t nPart = (nEnd - nBegin) / 4;
+ uint32_t nThreads = boost::thread::hardware_concurrency();
+ uint32_t nPart = (SearchInterval.second - SearchInterval.first) / nThreads;
+
- ScanMidstateWorker workers[4];
+ ScanMidstateWorker *workers = new ScanMidstateWorker[nThreads];
boost::thread_group group;
- for(int i = 0; i<4; i++)
+ for(size_t i = 0; i < nThreads; i++)
{
- nBegin += (nPart * i);
- uint32_t nIntervalEnd = nBegin + nPart * (i + 1);
-
- std::cout << nBegin << " " << nIntervalEnd << std::endl;
-
- std::pair<uint32_t, uint32_t> interval(nBegin, nIntervalEnd);
- workers[i] = ScanMidstateWorker(ctx, nBits, nInputTxTime, nValueIn, interval);
-
+ uint32_t nBegin = SearchInterval.first + nPart * i;
+ uint32_t nEnd = SearchInterval.first + nPart * (i + 1);
+ workers[i] = ScanMidstateWorker(kernel, nBits, nInputTxTime, nValueIn, nBegin, nEnd);
boost::function<void()> workerFnc = boost::bind(&ScanMidstateWorker::Do, &workers[i]);
group.create_thread(workerFnc);
}
group.join_all();
solutions.clear();
- for(int i = 0; i<4; i++)
+ for(size_t i = 0; i < nThreads; i++)
{
std::vector<std::pair<uint256, uint32_t> > ws = workers[i].GetSolutions();
solutions.insert(solutions.end(), ws.begin(), ws.end());
}
+ delete [] workers;
+
if (solutions.size() == 0)
{
// no solutions
}
// Scan given midstate for solution
-bool ScanMidstateBackward(SHA256_CTX &ctx, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, std::pair<uint32_t, uint32_t> &SearchInterval, std::pair<uint256, uint32_t> &solution)
+bool ScanContextBackward(SHA256_CTX &ctx, uint32_t nBits, uint32_t nInputTxTime, int64_t nValueIn, std::pair<uint32_t, uint32_t> &SearchInterval, std::pair<uint256, uint32_t> &solution)
{
CBigNum bnTargetPerCoinDay;
bnTargetPerCoinDay.SetCompact(nBits);
// Get maximum possible target to filter out the majority of obviously insufficient hashes
- CBigNum bnMaxTargetPerCoinDay = bnTargetPerCoinDay * CBigNum(nValueIn) * nStakeMaxAge / COIN / (24 * 60 * 60);
+ CBigNum bnMaxTargetPerCoinDay = bnTargetPerCoinDay * CBigNum(nValueIn) * nStakeMaxAge / COIN / nOneDay;
uint256 maxTarget = bnMaxTargetPerCoinDay.getuint256();
SHA256_CTX ctxCopy = ctx;
if (hashProofOfStake > maxTarget)
continue;
- CBigNum bnCoinDayWeight = CBigNum(nValueIn) * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeTx) / COIN / (24 * 60 * 60);
+ CBigNum bnCoinDayWeight = CBigNum(nValueIn) * GetWeight((int64_t)nInputTxTime, (int64_t)nTimeTx) / COIN / nOneDay;
CBigNum bnTargetProofOfStake = bnCoinDayWeight * bnTargetPerCoinDay;
if (bnTargetProofOfStake >= CBigNum(hashProofOfStake))