[<prev] [next>] [<thread-prev] [thread-next>] [day] [month] [year] [list]
Message-ID: <CA+EaD-ZOZjiTVhrf01EThKUqHT1CGYnE1wBMMP67BafrtbWU9g@mail.gmail.com>
Date: Mon, 14 Apr 2014 12:28:09 +0200
From: Katja Malvoni <kmalvoni@...il.com>
To: john-dev@...ts.openwall.com
Subject: Re: ZedBoard: bcrypt
ᐧ
On 13 April 2014 10:23, Solar Designer <solar@...nwall.com> wrote:
> > Redesigning PS-PL communication resulted in improvement. I have working
> > design with 70 bcrypt cores. Performance is 2162 c/s on 71 MHz
> frequency. 2
> > cycles are needed for one Blowfish round. Computation on host is
> overlapped
> > with computation on FPGA 5/6th of the time.
>
> Off-list, you had reported 67 cores at 71 MHz doing 1895 c/s when you
> had 4 cycles/round, or so I understood you (possibly incorrectly since
> this data was split across multiple e-mails).
That's correct.
> 70 cores would be doing
> something like 1895*70/67 = 1980 c/s. At 2 cycles/round, the speed
> should be almost twice that, but you're reporting "only" 2162 c/s. Why
> is that?
>
The problem is computation on host. Lines 649 to 681 in
https://github.com/kmalvoni/JohnTheRipper/blob/master/src/BF_std.c#L649take
0.016221s to compute while FPGA computation takes 0.011521s. Another
problem are data transfers to/from FPGA. Each transfer takes
around 0.006414s (these numbers are for cost 5). First all the data gets
ready and transferred to FPGA and after that computation is started. When
all 70 cores finish, data is transferred back to host.
I should change that so that cores start computing as soon as data is ready.
> It makes sense to start by running some more benchmarks, though: what
> speeds are you getting for 1 core (in FPGA), for the 2-cycle and 4-cycle
> versions? What speeds are you getting for $2a$08 (reduces relative
> cost of host's computation by a factor of 8 compared to $2a$05)?
>
I can't test speed for 1 core at the moment - I'm not able to ssh to the
Zed system, the error I get is connection refused. The test fails on my
ZedBoard.
For 4-cycle version, $2a$08 speed is 425 c/s and $2a$12 speed is 32 c/s
(tested on my ZedBoard, self test passes but not all instances return
correct results).
> > Code: git clone https://github.com/kmalvoni/JohnTheRipper -b master
>
> Can you also post a summary of what work is done on those two cycles?
>
cycle 0: compute tmp; initiate 2 S-box lookups
cycle 1: compute new R, L; initiate 2 S-box lookups; initiate P-box lookup
> Are you still getting correct results on my ZedBoard only, but not on
> yours (needing a lower core count for yours)? And not on Parallella
> board either? I suspect the limited power / core voltage drop issue.
> At 1.0 V core voltage, even a (peak) power usage of just 1.0 W means a
> current of 1.0 A, so if e.g. a PCB trace has impedance of 0.1 Ohm (I
> think this is too high, but not unrealistic) we might have a voltage
> drop of 0.1 V right there, and that's 10% of total. That's not even
> considering limitations of the voltage regulator. (I am assuming that
> there's no voltage sense going back from the FPGA to the voltage
> regulator. I think there is not.)
>
That's correct. I'm not getting correct results on my boards. I've tried
using 12V/8A PSU instead of 12V/3A on ZedBoard but that didn't help. I'm
also having problems with gcc crashes (every time it crashes on different
file):
"/usr/lib/gcc/arm-linux-gnueabihf/4.6/include/arm_neon.h:7348:1: internal
compiler error: Bus error
Please submit a full bug report,
with preprocessed source if appropriate.
See <file:///usr/share/doc/gcc-4.6/README.Bugs> for instructions.
The bug is not reproducible, so it is likely a hardware or OS problem."
> As discussed off-list, I think you should also proceed with ztex board.
> You mentioned that the documentation wasn't of sufficient help for you
> to get communication going, right? If so, suggest that you work
> primarily from working code examples, such as those for Bitcoin and
> Litecoin mining, as well as with the vendor's SDK examples.
>
Somehow I missed link to the EZ-USB FX2 Technical Reference Manual. I found
some answers there and I hope to find other answers in the code examples.
Katja
Content of type "text/html" skipped
Powered by blists - more mailing lists
Confused about mailing lists and their use?
Read about mailing lists on Wikipedia
and check out these
guidelines on proper formatting of your messages.
